在 Haswell 和 Kabylake iGPU 上，OpenCL 全局 worskize 的解释不同

【问题标题】：OpenCL global worskize interpreted differently on Haswell & Kabylake iGPUs在 Haswell 和 Kabylake iGPU 上，OpenCL 全局 worskize 的解释不同
【发布时间】：2019-02-28 17:59:28
【问题描述】：

我们的内核被初始化为：

size_t localWorkSize[1] = {1};
size_t globalWorkSize[2] = {60, 80};

内核在图像文件上实现了典型的卷积。它在配备 Kabylake iGPU 的机器上运行良好，但在 Haswell 或 Bay Trail 机器上执行时，全局工作大小被解释为 {60, 60}，因此使用错误的 NDRange 执行。

在所有系统上，我们的平台都是 OpenCL 1.2 beignet 1.3

这是一个已知问题吗？或者全局工作大小是否存在硬件相关限制？ OpenCL 编程指南中似乎没有任何相关信息。

【问题讨论】：

听起来像一个你需要向 Beignet 开发人员提出的错误。

标签： opencl

【解决方案1】：

本地工作大小和全局工作大小必须具有相同的维度。请参阅 clEnqueueNDRangeKernel 的文档：

local_work_size  Points to an array of work_dim unsigned values
global_work_size  Points to an array of work_dim unsigned values

所以你的代码

size_t localWorkSize[1] = {1};
size_t globalWorkSize[2] = {60, 80};

如果您使用这些和 workdim == 2 将内核排入队列，驱动程序会将其读取为

size_t localWorkSize[2] = {1, something};
size_t globalWorkSize[2] = {60, 80};

localWorkSize 之上的堆栈中的任何东西。你需要做的

size_t localWorkSize[2] = {1, 1};

【讨论】：

做到了。非常感谢。