cudaMemcpy分段错误

Question

cudaMemcpy分段错误

我已经被这个错误困扰了很长一段时间所以我决定在这里发布它。

调用cudaMemcpy时发生此分段错误：

CurrentGrid->cdata[i] = new float[size];cudaMemcpy(CurrentGrid->cdata[i], Grid_dev->cdata[i], size*sizeof(float),\
                cudaMemcpyDeviceToHost);

CurrentGrid并且Grid_dev分别指向grid主机和设备上的类对象，在此上下文中i = 0。类成员cdata是一个浮点类型指针数组。为了调试，这cudaMemcpy调用之前对的，我打印出来的每个元素的值Grid_Dev->cdata[i]，地址CurrentGrid->cdata[i]和Grid_dev->cdata[i]和的价值size，这一切看起来不错。但它仍然以“分段故障（核心转储）”结束，这是唯一的错误消息。cuda-memcheck只给出了“进程没有成功终止”。我目前无法使用cuda-gdb。关于去哪儿的任何建议？

更新：现在看来我已经通过cudaMalloc解决了这个问题，设备上的另一个浮点指针A和cudaMemcpy的Grid_dev-> cdata [i]的值为A，然后是cudaMemcpy A来主机。所以上面写的代码段变成：

float * A;cudaMalloc((void**)&A, sizeof(float));......cudaMemcpy(&A, &(Grid_dev->cdata[i]), sizeof(float *), cudaMemcpyDeviceToHost);    CurrentGrid->cdata[i] = new float[size];cudaMemcpy(CurrentGrid->cdata[i], A, size*sizeof(float), cudaMemcpyDeviceToHost);

我之所以这样做是因为valgrind突然出现了“8号无效读取”，我认为这是指的Grid_dev->cdata[i]。我用gdb再次检查它，打印出Grid_dev->cdata[i]NULL值。所以我想即使在这个cudaMemcpy调用中也无法直接取消引用设备指针。但为什么 ？根据这个帖子底部的评论，我们应该能够在cudaMemcpy函数中取消引用设备指针。

另外，我不知道cudaMalloc和cudaMemcpy如何工作的基本机制，但我认为cudaMalloc是一个指针，比如A，我们实际上指定这个指针指向设备上的某个地址。通过cudaMemcpy Grid_dev->cdata[i]到A，如上面的修改代码，我们重新分配指针A指向数组。那么，当它是cudaMalloced时，我们不会失去A指向的先前地址的轨道吗？这会导致内存泄漏吗？如果是的话，我应该如何妥善解决这种情况？谢谢！

作为参考，我将完整函数的代码放在下面发生此错误的代码中。

Answer 1

我相信我知道问题是什么，但要确认它，看看你用来Grid_dev在设备上设置类的代码会很有用。当要在设备上使用类或其他数据结构时，该类中有指针指向内存中的其他对象或缓冲区（可能在设备内存中，对于将在设备上使用的类），使这个顶级类在设备上可用的过程变得更加复杂。假设我有一个这样的类：class myclass{   int myval;   int *myptr;   }我可以在主机上实例化上面的类，然后malloc是一个数组，int并指定指针myptr，一切都会好的。要使此类仅在设备和设备上可用，过程可能类似。我可以：cudaMalloc指向将保持的设备内存的指针 myclass（可选）myclass使用cudaMemcpy将主机上的实例化对象复制到步骤1中的设备指针在设备上，使用malloc或new分配设备存储myptr如果我从不想访问myptr在主机上分配的存储空间，则上面的顺序很好。但如果我确实希望从主机可以看到该存储，我需要一个不同的序列：cudaMalloc是一个指向设备内存的指针myclass，让我们调用它mydevobj（可选）使用cudaMemcpy myclass将主机上的实例化对象复制到mydevobj步骤1中的设备指针在主机上创建一个单独的int指针，让我们调用它 myhostptrcudaMalloc int存储在设备上myhostptrcudaMemcpy的指针值的myhostptr从主机到设备的指针&(mydevobj->myptr)之后，您可以cudaMemcpy通过嵌入指针指向myptr分配（通过cudaMalloc）的区域指向的数据myhostptr请注意，在步骤5中，因为我正在获取此指针位置的地址，所以此cudaMemcpy操作仅需要mydevobj主机上的指针，该指针在cudaMemcpy操作中有效（仅限）。myint然后将正确设置设备指针的值以执行您尝试执行的操作。如果你想要cudaMemcpy数据进出myint主机，你可以myhostptr在任何cudaMemcpy调用中使用指针，而不是 mydevobj->myptr。如果我们尝试使用mydevobj->myptr，则需要解除引用mydevobj，然后使用它来检索存储在其中的指针，myptr然后使用该指针作为复制到/来自位置。这在主机代码中是不可接受的。如果你试图这样做，你会得到一个seg错误。（注意，通过类比，我mydevobj就像你Grid_dev，我myptr就像你一样cdata）