0

我的内核调用有问题。我的代码如下所示：

std::vector<cl::Event> events;
...

queue.enqueueWriteBuffer(arrayFirst, CL_FALSE, 0, sizeOfArray, NULL, NULL, &arrayEvent);
events.push_back(arrayEvent);

queue.enqueueWriteBuffer(arraySecond, CL_FALSE, 0, sizeOfArraySecond, this->arraySecond, NULL, &arraySecondEvent);
events.push_back(arraySecondEvent);

kernel(cl::EnqueueArgs(queue, events, cl::NDRange(512), cl::NDRange(128)), arrayFirst, arraySecond);

当我运行它时，它不会进入内核代码，但是当我将“make_kernel”调用更改为：

kernel(cl::EnqueueArgs(queue, arraySecondEvent, cl::NDRange(512), cl::NDRange(128)), arrayFirst, arraySecond);

它进入内核，但我不确定“arrayFirst”的内存是否正确分配，我检查了 OpenCl 1.2 Wrapper 的文档，我发现调用应该如下所示：

cl::EnqueueArgs::EnqueueArgs(CommandQueue &queue,
const VECTOR_CLASS<Event> &events, NDRange offset, NDRange global,
NDRange local) //page 42

但是当我尝试传递事件向量的地址时，我得到编译错误，没有合适的方法具有以下参数..

错误：

error: no instance of constructor "cl::EnqueueArgs::EnqueueArgs" matches the argument list
            argument types are: (cl::CommandQueue, std::vector<cl::Event, std::allocator<cl::Event>> *, cl::NDRange, cl::NDRange)
              valueOfImageKernel(cl::EnqueueArgs(valueOfImageQueue, &events, cl::NDRange(512), cl::NDRange(128)),

有人知道我做错了什么吗？

4

2 回答 2

1

似乎您不需要的以下行给您带来了麻烦： queue.enqueueWriteBuffer(arrayFirst, CL_FALSE, 0, sizeOfArray, NULL, NULL, &arrayEvent); 当您实际上有要写的东西时，您需要调用写入缓冲区，而这里不是这种情况。

在完整的工作示例下方，在 PHI 上进行了测试（为了清楚起见，省略了错误处理）：

#include <iostream>
#include <vector>
#include <string>

#include <CL/cl.hpp>

int main()
{
    const char *kernel_str{
        "kernel void k1(global int *data1, global int *data2){"
        " int local_id = get_local_id(0);"
        " data1[local_id] = data2[local_id] + data2[local_id];"
        "}" };

    cl_int err = CL_SUCCESS;

    std::vector<cl::Platform> platforms;
    cl::Platform::get(&platforms);
    cl::Platform plat;
    for (auto &p : platforms)
    {
        std::vector<cl::Device> devices;
        p.getDevices(CL_DEVICE_TYPE_ACCELERATOR, &devices);
        if (!devices.empty())
        {
            plat = p;
            break;
        }
    }
    if (plat() == 0)
    {
        std::cout << "No OpenCL platform found.";
        return -1;
    }

    cl_context_properties properties[] =
    { CL_CONTEXT_PLATFORM, (cl_context_properties)(plat)(), 0 };
    cl::Context context(CL_DEVICE_TYPE_ACCELERATOR, properties);

    std::vector<cl::Device> devices = context.getInfo<CL_CONTEXT_DEVICES>();

    cl::Program::Sources source(1, std::make_pair(kernel_str, strlen(kernel_str)));
    cl::Program program = cl::Program(context, source);
    err = program.build(devices);

    cl::CommandQueue queue(context, devices[0], 0, &err);

    size_t sizeOfArray = 512, sizeOfArraySecond = 512;
    std::vector<int> varrayFirst(sizeOfArray);
    std::vector<int> varraySecond(sizeOfArraySecond);
    for (size_t x = 0; x < sizeOfArraySecond; ++x)
        varraySecond[x] = x;

    cl::Buffer arrayFirst(context, CL_MEM_WRITE_ONLY, sizeOfArray*sizeof(varrayFirst[0]));
    cl::Buffer arraySecond(context, CL_MEM_READ_ONLY, sizeOfArraySecond*sizeof(varraySecond[0]));

    cl::Event arraySecondEvent;

    std::vector<cl::Event> events;
    err = queue.enqueueWriteBuffer(arraySecond, CL_FALSE, 0, sizeOfArraySecond*sizeof(varraySecond[0]), &varraySecond[0], NULL, &arraySecondEvent);
    events.push_back(arraySecondEvent);

    cl::make_kernel<cl::Buffer&, cl::Buffer&> kernel(program, "k1");

    cl::Event ev = kernel(cl::EnqueueArgs(queue, events, cl::NDRange(512), cl::NDRange(128)), arrayFirst, arraySecond);

    std::vector<cl::Event> evs(1, ev);

    err = queue.enqueueReadBuffer(arrayFirst, CL_TRUE, 0, sizeOfArray*sizeof(varrayFirst[0]), &varrayFirst[0], &evs); // final blocking read

    std::cout << "Outputting first 10 values: " << std::endl;
    for (int x = 0; x < 10; ++x)
        std::cout << varrayFirst[x] << ", ";
    std::cout << std::endl;

    return 0;
}

输出：

Outputting first 10 values:
0, 2, 4, 6, 8, 10, 12, 14, 16, 18,
于 2015-11-01T21:10:25.507 回答
0

您的事件集合是正确的，内核调用也是正确的。现在的问题是……你确定内核被阻塞了吗？启动速度可能会很慢。

我会用event.finish()内核事件来检查它。如果您的应用程序死锁，那么这是事件的问题。

否则可能只是您的可执行文件在内核运行之前完成（因为它正在等待第一个缓冲区副本，这需要很长时间）。所以你不会看到任何日志，因为当内核 printfs 时，应用程序已经在清理了。

此外，如果您可以为事件添加所有代码，那么它可能对调试很有用。因为我们没有看到事件数组的完整生命周期。

于 2015-11-02T14:41:29.480 回答