正如标题所暗示的那样，我正在寻找如何有效地交换两个 OpenCL 缓冲区。我的内核使用两个全局缓冲区，一个作为输入，一个作为输出。但是，我在 for 循环中使用相同的 NDRange 调用我的内核，每次设置内核参数、将内核排入队列并交换缓冲区，因为之前的输出缓冲区将是下一次迭代的输入缓冲区种子。
交换这两个缓冲区的适当方法是什么？我想将缓冲区复制回主机到一个已经 malloc 的数组并使用clEnqueueWriteBuffer() 和clEnqueueReadBuffer() 将其复制到下一个输入缓冲区是一种低效的方法。否则我只是使用一个临时的cl_mem 变量来进行交换。
【问题讨论】：
您不需要，只需使用clSetKernelArg 设置正确的内核参数，然后再将您的内核排入队列（使用clEnqueueNDRangeKernel）。缓冲区将保留在设备上，不会将任何内容复制回主机。
当然，在这种情况下，您的缓冲区必须使用CL_MEM_READ_WRITE 创建。
【讨论】：
setArg 之前使用std::swap(bufferA, bufferB);，以避免对偶数和奇数迭代使用单独的代码。
如上一个答案：不，您根本不需要交换缓冲区。
但是，我不同意建议的答案。函数clSetKernelArg() 不是线程安全的，并且不设计为在操作循环中调用。
正确的解决方案是创建 2 个使用相同程序和源创建的内核。这种方法更符合 OpenCL 编程理念“一个内核完成一项任务”。拥有许多具有相同代码但参数不同的内核是要走的路。
第一个内核将有：
kernel1 = clCreateKernel(program, "mykernel", NULL);
clSetKernelArg(kernel1, 0, &buff1);
clSetKernelArg(kernel1, 1, &buff2);
另一个是：
kernel2 = clCreateKernel(program, "mykernel", NULL);
clSetKernelArg(kernel2, 0, &buff2);
clSetKernelArg(kernel2, 1, &buff1);
这样，您无需在每次迭代时停止执行。你可以简单地运行：
for(int it=0; it<iter; it++){
clEnqueueNDRangeKernel(it%2 ? kernel1 : kernel2, ....);
}
clFinish(command);
这种方法肯定会比更改内核参数更好，更高效，API 调用更少。此外，在某些系统上，clSetKernelArgs() 可能是阻塞调用，因为 API 实现不佳。所以最好尽量避开它们。
【讨论】：
clSetKernelArgs() 上阻塞