バッファの引数を設定するときのCL_INVALID_ARG_VALUE

Question

私はOpenCLプログラムを書いていますが、バッファをすべてゼロとして読み込んでいます。インテルSDKのトレースに目を通すと、バッファ引数を設定するときにCL_INVALID_ARG_VALUEが得られることがわかりました。 （スカラー引数を設定してもエラーは発生しません）

私はOpenCL C++バインディング（cl.hpp）を使用しています。

私のコードは長いので、テストプログラムで問題を再現しました。

cl::CommandQueue queue(context, devices.front()); 

cl::Buffer resultsBuf(context, CL_MEM_WRITE_ONLY | CL_MEM_HOST_READ_ONLY, sizeof(cl_short) * 2048); 
cl::Buffer inputBuf(context, CL_MEM_READ_ONLY | CL_MEM_HOST_WRITE_ONLY | CL_MEM_COPY_HOST_PTR, sizeof(cl_uchar) * 2048, input.data()); 

queue.enqueueWriteBuffer(inputBuf, CL_TRUE, 0, sizeof(cl_uchar) * 2048, input.data()); 

// Execution of the following two lines produces CL_INVALID_ARG_VALUE for both. 
err = kernel.setArg(0, resultsBuf); 
err = kernel.setArg(1, inputBuf); 

// Execution of the following line produces CL_INVALID_KERNEL_ARGS 
err = queue.enqueueTask(kernel); 

vector<cl_short> result(2048); 
err = queue.enqueueReadBuffer(resultsBuf, CL_TRUE, 0, sizeof(cl_short) * 2048, result.data()); 

とカーネルコード：

__kernel void myKernel(
    __local short* resultsBuf, 
    __local uchar* inputBuf 
) { 
    for (int i = 0; i < 2048; ++i) { 
     resultsBuf[i] = -3; 
    } 
} 

inputは、それがまだ何のために使用されていない、いくつかのテストデータで埋めvector<cl_uchar>(2048)です。私がこのテストケースから期待しているのは、値-3で満たされたバッファを読み戻すことだけです。

私は私がオンラインで見つけた他のサンプルと私のコードを比較しましたが、何も私には奇妙に飛び出しませんでした。私は様々な小さな調整（memフラグの変更など）を試みました。状況。

バッファーについて見落としたことはありますか？

（妙に私のテストプログラムは、いくつかのジャンクバイトでresultを埋めるのか？）

Answer 1

あなたがグローバルメモリを使用する必要があり、ホストとGPUの間に、バックデータを渡すために。これはホスト側でOKですが、カーネルでは__localという名前のメモリアドレス指定子を使用します。これは、名前が示すようにカーネル内でローカルに使用されることを意味します。 修正されたカーネルを使用する__global：

__kernel void myKernel(
    __global short* resultsBuf, 
    __global uchar* inputBuf 
) { 
    for (int i = 0; i < 2048; ++i) { 
     resultsBuf[i] = -3; 
    } 
}