OpenCL 根据缓冲区的大小返回 INVALID_KERNEL_ARGS

Question

我在使用 OpenCL 时遇到了一个奇怪的问题，我正在为使用大内存缓冲区作为参数的内核调用 clEnqueueNDRangeKernel。对于小于 16384 字节的缓冲区，一切正常。如果我将缓冲区大小增加到超过该值，则会返回 INVALID_KERNEL_ARGS 错误。据我了解，此错误表示未设置参数。将参数设置为无效大小或不适合内存的内容会触发不同的错误。

有什么想法吗？

更新

@mfa 的回答让我再次查看了设备规格。看起来一个 128*128 的浮点数组正好是 64KB，这是卡的常量内存的大小。全局内存要大得多，因此内核参数使用 __global 而不是 __constant 可以解决此问题。

但我仍然感到困惑：如何调用 const memory every 的内存不足参数？在我看来，当我创建缓冲区时，尚不知道它是用作常量还是全局......有没有办法获得更有用的错误消息？

Answer 1

在您的设备上查询“CL_DEVICE_MAX_PARAMETER_SIZE”，我敢打赌它会是 16384。对于我的英特尔 CPU，这个值是 4096。

规范定义的最小值是：

• opencl 1.0 - 256 字节
• opencl 1.1 - 1024 字节
• opencl 1.2 - 1024 字节
• opencl 2.0 - 1024 字节

Read more on the clGetDeviceInfo page.

---

Re: 缓冲区和内存不足错误

当您创建缓冲区时，就知道它可以连接到哪些设备。 clCreateBuffer 获取缓冲区将关联的 cl_context，并且先前对 clCreateContext 的调用获取了与新上下文关联的设备列表。但缓冲区不是你的问题。

__constant 是您最初的问题。您的设备不允许您使用总计超过 4352 字节的常量参数，而您试图传递 65536 字节。全局内存没有这么低的限制（默认情况下，GPU 占总内存的 50%，CPU 占 25%）。在您尝试将内核参数设置为太大的值之前，不会知道/触发内存不足错误。

问题发生在低级别，当常量内存要共享（或复制——这取决于实现）以供所有工作组使用时。计算单元中仅保留有限数量的内存用于此用途。在芯片设计者不得不削减 ALU 内核或其他类型的存储器以允许更大的恒定存储器大小之前，只能有这么多专用于此目的的晶体管。即使在 opencl 2.0 中，最小值仍然只有 1024 字节。