0

当我使用 cuda-gdb 为特定输入运行它时，我编写了一个由于设备非法地址而面临内核启动失败的代码。我使用 cuda-memcheck 运行它并得到 Invalid write of size 4 错误。代码太大，所以我将在这里解释这个场景。

我有一个主内核，我将一个用作堆栈的数组指针传递给它。我有一个从主内核调用并使用堆栈的设备函数。

__device__ void find(int v , int* p, int* pv,int n, int* d_stackContents)
{

    int d_stackTop;
    d_stackTop = -1;
    *pv = p[v];
    if(*pv == -1){
            *pv = v;

    }
    else{
    cuPrintf("Stack top is %d\n",d_stackTop);
    d_stackTop = d_stackTop + 1;
    d_stackContents[d_stackTop] = v;
    cuPrintf("Stack top is %d\n",d_stackTop);
    while(*pv != -1){
            d_stackTop = d_stackTop + 1;
            d_stackContents[d_stackTop] = *pv;
            cuPrintf("Stack top is %d\n",d_stackTop);
            *pv = p[*pv];
    }

}

错误发生在 d_stackContents[d_stackTop] = *pv;

我在主内核中调用设备函数如下：

查找（v[idx]，p，&pv，n，d_stackContents）；

其中 idx = threadIdx.x + blockDim.x * blockIdx.x 我已将 pv 声明为 int pv;

此外，d_stackContents 数组使用 cudaMalloc 在 main 中分配，并作为参数传递给主内核

4

1 回答 1

4

除非您在单个块中使用单个线程调用内核，否则这将不起作用。否则，所有线程都会在彼此的堆栈上乱涂乱画。如果您随后取消引用存储在损坏堆栈上的指针，它将立即解释您的代码为何试图访问非法地址。

您需要为每个线程使用单独的堆栈，或者在全局内存中使用具有堆栈指针的单个堆栈，该堆栈指针仅通过原子操作进行操作。

于 2012-10-26T10:07:38.070 回答