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 堆上动态分配内存。它可能会对内核的性能产生不利影响。