2011-11-15 31 views
1

我一直在尝试调试我的代码,因为我知道内核中出现了问题,我一直试图弄清楚具体是什么。如果我尝试步入内核似乎在内核函数完全步骤,并将最终导致对戒烟的错误:CUDA-GDB在内核中崩溃

Single stepping until exit from function dyld_stub_cudaSetupArgument, 
which has no line number information. 
[Launch of CUDA Kernel 0 (incrementArrayOnDevice<<<(3,1,1),(4,1,1)>>>) on 
Device 0] 
[Termination of CUDA Kernel 0 (incrementArrayOnDevice<<<(3,1,1), 
(4,1,1)>>>) on Device 0] 
[Launch of CUDA Kernel 1 (fillinBoth<<<(40,1,1),(1,1,1)>>>) on Device 0] 
[Termination of CUDA Kernel 1 (fillinBoth<<<(40,1,1),(1,1,1)>>>) on Device 0] 
add (below=0x124400, newtip=0x124430, newfork=0x125ac0) at test.cu:1223 

如果我尝试在内核打破我的整个计算机崩溃,我有重新启动它。

我认为我调用内核的方式肯定有问题,但我不知道是什么。

的代码比较长,所以我只包括它的一个摘录:

__global__ void fillinOne(seqptr qset, long max) { 
    int i, j; 
    aas aa; 
    int idx = blockIdx.x; 
    __shared__ long qs[3]; 
    if(idx < max) 
    { 
     memcpy(qs, qset[idx], sizeof(long[3])); 
     for (i = 0; i <= 1; i++) 
     { 
      for (aa = ala; (long)aa <= (long)stop; aa = (aas)((long)aa + 1)) 
      { 
       if (((1L << ((long)aa)) & qs[i]) != 0) 
       { 
        for (j = i + 1; j <= 2; j++) 
         qs[j] |= cudaTranslate[(long)aa - (long)ala][j - i]; 
       } 
      } 
     } 
    } 
} 

//Kernel for left!= NULL and rt != NULL 

void fillin(node *p, node *left, node *rt) 
{ 

    cudaError_t err = cudaGetLastError(); 
    size_t stepsize = chars * sizeof(long); 
    size_t sitesize = chars * sizeof(sitearray); 
    //int i, j; 
    if (left == NULL) 
    { 
     //copy rt->numsteps into p->numsteps--doesn't actually require CUDA, because no computation to do 
     memcpy(p->numsteps, rt->numsteps, stepsize); 
     checkCUDAError("memcpy"); 

     //allocate siteset (array of sitearrays) on device 
     seqptr qsites; //as in array of qs's 
     cudaMalloc((void **) &qsites, sitesize); 
     checkCUDAError("malloc"); 

     //copy rt->siteset into device array (equivalent to memcpy(qs, rs) but for whole array) 
     cudaMemcpy(qsites, rt->siteset, sitesize, cudaMemcpyHostToDevice); 
     checkCUDAError("memcpy"); 

     //do loop in device 
     int block_size = 1; //each site operated on independently 
     int n_blocks = chars; 
     fillinOne <<< n_blocks, block_size>>> (qsites, chars); 
     cudaThreadSynchronize(); 

     //put qset in p->siteset--equivalent to memcpy(p->siteset[m], qs) 
     cudaMemcpy(p->siteset, qsites, sitesize, cudaMemcpyDeviceToHost); 
     checkCUDAError("memcpy"); 

     //Cleanup 
     cudaFree(qsites); 
} 

如果任何人有任何想法都请resond!提前致谢!

回答

1

我想你有一个卡配置。当你正在调试一个cuda内核,并且你打破它时,你有效地使显示驱动程序暂停。这会导致你认为是崩溃。如果你只想用一个图形卡来使用cuda-gdb,你必须在命令行模式下使用它(不要启动X或者按下X的ctrl-alt-fn)。

如果您有两张卡片,您必须在未运行显示器的卡片上运行代码。使用cudaSelectDevice(n)。

+0

感谢您的回应!这是有道理的,但你怎么在命令行模式中使用它?我认为这就是我一直在做的事情。我一直从命令行运行cuda-gdb a.out。我应该怎么做呢? – Izri

+0

您可能只是在桌面环境中打开一个终端。如果按下ctrl-alt-f1,则在桌面环境之外进入命令行(我认为它被称为控制台)。为了回报你,我只想做ctrl-alt-f7。 – jmsu