将包含指向另一个结构的指针的结构传递给 CUDA 中的内核

我有两个结构

struct collapsed {
    char **seq;
    int num;
};


struct data {
    collapsed *x;
    int num;
    int numblocks;
    int *blocksizes;
    float *regmult;
    float *learnmult;
};

我将它传递给我的内核：

__global__ void KERNEL(data* X,...){
    ...
    collapsed x = X->x[0]; // GIVES CUDA_EXPECTION_1:Lane Illegal Address
}

data X;
//init X
data *X_dev;
cudaMalloc((data **) & X_dev, sizeof(data));
cudaMemcpy(X_dev, &X, sizeof(data), cudaMemcpyHostToDevice);
KERNEL<<<...>>>(X_dev,...);

这段代码给出了CUDA_EXPECTION_1：通道非法地址在内核代码中。有什么问题或者正确的方法是什么？任何想法？

您正在取消引用设备上的主机指针。X是一个有效的设备指针。

但是当你复制X结构到设备，您复制了x随之而来的是，它包含一个主机指针。当您取消引用该指针时：

collapsed x = X->x[0];
                 ^ this is dereferencing the x pointer

设备代码抛出错误。

给出了更多细节here https://stackoverflow.com/questions/15431365/cudamemcpy-segmentation-fault/15435592#15435592以及如何修复它的说明。