CUDA ptxas警告(条目的堆栈大小)

Question

在编译CUDA代码时，我收到了以下我不理解的警告：

CUDACOMPILE : ptxas warning : Stack size for entry function
'_Z24gpu_kernel_get_3d_pointsiPK8RtmPointS1_PKfS3_P10RtmPoint3DPif' cannot be statically
determined.

内核原型是：

__global__ void gpu_kernel_get_3d_points(int count1, const RtmPoint *pPoints1,
const RtmPoint *pPoints2, const float *PL, const float *PR, RtmPoint3D *pPoints3D,
int *pGlobalCount, float bbox)

所有指针都是指向设备内存的指针。我不明白为什么编译器在确定堆栈大小时会有问题。内核中有一些局部变量，但并不多。有什么想法吗？这个警告重要吗？

Answer 1

当函数是递归的时，会出现此警告。除非您使用递归，否则Cuda会在执行之前尝试分配堆栈空间，这不是什么大问题。它的问题是堆栈大小是不可预测的。递归的深度不是一个已知值，因此堆栈将使用的内存是未知的。此警告并不重要，但如果您的数据超出了GPU堆栈，则必须手动增加堆栈大小。

Answer 2

您的内核似乎正在使用malloc()或new运算符在GPU堆上动态分配内存。它可能会对内核的性能产生不利影响。