レジスタ値のOpenCLの使用がプログラムにクラッシュする

Question

熱力学計算のためのOpenCLカーネルの作成が終了し、本当に奇妙なバグが観測されました。 私のカーネルは、次のようになります。

__kernel void energy(... float3 dest, int nlocal, ...){ 
    int i = get_global_id(0); 
    float3 ev = {0.0f, 0.0f, 0.0f}; 
    for(...){ 
     //some thermo calculations, adding values to evx and evy 
     ev.x +=...; 
     ev.y +=...; 
    } 

    //Then I want to save the result in dest[i]. 
    //Program exits at next two line 
    dest[i].x = ev.x; 
    dest[i].y = ev.y; 

私は「マップされていないメモリ」とセグメンテーション違反エラーが発生します。 printfを使用して値を出力しようとしたときに同じエラーが発生します。プログラムが値を読み取ることができないようです。しかし、コンパイラの最適化のために） 別のフロートレジスタ値を使用すると、同じエラーが発生します。しかし、私は

dest[i].x = i/nlocal*3.1f 
dest[i].y = ...; 

すべてが期待通りに起こっているこのような何か（ev.xまたはev.yの不使用）への最後の行を変更し、私はエラーを取得していない場合。

これはあまりにも動作します：

int i = ... 
float3 = {0.0f, ...} 
dest[i].x = ev.x; 

しかし、それはもはや不可能です何とか実際の計算の後。

プログラムは、Nvidia K40m、Keplerアーキテクチャ上で動作しています。

Answer 1

これはあなたのコード内の疑わしい：あなたは、neighにポインタの配列を渡し、その後、ポインタを取得し、それを使用しているよう

kernel(... __global int* neigh 
    __global int* neighs = neigh+i; 
    ... 
    int j = neighs[k*n]; 
    ... 

は思えます。 ポインタを渡すと、CLでポインタが許可されず、GPUメモリからアドレス指定されているため、クラッシュします。

あなたのベクトルは単に適切に計算されていない、サイズがなければならないことも可能である：（覚えて、彼らは浮いている、とするfloat3あなたは、彼らがあるべきよりも小さいバッファを作成しました

res, nneigh = GLOBAL_SIZE 
neighs = max(nneigh[])*n 
x = max(neighs[]) 

も可能これは要素あたり32ビットと128ビットを使用します）。 CL API呼び出しは、要素ではなくバイトで定義されます（sizeof()を使用する必要があります）。

Answer 2

私は答えを見つけ、上記のコードが動作しています。カーネルのパラメータを変更して理解を深め、ここにコードを投稿したときに間違いを修正しました。 P