cuda-gdb与推力崩溃（CUDA版本5.5） [英] cuda-gdb crashes with thrust (CUDA release 5.5)

问题描述

我有以下琐碎的thrust :: gather程序（直接从thrust :: gather文档获取）

  #include < thrust / gather.h> 
 #include< thrust / device_vector.h> 
 int main（void）
 {
 
 //用1表示偶数索引;具有0 
的奇数索引int值[10] = {1,0,1,0,1,0,1,0,1,0}; 
 thrust :: device_vector< int> d_values（values，values + 10）; 
 //将所有偶数索引收集到范围的前半部分
 //和奇数索引到范围的后一半
 int map [10] = {0，2，4， 6，8，1，3，5，7，9}; 
 thrust :: device_vector< int> d_map（map，map + 10）; 
 thrust :: device_vector< int> d_output（10）; 
 thrust :: gather（d_map.begin（），d_map.end（），
 d_values.begin（），
 d_output.begin（））; 
 // d_output现在为{1,1,1,1,1,0,0,0,0,0} 0 
 return 0; 
} 
  

我用

编译

  / usr / local / cuda / bin / nvcc -ccbin g ++ -I ../../ common / inc -m64 -g -G -gencode arch = compute_30，code = sm_30 -o thrustGather.o -c thrustGather.cu 
 
 / usr / local / cuda / bin / nvcc -ccbin g ++ -m64 -g -G -o pushGather thrustGather.o 
  

接下来我尝试在将它附加到cuda-gdb后运行这个简单的程序：

 > cuda-gdb ./thrustGather 
 NVIDIA（R）CUDA调试器
 5.5发行版
部分版权所有（C）2007-2013 NVIDIA公司
 GNU gdb（GDB）7.2 
