4

我正在为 OpenCL 使用 C++ 绑定，并且在将我的一个内核排入队列时，我得到了一个cl::Errorfor .-38 (CL_INVALID_MEM_OBJECT)clEnqueueNDRangeKernel

此错误未列为clEnqueueNDRangeKernel的可能错误之一。通知功能给我以下输出：

在 GeForce GTX 560（设备 0）上执行 CL_COMMAND_NDRANGE_KERNEL 时出现 CL_INVALID_MEM_OBJECT 错误。

我还没有找到一个展示这种行为的最小例子。

调用此函数时会导致这种错误的原因是什么？

使用谷歌我只找到了这个答案。它指出，setKernelArg如果已更新，我需要重新附加一个内存对象。（至少这是我对它的解释，并且没有详细解释更新的含义。）但是，我怀疑这是正确的，尽管我无法证明这一点。也许你知道这方面的官方消息？

更新

经过一些测试，我发现向__global const float*内核添加参数会引入错误。clSetKernelArg我还发现，如果我在另一个（已经存在的）参数之后使用这个新参数，那么每次都会发生错误。如果我在设置另一个参数之前这样做，它会每秒钟工作一次。当然这不是一个选项，因为我需要能够随时设置参数。

更新 2

我注意到，通过调试单步执行代码会“重新引入”我在另一个参数之前设置新参数的版本中的错误。（这意味着错误每次都会再次发生。）

这可能是某种竞争条件吗？我自己不使用多线程，但在调试器中有 7 个线程可能来自 Qt 或 OpenCL。

最小的工作示例

#include <CL/cl.hpp>
#include <vector>
#include <iostream>

#define STRINGIFY(x) #x

std::string kernel = STRINGIFY(
__kernel void apply(__global const float *param1)
{
}
);


template <class T>
cl::Buffer genBuffer(const cl::Context &context, const std::vector<T> &data,
                        cl_mem_flags flags = CL_MEM_READ_ONLY)
{
        return cl::Buffer(context, flags | CL_MEM_COPY_HOST_PTR,
                                data.size() * sizeof(data[0]),
                                const_cast<T*>(&data[0]));
}

int main()
{
        std::vector<cl::Platform> clPlatforms;
        cl::Platform::get(&clPlatforms);
        cl_context_properties props[] = {
                CL_CONTEXT_PLATFORM, (cl_context_properties)clPlatforms[0](),
                0};
        cl::Context clContext = cl::Context(CL_DEVICE_TYPE_GPU, props);
        std::vector<cl::Device> devices = clContext.getInfo<CL_CONTEXT_DEVICES>();
        if(devices.empty())
        {
                std::cerr << "No devices found!\n";
                exit(-1);
        }
        cl::Device clDevice = devices[0];
        cl::CommandQueue clQueue = cl::CommandQueue(clContext, clDevice, 0, 0);
        cl::Program program(clContext, cl::Program::Sources(1,
                                std::make_pair(kernel.c_str(), kernel.size())));
        program.build(devices);
        cl::Kernel kernel(program, "apply");

        //this introduces the error
        kernel.setArg(0, genBuffer(clContext, std::vector<cl_float>(100));
        //the error is triggered here
        clQueue.enqueueNDRangeKernel(kernel, cl::NullRange, cl::NDRange(100), cl::NullRange);
}
4

1 回答 1

2

问题是我假设内核将保留缓冲区，我将缓冲区附加到内核。然后我破坏了所有导致 OpenCL 实现删除缓冲区的引用cl::Buffer/对象。Memory

通过 valgrind 运行我的程序后，我注意到一个对象的访问内存在子例程opencl.so中早些时候被释放。cl::~Buffer阅读clSetKernelArg我注意到：

用户不能依赖内核对象来保留指定为内核参数值的对象。

不确定的行为显然是驱动程序访问释放的内存区域从而进入 UB 土地的结果。

更正的 MWE

#include <CL/cl.hpp>
#include <vector>
#include <iostream>

#define STRINGIFY(x) #x

std::string kernel = STRINGIFY(
__kernel void apply(__global const float *param1)
{
}
);


template <class T>
cl::Buffer genBuffer(const cl::Context &context, const std::vector<T> &data,
                        cl_mem_flags flags = CL_MEM_READ_ONLY)
{
        return cl::Buffer(context, flags | CL_MEM_COPY_HOST_PTR,
                                data.size() * sizeof(data[0]),
                                const_cast<T*>(&data[0]));
}

int main()
{
        std::vector<cl::Platform> clPlatforms;
        cl::Platform::get(&clPlatforms);
        cl_context_properties props[] = {
                CL_CONTEXT_PLATFORM, (cl_context_properties)clPlatforms[0](),
                0};
        cl::Context clContext = cl::Context(CL_DEVICE_TYPE_GPU, props);
        std::vector<cl::Device> devices = clContext.getInfo<CL_CONTEXT_DEVICES>();
        if(devices.empty())
        {
                std::cerr << "No devices found!\n";
                exit(-1);
        }
        cl::Device clDevice = devices[0];
        cl::CommandQueue clQueue = cl::CommandQueue(clContext, clDevice, 0, 0);
        cl::Program program(clContext, cl::Program::Sources(1,
                                std::make_pair(kernel.c_str(), kernel.size())));
        program.build(devices);
        cl::Kernel kernel(program, "apply");

        //this version triggers the error
        //kernel.setArg(0, genBuffer(clContext, std::vector<cl_float>(100));

        //This is how it is done correctly
        cl::Buffer buffer = genBuffer(clContext, std::vector<cl_float>(100));
        kernel.setArg(0, buffer);

        clQueue.enqueueNDRangeKernel(kernel, cl::NullRange, cl::NDRange(100), cl::NullRange);
}
于 2013-09-20T18:51:42.827 回答