CUDA读取变量崩溃求助：光线追踪器移植问题排查

正在将《Ray Tracing in One Weekend》中的光线追踪器移植到CUDA平台，在适配可命中对象列表的碰撞检测逻辑时遇到问题。具体碰撞检测代码如下：

__device__ bool hittable_list_hit(const ray& r, double t_min, double t_max, hit_record& rec, uint8_t* data, int& offset) {
    hit_record temp_rec = { point3(0,0,0), point3(0,0,0), 0.0, false };
    bool hit_anything = false;
    auto closest_so_far = t_max;

    //printf("%f", temp_rec.t); <-- UNCOMMENTING THIS LINE MAKES CUDA CRASH

    uint8_t size = data[offset++];

    for (uint8_t i = 0; i < size; i++) {
        if (top_level_hit(r, t_min, closest_so_far, temp_rec, data, offset)) {
            hit_anything = true;
            //closest_so_far = temp_rec.t;
            //rec = temp_rec;
        }
    }

    return hit_anything;
}

取消注释读取temp_rec.t的printf语句后，程序输出黑屏，疑似CUDA崩溃；注释该行则能正常显示教程中的天空背景。该函数在核函数启动后嵌套4层，为何读取普通变量会引发此类问题？

• 线程资源耗尽：CUDA单线程的栈空间和寄存器数量有限，4层嵌套调用已经占用了大量资源。添加printf会引入额外的寄存器使用（比如格式化字符串处理、临时存储），直接触发栈溢出或寄存器不足，导致线程崩溃。看似是读取temp_rec.t的问题，实际是printf带来的额外资源开销压垮了线程。
• 隐藏的非法内存访问被暴露：注释printf时，编译器可能优化掉了temp_rec的部分操作，掩盖了data指针或offset变量的非法访问问题（比如offset在嵌套调用中被错误修改，导致data[offset++]越界）。添加printf后，编译器无法跳过这些操作，非法内存访问被触发，引发崩溃。
• CUDA printf的同步冲突：CUDA的printf依赖线程束同步，且输出缓冲区有大小限制。在深层嵌套函数中调用printf，可能与现有代码的执行流产生同步冲突，引发死锁或缓冲区溢出，最终导致核函数崩溃。

内容的提问来源于stack exchange，提问作者Yxuer