opencl - clEnqueueBarrier 和 clFinish 之间有什么区别？

Question

OpenCL 1.1 规范说:

cl_int clEnqueueBarrier(cl_command_queue command_queue)

clEnqueueBarrier is a synchronization point that ensures that all queued commands in command_queue have finished execution before the next batch of commands can begin execution.

cl_int clFinish(cl_command_queue command_queue)

Blocks until all previously queued OpenCL commands in command_queue are issued to the associated device and have completed. clFinish does not return until all queued commands in command_queue have been processed and completed. clFinish is also a synchronization point.

应该对有序或无序执行执行一些操作，但我看不出有什么区别。如果我按顺序执行，是否需要它们？目前我正在做类似的事情:

...
for(...){
    clEnqueuNDRangeKernel(...);
    clFlush(command_queue);
    clFinish(command_queue);
}
...

在 Nvidia GPU 上。任何相关评论表示赞赏。

Answer 1

如果您正在编写无序队列作为确保依赖关系的一种方法，则需要对屏障进行排队。您还可以使用 cl_event 对象来确保命令队列上命令的正确排序。

如果您编写的代码在每次内核调用后调用 clFinish，那么使用 clEnqueueBarrier 不会对您的代码产生任何影响，因为您已经确保订购。

使用clEnqueueBarrier的要点是这样的情况:

clEnqueueNDRangeKernel(queue, kernel1);
clEnqueueBarrier(queue);
clEnqueueNDRangeKernel(queue, kernel2);

在这种情况下，kernel2 依赖于 kernel1 的结果。如果这个队列是无序的，那么如果没有屏障，kernel2可以在kernel1之前执行，从而导致不正确的行为。您可以通过以下方式实现相同的排序:

clEnqueueNDRangeKernel(queue, kernel1);
clFinish(queue);
clEnqueueNDRangeKernel(queue, kernel2);

因为clFinish将等待队列为空(所有内核/数据传输已完成)。但是，在这种情况下，clFinish 将等到 kernel1 完成，而 clEnqueueBarrier 应立即将控制权返回给应用程序(允许您将更多内核排入队列或执行其他有用的工作。

顺便说一句，我认为 clFinish 将隐式调用 clFlush，因此您不需要每次都调用它。