cuda, OpenGL互操作性:cudaGraphicsGLRegisterBuffer的cudaErrorMemor
cuda, OpenGL interoperability: cudaErrorMemoryAllocation error on cudaGraphicsGLRegisterBuffer
我在使用cudaGraphicsGLRegisterBuffer()
时遇到随机cuda内存分配错误。我有一个相当大的OpenGL PBO对象,它与CUDA共享。创建PBO对象的方法如下:
GLuint buffer;
glGenBuffers(1, &buffer);
glBindBuffer(GL_PIXEL_UNPACK_BUFFER, buffer);
glBufferData(target, rows * cols * 4, NULL, GL_DYNAMIC_COPY);
glUnmapBuffer(_target);
glBindBuffer(_target, 0);
这个物体相当大。宽高均为5000。然而,它在我的GPU上分配得很好。现在,我在OpenGL和CUDA之间分享如下。我有一个简单的类来管理它,如下所示:
class CudaPBOGraphicsResource
{
public:
CudaPBOGraphicsResource(GLuint pbo_id);
~CudaPBOGraphicsResource();
inline cudaGraphicsResource_t resource() const { return _cgr; }
private:
cudaGraphicsResource_t _cgr;
};
CudaPBOGraphicsResource::CudaPBOGraphicsResource(GLuint pbo_id)
{
checkCudaErrors(cudaGraphicsGLRegisterBuffer(&_cgr, pbo_id,
cudaGraphicsRegisterFlagsNone));
checkCudaErrors(cudaGraphicsMapResources(1, &_cgr, 0));
}
CudaPBOGraphicsResource::~CudaPBOGraphicsResource()
{
if (_cgr) {
checkCudaErrors(cudaGraphicsUnmapResources(1, &_cgr, 0));
}
}
现在我做OpenGL和CUDA互操作性如下:
{
CudaPBOGraphicsResource input_cpgr(pbo_id);
uchar4 * input_ptr = 0;
size_t num_bytes;
checkCudaErrors(cudaGraphicsResourceGetMappedPointer((void
**)&input_ptr, &num_bytes,
input_cpgr.resource()));
call_my_kernel(input_ptr);
}
对于我的输入运行了一段时间,但过了一段时间它崩溃了:
CUDA error code=2(cudaErrorMemoryAllocation)
"cudaGraphicsGLRegisterBuffer(&_cgr, pbo_id,
cudaGraphicsRegisterFlagsNone)"
Segmentation fault
我不知道为什么有内存分配,因为我认为这是共享的。我在内核调用之后添加了cudaDeviceSynchronize()
,但错误仍然存在。我的call_my_kernel()
函数现在几乎什么都不做,所以没有其他CUDA调用可以引发此错误!
我在linux上使用Cuda 7和K4000 Quadro卡。
编辑我将驱动程序更新到最新的346.72版本,错误仍然发生。它也不依赖于内核调用。只是调用cudaGraphicsGLRegisterBuffer()
似乎会泄漏GPU上的内存。在程序运行时运行nvidia-smi显示内存稳步上升。
好了,我找到了我的难题的答案,我希望它能帮助到其他使用CUDA-OGL的人。
问题是我在打电话:
checkCudaErrors(cudaGraphicsGLRegisterBuffer(&_cgr, pbo_id,
cudaGraphicsRegisterFlagsNone));
每次。这实际上只需要调用一次,然后我只需要在_cgr对象上调用map/unmap。
相关文章:
- 没有找到相关文章