私はかなり長い間このエラーに悩まされてきたので、ここに投稿することにしました。
このセグメンテーション違反は、cudaMemcpyが呼び出されたときに発生しました。
CurrentGrid->cdata[i] = new float[size];
cudaMemcpy(CurrentGrid->cdata[i], Grid_dev->cdata[i], size*sizeof(float),\
cudaMemcpyDeviceToHost);
CurrentGridおよびは、それぞれホストとデバイス上Grid_devのクラスオブジェクトへのポインタであり、このコンテキストではi=0です。gridクラスメンバーcdataはfloat型のポインタ配列です。デバッグのために、このcudaMemcpy呼び出しの直前に、の各要素の値Grid_Dev->cdata[i]、アドレス、CurrentGrid->cdata[i]およびGrid_dev->cdata[i]の値を出力sizeしました。これらはすべて良好に見えます。ただし、それでも「セグメンテーション違反（コアダンプ）」が発生します。これが唯一のエラーメッセージです。cuda-memcheckは「プロセスが正常に終了しませんでした」のみを提供しました。現在、cuda-gdbを使用できません。どこに行くべきかについて何か提案はありますか？
更新：デバイス上の別のfloatポインターAをcudaMallocし、Grid_dev-> cdata [i]の値をAにcudaMemcpyし、次にcudaMemcpyAをホストすることでこの問題を解決したようです。したがって、上記のコードのセグメントは次のようになります。
float * A;
cudaMalloc((void**)&A, sizeof(float));
...
...
cudaMemcpy(&A, &(Grid_dev->cdata[i]), sizeof(float *), cudaMemcpyDeviceToHost);
CurrentGrid->cdata[i] = new float[size];
cudaMemcpy(CurrentGrid->cdata[i], A, size*sizeof(float), cudaMemcpyDeviceToHost);
これを行ったのは、valgrindが「サイズ8の無効な読み取り」をポップアップしたためGrid_dev->cdata[i]です。もう一度gdbでチェックし、Grid_dev->cdata[i]NULLの値を出力しました。したがって、このcudaMemcpy呼び出しでも、デバイスポインターを直接逆参照することはできないと思います。しかし、なぜ ？このスレッドの下部にあるコメントによると、cudaMemcpy関数でデバイスポインタを逆参照できるはずです。
また、cudaMallocとcudaMemcpyがどのように機能するかについての根本的なメカニズムはわかりませんが、cudaMallocによってポインター、たとえばここでAと考えると、実際にはこのポインターをデバイス上の特定のアドレスを指すように割り当てます。そして、上記の変更されたコードのようにcudaMemcpyGrid_dev->cdata[i]をAに変更することにより、配列を指すようにポインターAを再割り当てします。それなら、cudaMallocedのときにAが指していた前のアドレスを見失ってはいけませんか？これにより、メモリリークなどが発生する可能性がありますか？はいの場合、この状況を適切に回避するにはどうすればよいですか？ありがとう！
参考までに、このエラーが発生した完全な関数のコードを以下に示します。
どうもありがとう！
__global__ void Print(grid *, int);
__global__ void Printcell(grid *, int);
void CopyDataToHost(param_t p, grid * CurrentGrid, grid * Grid_dev){
cudaMemcpy(CurrentGrid, Grid_dev, sizeof(grid), cudaMemcpyDeviceToHost);
#if DEBUG_DEV
cudaCheckErrors("cudaMemcpy1 error");
#endif
printf("\nBefore copy cell data\n");
Print<<<1,1>>>(Grid_dev, 0); //Print out some Grid_dev information for
cudaDeviceSynchronize(); //debug
int NumberOfBaryonFields = CurrentGrid->ReturnNumberOfBaryonFields();
int size = CurrentGrid->ReturnSize();
int vsize = CurrentGrid->ReturnVSize();
CurrentGrid->FieldType = NULL;
CurrentGrid->FieldType = new int[NumberOfBaryonFields];
printf("CurrentGrid size is %d\n", size);
for( int i = 0; i < p.NumberOfFields; i++){
CurrentGrid->cdata[i] = NULL;
CurrentGrid->vdata[i] = NULL;
CurrentGrid->cdata[i] = new float[size];
CurrentGrid->vdata[i] = new float[vsize];
Printcell<<<1,1>>>(Grid_dev, i);//Print out element value of Grid_dev->cdata[i]
cudaDeviceSynchronize();
cudaMemcpy(CurrentGrid->cdata[i], Grid_dev->cdata[i], size*sizeof(float),\
cudaMemcpyDeviceToHost); //where error occurs
#if DEBUG_DEV
cudaCheckErrors("cudaMemcpy2 error");
#endif
printf("\nAfter copy cell data\n");
Print<<<1,1>>>(Grid_dev, i);
cudaDeviceSynchronize();
cudaMemcpy(CurrentGrid->vdata[i], Grid_dev->vdata[i], vsize*sizeof(float),\
cudaMemcpyDeviceToHost);
#if DEBUG_DEV
cudaCheckErrors("cudaMemcpy3 error");
#endif
}
cudaMemcpy(CurrentGrid->FieldType, Grid_dev->FieldType,\
NumberOfBaryonFields*sizeof(int), cudaMemcpyDeviceToHost);
#if DEBUG_DEV
cudaCheckErrors("cudaMemcpy4 error");
#endif
}
編集：これは、メモリリークが発生した場所を追跡しようとしているvalgrindからの情報です。
==19340== Warning: set address range perms: large range [0x800000000, 0xd00000000) (noaccess)
==19340== Warning: set address range perms: large range [0x200000000, 0x400000000) (noaccess)
==19340== Invalid read of size 8
==19340== at 0x402C79: CopyDataToHost(param_t, grid*, grid*) (CheckDevice.cu:48)
==19340== by 0x403646: CheckDevice(param_t, grid*, grid*) (CheckDevice.cu:186)
==19340== by 0x40A6CD: main (Transport.cu:81)
==19340== Address 0x2003000c0 is not stack'd, malloc'd or (recently) free'd
==19340==
==19340==
==19340== Process terminating with default action of signal 11 (SIGSEGV)
==19340== Bad permissions for mapped region at address 0x2003000C0
==19340== at 0x402C79: CopyDataToHost(param_t, grid*, grid*) (CheckDevice.cu:48)
==19340== by 0x403646: CheckDevice(param_t, grid*, grid*) (CheckDevice.cu:186)
==19340== by 0x40A6CD: main (Transport.cu:81)
==19340==
==19340== HEAP SUMMARY:
==19340== in use at exit: 2,611,365 bytes in 5,017 blocks
==19340== total heap usage: 5,879 allocs, 862 frees, 4,332,278 bytes allocated
==19340==
==19340== LEAK SUMMARY:
==19340== definitely lost: 0 bytes in 0 blocks
==19340== indirectly lost: 0 bytes in 0 blocks
==19340== possibly lost: 37,416 bytes in 274 blocks
==19340== still reachable: 2,573,949 bytes in 4,743 blocks
==19340== suppressed: 0 bytes in 0 blocks
==19340== Rerun with --leak-check=full to see details of leaked memory
==19340==
==19340== For counts of detected and suppressed errors, rerun with: -v
==19340== ERROR SUMMARY: 1 errors from 1 contexts (suppressed: 2 from 2)