如何在cuda中使用指向指針的指針

Question

我在使用cuda中的指針指針時遇到問題。 代碼片段如下。

char** d_ppcPtr, *d_pcPtr, *h_pcPtr; 
cudaMalloc(&d_ppcPtr, sizeof(char*) * 10); 

h_pcPtr = (char*)malloc(sizeof(char) * 100); 
for(int i = 0; i < 10; i ++) 
{ 
     cudaMalloc(&d_pcPtr, sizeof(char) * 100); 
     cudaMemset(d_pcPtr, 1, sizeof(char) * 100); 
     cudaMemcpy(&d_ppcPtr[i], &d_pcPtr, sizeof(char*), cudaMemcpyHostToDevice); 
     cudaMemcpy(h_pcPtr, d_ppcPtr[i], sizeof(char) * 100, cudaMemcpyDeviceToHost); //crash here 
     cudaFree(d_ppcPtr[i]); //crash also here 
} 
cudaFree(d_ppcPtr); 

我該如何修復以上兩次崩潰？ 在此先感謝。

Answer 1

以下修改將「修理」你的代碼（整個例子，包括主機和設備驗證）：

$ cat t583.cu 
#include <stdio.h> 

__global__ void testkernel(char **data, unsigned n){ 
    for (int i = 0; i < 100; i++) if (data[n][i] != 1) printf("kernel error\n"); 
} 

int main(){ 
    char** d_ppcPtr, *d_pcPtr, *h_pcPtr; 
    cudaMalloc(&d_ppcPtr, sizeof(char*) * 10); 

    h_pcPtr = (char*)malloc(sizeof(char) * 100); 
    for(int i = 0; i < 10; i ++) 
    { 
     cudaMalloc(&d_pcPtr, sizeof(char) * 100); 
     cudaMemset(d_pcPtr, 1, sizeof(char) * 100); 
     cudaMemcpy(&d_ppcPtr[i], &d_pcPtr, sizeof(char*), cudaMemcpyHostToDevice); 
     memset(h_pcPtr, 0, sizeof(char)*100); 
     testkernel<<<1,1>>>(d_ppcPtr, i); 
     cudaMemcpy(h_pcPtr, d_pcPtr, sizeof(char) * 100, cudaMemcpyDeviceToHost); 
     cudaFree(d_pcPtr); 
     for (int i = 0; i < 100; i++) if (h_pcPtr[i] != 1) printf("Error!"); 
    } 
    cudaFree(d_ppcPtr); 
} 
$ nvcc -arch=sm_20 -o t583 t583.cu 
$ cuda-memcheck ./t583 
========= CUDA-MEMCHECK 
========= ERROR SUMMARY: 0 errors 

注意，在概念上，有我的代碼和你之間沒有區別，因爲指針您正試圖在位置d_ppcPtr[i]中使用（並正在崩潰，因爲它位於設備上）已經包含在主機上的d_pcPtr中。