OpenCL 本地工作本地内存答案

【问题标题】：OpenCL local work local memoryOpenCL 本地工作本地内存
【发布时间】：2017-02-22 00:51:50
【问题描述】：

我的本地内存有问题，特别是保存值。这是加载到程序的文件中的所有内核。

__kernel void initData(int bitSample, int transmitorCount ,int bufferLen, __global short *sequence)
{

   __local int constData[2];
   __local short mask[(15 * 1023)];

   constData[0] = bitSample;
   constData[1] = bufferLen;

   for (int i = 0; i < transmitorCount * 1023; i++) {
       mask[i] = sequence[i];
   }

   printf("startPlace: %u \t Resutl: %i = %i\n", transmitorCount, constData[0], constData[1]);
   barrier(CLK_LOCAL_MEM_FENCE);
}

__kernel void correlation(__global short *inBuffer, __global int *outBuffer, __local int *constData)
{

   uint startPlace = get_global_id(0);
   uint sequence = get_global_id(1);

   outBuffer[0] = inBuffer[0];

   printf("startPlace: %i Sequence: %i\t Resutl: %i = %i\n", startPlace, sequence, constData[0], constData[1]);
}

程序正在运行，本地内存已保存。初始化调用是：

    size_t globaId[3] = { 1, 0, 0 };
    ret = clEnqueueNDRangeKernel(gpuControlData->cmdQueue, gpuControlData->initKernel, 1, NULL, globaId, NULL, 0, NULL, NULL);

但是当我启动相关内核时，保存的值仅在第一次启动时在本地。第二次和下一次开始是错误的数据。我尝试在每次启动之前初始化本地内存，但它不起作用。创建队列的命令是：

while(true){
    ret = clSetKernelArg(gpuControlData->corelationKernel, 0, sizeof(cl_mem), (void *) &inBuffer);
    ret = clSetKernelArg(gpuControlData->corelationKernel, 1, sizeof(cl_mem), (void *)&outBuffer);
    ret = clSetKernelArg(gpuControlData->corelationKernel, 2, sizeof(cl_int) * 2, NULL);

    size_t globaId[3] = { 3, 2, 0 };
    ret = clEnqueueNDRangeKernel(gpuControlData->maskCorrelQueue, gpuControlData->corelationKernel, 2, NULL, globaId, NULL, 0, NULL, NULL);
}

一次运行的结果是：

startPlace: 2    Resutl: 100 = 150000
startPlace: 0 Sequence: 0        Resutl: 100 = 150000
startPlace: 1 Sequence: 0        Resutl: 100 = 150000
startPlace: 2 Sequence: 0        Resutl: 100 = 150000
startPlace: 0 Sequence: 1        Resutl: 100 = 150000
startPlace: 1 Sequence: 1        Resutl: 100 = 150000
startPlace: 2 Sequence: 1        Resutl: 100 = 150000
oneIteration
startPlace: 0 Sequence: 0        Resutl: 1056562655 = 1058300571
startPlace: 1 Sequence: 0        Resutl: 1056562655 = 1058300571
startPlace: 2 Sequence: 0        Resutl: 1056562655 = 1058300571
startPlace: 0 Sequence: 1        Resutl: 1056562655 = 1058300571
startPlace: 1 Sequence: 1        Resutl: 1056562655 = 1058300571
startPlace: 2 Sequence: 1        Resutl: 1056562655 = 1058300571

所以我需要一些帮助或示例如何使用相同的本地数据循环运行内核？

感谢您的帮助。

【问题讨论】：

如果我没记错的话，本地内存中的数据不会在波前之间保留。而且我想我不知道你想做什么。
我要比较数据。一个数据是定义的并且是静态的，第二个数据是变化的。所以我想将常量数据保存到本地内存以便更快地访问。每次迭代我都必须尝试 inBuffer 。
@StepanRydlo 工作组中的所有线程都可以将数据从全局内存收集到本地内存，并且它们同时进行。所以你可以让单个内核同时进行初始化和关联。在开始关联之前，您需要与屏障命令同步。
但是如果我在一个内核中同时做这两件事，每个内核都会在每次启动时从全局内存复制到本地内存。而且它不会更快。我想在程序启动时将数据保存到局部变量。而这个数据我不想改变。是否可以创建？
我创建了新测试，本地值保存在 126 次迭代中，工作组大小我有 128。

标签： c memory opencl local

【解决方案1】：

本地内存本质上是“临时”内存，在内核结束后不会保留其内容。您通常在内核中对其进行初始化以用作手动缓存。你不能用本地内存做你想做的事情。

您可以使用 const memory 来尝试加快内存访问速度。 const memory 可能会使用设备的实际缓存，并且具有与本地相当的速度。唯一的问题是没有办法保证（或知道）内存是否被缓存——它最终可能只是全局的。你需要尝试一下。

【讨论】：

我想问一下如何创建常量全局缓冲区。我没有找到任何例子。我创建缓冲区 CL_MEM_READ_ONLY 并在内核中使用参数 __constant short *mask。但是快没有什么不同。 Sp 我如何创建常量缓冲区？
你怎么知道常量内存是瓶颈？你检查了一切吗？
在任何 CL 桌面设备中，只要常量内存小于 16KB 就可以了。
@StepanRydlo 常量内存是您从主机传递给内核的任何非指针参数。或声明为“__constant”的指针。没有专门针对常量内存的函数。