このcudaカーネル内のローカル変数？

Question

最近私はcudaを試していますが、次のcudaカーネルに問題がありました。

__global__ void addKernel(float *c, const float *a, const float *b, int nsize) 
{ 
    int blockID = blockIdx.x + blockIdx.y*gridDim.x; 
    int i = blockID*blockDim.x+threadIdx.x; 
    if (i < nsize){ 
     c[i] = a[i] + b[i]; 
    } 
    float k = c[i]; 
}` 

このカーネルは、単純なベクターの追加に使用されます。最後の文float k = c[i];がなければ正常に動作します。しかし、私はこのステートメントを追加した後、コードを実行するとunspecified launch failureエラーが表示されます。誰にでもこのカーネルの何が問題なのか教えてくれますか？

Answer 1

実際のデバイスメモリ割り当てと、このカーネル（ブロック、スレッドなど）の起動方法を含めて、完全なコードを表示してください。しかし、あなたは仕事の大きさ（すなわち、ベクトルの長さ）をカバーするのに十分なスレッド以上を起動している可能性が非常に高いです。これはかなり一般的なCUDAの習慣です。

あなたはそれがあなたのカーネルでスレッド・チェックを含めるのが通例だが、それを行う：

if (i < nsize){ 

実際に索引付けに慣れるi値は、すなわちベクトル長内（有効であることを確認するために、 ）。

しかし、あなたは（if文のすなわち外体）外スレッドチェックをこの文を含むことによって、物事が壊れました：いずれかのために、

float k = c[i]; 

今は中iを計算しましたあなたのカーネルでは、その場所のcベクトルへのインデックス付けを試行します。でも、iがnsizeより大きい場合は、おそらくcベクトルの長さです。

この文は、ベクトル割り当てのcの範囲外にインデックスを設定している可能性が最も高いです。恐らく、hereのような方法を使って、もう少しデバッグして確認できます。