4

我正在尝试使用 clang/LLVM 3.2 版为“nbody”示例程序的内核（nbody_kernel.cu）生成 PTX 代码。nbody CUDA 程序在 Nvidia 的 SDK 中可用。

我指的是https://github.com/jholewinski/llvm-ptx-samples项目。

以下是我的命令，

clang++ -O4 -S -I/usr/local/cuda/include -emit-llvm -target nvptx64 nbody_kernel.cu -o nbody_kernel.ll

选择 -O3 -loop-unroll -unroll-allow-partial nbody_kernel.ll -o nbody_kernel.ll

llc nbody_kernel.ll -o nbody_kernel.ptx

执行最后一个命令（llc）后，我执行了一个 UNREACHABLE ！以下堆栈跟踪错误

UNREACHABLE executed!
0  libLLVM-3.2svn.so 0x00000033eb79fadf
1  libLLVM-3.2svn.so 0x00000033eb7a01d6
2  libpthread.so.0   0x0000003825a0f500
3  libc.so.6         0x0000003824e328a5 gsignal + 53
4  libc.so.6         0x0000003824e34085 abort + 373
5  libLLVM-3.2svn.so 0x00000033eb788320 llvm::llvm_unreachable_internal(char const*, char const*, unsigned int) + 336
6  libLLVM-3.2svn.so 0x00000033eb43dc37
7  libLLVM-3.2svn.so 0x00000033eb4411a0
8  libLLVM-3.2svn.so 0x00000033eb4422a5
9  libLLVM-3.2svn.so 0x00000033eb210d76 llvm::FPPassManager::doInitialization(llvm::Module&) + 54
10 libLLVM-3.2svn.so 0x00000033eb217ec7 llvm::FPPassManager::runOnModule(llvm::Module&) + 23
11 libLLVM-3.2svn.so 0x00000033eb217ac5 llvm::MPPassManager::runOnModule(llvm::Module&) + 389
12 libLLVM-3.2svn.so 0x00000033eb217c1b llvm::PassManagerImpl::run(llvm::Module&) + 107
13 llc               0x000000000040d157 main + 5415
14 libc.so.6         0x0000003824e1ecdd __libc_start_main + 253
15 llc               0x0000000000409a29
Stack dump:
0.  Program arguments: llc nbody_kernel.ll -o nbody_kernel.ptx 
1.  Running pass 'Function Pass Manager' on module 'nbody_kernel.ll'.
Aborted (core dumped)

我用 __builtin_ptx_read_tid_x() 等替换了全局索引，例如 threadIdx.x。生成 LLVM IR（即 .ll）没有问题。尝试使用 llc 从 IR 生成 PTX 时弹出错误。

关于这里可能发生的事情的任何指示？

4

0 回答 0