在內核函數中使用cuPrint打印字符串向量的元素

Question

我試圖打印使用cuPrint函數作爲內核函數參數傳遞的字符串向量的元素。

內核

__global__ void testKernel(string wordList[10000]) 
{ 
    //access thread id 
    const unsigned int bid = blockIdx.x; 
    const unsigned int tid = threadIdx.x; 
    const unsigned int index = bid * blockDim.x + tid; 


    cuPrintf("wordList[%d]: %s \n", index, wordList[index]); 
} 

從主要功能設置執行參數代碼的代碼和啓動內核

//Allocate device memory for word list 
    string* d_wordList; 
    cudaMalloc((void**)&d_wordList, sizeof(string)*number_of_words); 

    //Copy word list from host to device 
    cudaMemcpy(d_wordList, wordList, sizeof(string)*number_of_words, cudaMemcpyHostToDevice); 

    //Setup execution parameters 
    int n_blocks = (number_of_words + 255)/256; 
    int threads_per_block = 256; 

    dim3 grid(n_blocks, 1, 1); 
    dim3 threads(threads_per_block, 1, 1); 

    cudaPrintfInit(); 
    testKernel<<<grid, threads>>>(d_wordList); 
    cudaDeviceSynchronize(); 
    cudaPrintfDisplay(stdout,true); 
    cudaPrintfEnd(); 

我收到錯誤： 「錯誤44錯誤：調用主機函數（「std :: basic_string，std :: allocator> ::〜basic_string」）從全球函數（「testKernel」）不被允許D：... \ kernel.cu 44 1 CUDA_BF_lar ge_word_list 「

我錯過了什麼？ 在此先感謝。

Answer 1

通常，您不能在CUDA設備代碼中使用C++庫中的函數（包括<string>）。使用數組char來代替您的字符串。

Here是將「字符串」操作爲以空字符結尾的C風格數組並將它們傳遞給內核的示例。

Answer 2

我修改了代碼，並使用了一串字符串的字符串。

內核的更新版本：

__global__ void testKernel(char* d_wordList) 
{ 
    //access thread id 
    const unsigned int bid = blockIdx.x; 
    const unsigned int tid = threadIdx.x; 
    const unsigned int index = bid * blockDim.x + tid; 


    //cuPrintf("Hello World from kernel! \n"); 


      cuPrintf("!! %c%c%c%c%c%c%c%c%c%c \n" , d_wordList[index * 20 + 0], 
                d_wordList[index * 20 + 1], 
                d_wordList[index * 20 + 2], 
                d_wordList[index * 20 + 3], 
                d_wordList[index * 20 + 4], 
                d_wordList[index * 20 + 5], 
                d_wordList[index * 20 + 6], 
                d_wordList[index * 20 + 7], 
                d_wordList[index * 20 + 8], 
                d_wordList[index * 20 + 9]); 


} 

我也想知道是否有從字符數組打印的話更簡單的方法。 （低音我需要打印，以後每個內核函數使用一個單詞）。

從主功能的代碼是：

  const int text_length = 20; 

     char (*wordList)[text_length] = new char[10000][text_length]; 
     char *dev_wordList; 

     for(int i=0; i<number_of_words; i++) 
     { 
      file>>wordList[i]; 
      cout<<wordList[i]<<endl; 
     } 

     cudaMalloc((void**)&dev_wordList, 20*number_of_words*sizeof(char)); 
     cudaMemcpy(dev_wordList, &(wordList[0][0]), 20 * number_of_words * sizeof(char), cudaMemcpyHostToDevice); 

     char (*resultWordList)[text_length] = new char[10000][text_length]; 

     cudaMemcpy(resultWordList, dev_wordList, 20 * number_of_words * sizeof(char), cudaMemcpyDeviceToHost); 

     for(int i=0; i<number_of_words; i++) 
      cout<<resultWordList[i]<<endl; 

     //Setup execution parameters 
     int n_blocks = (number_of_words + 255)/256; 
     int threads_per_block = 256; 


     dim3 grid(n_blocks, 1, 1); 
     dim3 threads(threads_per_block, 1, 1); 

cudaPrintfInit(); 
     testKernel<<<grid, threads>>>(dev_wordList); 
     cudaDeviceSynchronize(); 
     cudaPrintfDisplay(stdout,true); 
     cudaPrintfEnd(); 

如果使用更小的值這樣的塊/線程的數目：

dim3 grid(20, 1, 1); 
dim3 threads(100, 1, 1); 

內核發射是正確的，它顯示一個字每個線程。但我需要這個過程10000字。我錯過了什麼？