Opencl atomic_add() 函数返回错误值

Question

我在 OpenCL 1.2 中遇到问题。 看，我在内核中有一个数组为__global，组大小为1000。 问题是atomic_add()函数不能正常工作。

我的内核代码是：

__kernel void kernelfunction(__global uint32_t* buffer){

buffer[3] = 100;

atomic_add(&buffer[3], 1);

...

}

如果我创建 1000 个线程，我预计 buffer[3] 的值将是 1100，对吗？ 但是程序的行为是未定义的。 有时是 1100，有时是 1064，有时是 1093，然后......

我尝试过的：

我还启用了如下的 opencl 扩展：

#pragma OPENCL EXTENSION cl_khr_global_int32_base_atomics : enable

但问题仍然存在。 在另一个项目中，我将创建一个简单的 opencl 项目，atomic_add 工作正常，我检查了几乎整个项目配置，但我不知道问题出在哪里。

你能帮帮我吗？ 谢谢

Answer 1

如果没有原子，对同一元素进行简单访问时会出现竞争条件，更糟糕的是，所有数据都可能已按计算单元缓存，并且在内核结束之前不会更新。

buffer[3] = 100;

这是未定义的行为。结果甚至可能是 101；

如果没有同步命令，即使是同一个本地组中的线程也不能有真正的数据。

初始化应该由主机进行，因为 gpu 并发运行线程。不是连续的，不包括原子。或者，您为其自己的组进行初始化（从其他组中不可见）并在之后添加一个barrier(CLK_GLOBAL_MEM_FENCE)，以便同一组中的其他线程可以正确看到它。