版权所有（C）2010自由软件基金会，
许可GPLv3 +：GNU GPL第3版或更高版本< http：//gnu.org/licenses /gpl.html> 
这是免费软件：您可以随意更改和重新分配。 
在法律允许的范围内，没有任何保证。有关详细信息，请键入显示复制
和显示保修。 
此GDB配置为x86_64-unknown-linux-gnu。 
有关错误报告说明，请参阅：
< http：//www.gnu.org/software/gdb/bugs/> ... 
从/ usr / local读取符号/cuda-5.5/samples/0_Simple/thrustGatherRjm/thrustGather...done。 
（cuda-gdb）run 
启动程序：/usr/local/cuda-5.5/samples/0_Simple/thrustGatherRjm/thrustGather 
 [启用libthread_db的线程调试] 
 [New线程0x7ffff7272700（LWP 50318）] 
 [上下文在设备0上创建上下文0x78d790] 
 [CUDA内核0的启动（memset32_aligned1D <<<（1,1,1），（128,1 ，（1）>>>）在装置0上] 
 [启动CUDA内核1（memset32_aligned1D <<<（1,1,1），（128,1,1）> >）on Device 0] 
 [在设备0上启动CUDA内核2（memset32_aligned1D <<<（1,1,1），（128,1,1）> 
 [在设备0上启动CUDA内核3（memset32_aligned1D <<<（1,1,1），（128,1,1）>>）] 
 [ CUDA内核4（设备0上的memset32_aligned1D <<<（1,1,1），（128,1,1）>>）] 
 [启动CUDA内核5（memset32_aligned1D < ;在设备0上的<（1,1,1），（128,1,1）>>）
 [CUDA内核6的启动（memset32_aligned1D<< ，（128,1,1），（128,1,1），在设备0上] 
 [CUDA内核7的启动（memset32_aligned1D << （41帧）：
 cuda-gdb [0x4394e1] 
）
 
 
 
 
 $ b /lib64/libc.so.6[0x3d96635a90] 
 cuda-gdb [0x5b038b] 
 cuda-gdb [0x55aae8] 
 cuda-gdb [0x55ed65] 
 cuda-gdb [ 0x55fc51] 
 cuda-gdb [0x55ec22] 
 cuda-gdb [0x5609fe] 
 cuda-gdb [0x5607bd] 
 cuda-gdb [0x560c36] 
 cuda-gdb [ 0x4f7e44] 
 cuda-gdb [0x4f8038] 
 cuda-gdb [0x4fde3c] 
 cuda-gdb [0x5c9f66] 
 cuda-gdb [0x429c3c] 
 cuda-gdb [ 0x5ca4e5] 
 cuda-gdb [0x5cab5e] 
 cuda-gdb [0x4296e6] 
 cuda-gdb [0x479366] 
 cuda-gdb [0x53addd] 
 cuda-gdb [ 0x5129c0] 
 cuda-gdb [0x5134fd] 
 cuda-gdb [0x51369d] 
 cuda-gdb [0x5091e7] 
 cuda-gdb [0x40f65d] 
 cuda-gdb [ 0x522f54] 
 cuda-gdb [0x523a20] 
 cuda-gdb [0x5ff9aa] 
 cuda-gdb [0x522fb9] 
 cuda-gdb [0x521b81] 
 cuda-gdb [ 0x522b1e] 
 cuda-gdb [0x51d0cb] 
 cuda-gdb [0x4ae816] 
 cuda-gdb [0x406429] 
 cuda-gdb [0x51d0cb] 
 cuda-gdb [ 0x406b76] 
 cuda-gdb [0x51d0cb] 
 cuda-gdb [0x406204] 
 cuda-gdb [0x4061d6] 
 /lib64/libc.so.6（__ libc_start_main + 0xf5） 0x3d96621b75] 
 cuda-gdb [0x4060e9] 
 [CUDA内核7的终止（memset32_aligned1D <<<（1,1,1），（128,1,1）> ）on Device 0] 
 [在设备0上终止CUDA内核6（memset32_aligned1D <<<（1,1,1），（128,1,1）> $ b [在设备0上终止CUDA内核5（memset32_aligned1D <<<（1,1,1），（128,1,1）>>] 
 [CUDA内核终止4（设备0上的memset32_aligned1D <<<（1,1,1），（128,1,1）>>）
 [CUDA内核3的终止（memset32_aligned1D < ;设备0上的（1,1,1），（128,1,1）>>）
 [CUDA内核2的终止（memset32_aligned1D <<设备0] 
的终止[CUDA内核1的终止（memset 32​​_aligned1D <<<<（1,1,1），（128,1， 1）>>>>>>>>>>> ;）on Device 0] 
  

注意cuda-gdb本身是segfaults。我也为

• 推送了对应的示例：thrust :: gather_if


• thrust :: scatter
• 
  
• thrust :: count


• thrust :: inclusive_scan


• thrust :: sort_by_key


• thrust :: reduce_by_key

其中只有最后三个（inclusive_scan，sort_by_key，reduce_by_key） ，不要崩溃cuda-gdb）。

这必须是推力和/或cuda-gdb的最新版本（5.5）的问题，因为我已经运行

这里有一些关于我的设置的信息：

 > cat / proc / driver / nvidia / version 
 NVRM版本：NVIDIA UNIX x86_64内核模块319.21 Sat May 11 23:51:00 PDT 2013 
 GCC版本：gcc版本4.8.1 20130603（Red Hat 4.8。 1-1）（GCC）
 
> cat / proc / version 
 Linux版本3.9.9-302.fc19.x86_64（[e-mail]）（gcc版本4.8.1 20130603（Red Hat 4.8.1-1）（GCC） ）＃1 SMP Sat Jul 6 13:41:07 UTC 2013 
 
> gcc --version 
 gcc（GCC）4.8.1 20130603（Red Hat 4.8.1-1）
版权所有（C）2013自由软件基金会，
这是免费软件;请参阅复制条件的来源。有NO 
保修;甚至不适用于适销性或特定用途的适用性。 
 
> lspci | grep NVIDIA 
 05：00.0 3D控制器NVIDIA公司GK104 [GeForce GTX 690]（rev a1）
 05：00.1音频设备：NVIDIA公司GK104 HDMI音频控制器（rev a1）
 06： 00.0 VGA兼容控制器：NVIDIA公司GK104 [GeForce GTX 690]（rev a1）
 06：00.1音频设备：NVIDIA公司GK104 HDMI音频控制器（rev a1）
  pre> 
 
解决方案
如talonmies指出的，问题是Thrust库在使用调试构建时不能正确运行。在我的应用程序中，我有一个相当复杂的.cu文件包含几个我自己的CUDA内核，以及多个推力调用。如果我用-g -G调试标志编译这个文件并在cuda-gdb中运行，它会崩溃，使我无法调试我的内核。 
 
 
 
由于我不在乎调试Thrust调用本身（只有我的内核），我的解决方案涉及将所有我的推力调用在另一个文件thrustWrappers.cu和编译这个文件无需调试。然后在我的主要.cu文件中，我将替换的推力与相关联的包装函数（在thrustWrappers中定义）。例如，
  thrust :: reduce（...）
  
成为
  thrust :: reduce_wrapper b $ b  
然后我将两个生成的目标文件链接在一起。
 
I have the following trivial thrust::gather program (taken directly from the thrust::gather documentation)
#include <thrust/gather.h>
#include <thrust/device_vector.h>
int main(void)
{

    // mark even indices with a 1; odd indices with a 0
    int values[10] = {1, 0, 1, 0, 1, 0, 1, 0, 1, 0};
    thrust::device_vector<int> d_values(values, values + 10);
    // gather all even indices into the first half of the range
    // and odd indices to the last half of the range
    int map[10] = {0, 2, 4, 6, 8, 1, 3, 5, 7, 9};
    thrust::device_vector<int> d_map(map, map + 10);
    thrust::device_vector<int> d_output(10);
    thrust::gather(d_map.begin(), d_map.end(),
            d_values.begin(),
            d_output.begin());
    // d_output is now {1, 1, 1, 1, 1, 0, 0, 0, 0, 0}
    return 0;
}
I compile this with 
/usr/local/cuda/bin/nvcc -ccbin g++ -I../../common/inc  -m64 -g -G -gencode arch=compute_30,code=sm_30 -o thrustGather.o -c thrustGather.cu

/usr/local/cuda/bin/nvcc -ccbin g++ -m64 -g -G -o thrustGather thrustGather.o
Next I try running this simple program after first attaching it to cuda-gdb:
>cuda-gdb ./thrustGather
NVIDIA (R) CUDA Debugger
5.5 release
Portions Copyright (C) 2007-2013 NVIDIA Corporation
GNU gdb (GDB) 7.2
Copyright (C) 2010 Free Software Foundation, Inc.
License GPLv3+: GNU GPL version 3 or later <http://gnu.org/licenses/gpl.html>
This is free software: you are free to change and redistribute it.
There is NO WARRANTY, to the extent permitted by law.  Type "show copying"
and "show warranty" for details.
This GDB was configured as "x86_64-unknown-linux-gnu".
For bug reporting instructions, please see:
<http://www.gnu.org/software/gdb/bugs/>...
Reading symbols from /usr/local/cuda-5.5/samples/0_Simple/thrustGatherRjm/thrustGather...done.
(cuda-gdb) run
Starting program: /usr/local/cuda-5.5/samples/0_Simple/thrustGatherRjm/thrustGather 
[Thread debugging using libthread_db enabled]
[New Thread 0x7ffff7272700 (LWP 50318)]
[Context Create of context 0x78d790 on Device 0]
[Launch of CUDA Kernel 0 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Launch of CUDA Kernel 1 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Launch of CUDA Kernel 2 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Launch of CUDA Kernel 3 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Launch of CUDA Kernel 4 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Launch of CUDA Kernel 5 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Launch of CUDA Kernel 6 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Launch of CUDA Kernel 7 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
Error: received unexpected signal: Segmentation fault
BACKTRACE (41 frames):
cuda-gdb[0x4394e1]
/lib64/libc.so.6[0x3d96635a90]
cuda-gdb[0x5b038b]
cuda-gdb[0x55aae8]
cuda-gdb[0x55ed65]
cuda-gdb[0x55fc51]
cuda-gdb[0x55ec22]
cuda-gdb[0x5609fe]
cuda-gdb[0x5607bd]
cuda-gdb[0x560c36]
cuda-gdb[0x4f7e44]
cuda-gdb[0x4f8038]
cuda-gdb[0x4fde3c]
cuda-gdb[0x5c9f66]
cuda-gdb[0x429c3c]
cuda-gdb[0x5ca4e5]
cuda-gdb[0x5cab5e]
cuda-gdb[0x4296e6]
cuda-gdb[0x479366]
cuda-gdb[0x53addd]
cuda-gdb[0x5129c0]
cuda-gdb[0x5134fd]
cuda-gdb[0x51369d]
cuda-gdb[0x5091e7]
cuda-gdb[0x40f65d]
cuda-gdb[0x522f54]
cuda-gdb[0x523a20]
cuda-gdb[0x5ff9aa]
cuda-gdb[0x522fb9]
cuda-gdb[0x521b81]
cuda-gdb[0x522b1e]
cuda-gdb[0x51d0cb]
cuda-gdb[0x4ae816]
cuda-gdb[0x406429]
cuda-gdb[0x51d0cb]
cuda-gdb[0x406b76]
cuda-gdb[0x51d0cb]
cuda-gdb[0x406204]
cuda-gdb[0x4061d6]
/lib64/libc.so.6(__libc_start_main+0xf5)[0x3d96621b75]
cuda-gdb[0x4060e9]
[Termination of CUDA Kernel 7 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Termination of CUDA Kernel 6 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Termination of CUDA Kernel 5 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Termination of CUDA Kernel 4 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Termination of CUDA Kernel 3 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Termination of CUDA Kernel 2 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Termination of CUDA Kernel 1 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
[Termination of CUDA Kernel 0 (memset32_aligned1D<<<(1,1,1),(128,1,1)>>>) on Device 0]
Note that cuda-gdb, itself, segfaults.  I also ran the correpsonding expamples for


thrust::gather_if
thrust::scatter
thrust::count
thrust::inclusive_scan
thrust::sort_by_key
thrust::reduce_by_key


And of these, only the last three (inclusive_scan, sort_by_key, reduce_by_key), work (i.e., do not crash cuda-gdb).

This must be an issue with the latest release (5.5) of thrust and/or cuda-gdb, because I have run the same 
tests with release 5.0 with no issues whatsoever.

Here is some info about my setup:
> cat /proc/driver/nvidia/version 
NVRM version: NVIDIA UNIX x86_64 Kernel Module  319.21  Sat May 11 23:51:00 PDT 2013
GCC version:  gcc version 4.8.1 20130603 (Red Hat 4.8.1-1) (GCC) 

> cat /proc/version 
Linux version 3.9.9-302.fc19.x86_64 ([e-mail]) (gcc version 4.8.1 20130603 (Red Hat 4.8.1-1) (GCC) ) #1 SMP Sat Jul 6 13:41:07 UTC 2013

> gcc --version
gcc (GCC) 4.8.1 20130603 (Red Hat 4.8.1-1)
Copyright (C) 2013 Free Software Foundation, Inc.
This is free software; see the source for copying conditions.  There is NO
warranty; not even for MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.

> lspci | grep NVIDIA
05:00.0 3D controller: NVIDIA Corporation GK104 [GeForce GTX 690] (rev a1)
05:00.1 Audio device: NVIDIA Corporation GK104 HDMI Audio Controller (rev a1)
06:00.0 VGA compatible controller: NVIDIA Corporation GK104 [GeForce GTX 690] (rev a1)
06:00.1 Audio device: NVIDIA Corporation GK104 HDMI Audio Controller (rev a1)

解决方案
As talonmies indicated, the problem is the Thrust libraries do not run correctly when built with debugging.  In my application I have a rather complicated .cu file containing several of my own CUDA kernels, along with multiple Thrust calls.  If I were to compile this file with the -g -G debug flags and run inside cuda-gdb, it would crash -- making it impossible for me to debug my kernels.  

Since I do not care about debugging the Thrust calls themselves (only my kernels), my solution involved putting all my thrust calls in another file thrustWrappers.cu and compiling this file without debugging.  Then in my main .cu file I would replace the calls to thrust with associated wrapper functions (defined in thrustWrappers).  For example, 
thrust::reduce(...)
became
thrust::reduce_wrapper(...)
Then I would link the two resulting object files together.

                        
这篇关于cuda-gdb与推力崩溃（CUDA版本5.5）的文章就介绍到这了，希望我们推荐的答案对大家有所帮助，也希望大家多多支持IT屋！