CUDA-gdb를 충돌 (CUDA 5.5을 출시)

Question

나는 다음과 같은 사소한 추력 :: 프로그램 수집이 (추력에서 직접 촬영을 :: 문서를 수집)

#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; 
} 

내가

/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 

으로이 컴파일 그를

이

>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] 

참고 CUDA-GDB를 :

다음 나는 CUDA-GDB에 부착 한 후 먼저이 간단한 프로그램을 실행 해보십시오 엘프, 세그 폴트. 또한 추력 :: gather_if는

추력 : 분산

추력 :

추력 :: inclusive_scan

추력 :: sort_by_key

추력을 계산

• 의 correpsonding expamples를 실행 : : reduce_by_key

그리고 이들 중 마지막 3 개 (inclusive_scan, sort_by_key, reduce_by_key), 작동 (즉, cuda-gdb를 중단하지 마십시오.

릴리즈 012와 동일한 테스트를 실행했기 때문에 이것은 최신 릴리스 (5.5)의 추력 및/또는 cuda-gdb와 관련된 문제 여야합니다. talonmies가 표시

> 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 (mockbuild@bkernel01.phx2.fedoraproject.org) (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) 

Answer 1

으로 문제가 디버깅 구축 할 때 스러스트 라이브러리가 제대로 실행되지 않는 것입니다 : 여기

내 설정에 대한 몇 가지 정보입니다. 내 응용 프로그램에는 여러 가지 Thrust 호출과 함께 내 자신의 CUDA 커널을 포함하는 다소 복잡한 .cu 파일이 있습니다. 이 파일을 -g -G 디버그 플래그로 컴파일하고 cuda-gdb에서 실행하면 충돌이 발생하여 커널을 디버깅 할 수 없게됩니다.

Thrust 호출 자체 (내 커널 만) 디버깅에 신경 쓰지 않아서 내 솔루션은 thrustWrappers.cu 파일을 다른 모든 파일에 넣고 디버깅하지 않고이 파일을 컴파일해야했습니다. 그런 다음 내 주요 .cu 파일에서 thrustWrappers에 정의 된 관련 래퍼 함수로 밀어 넣기위한 호출을 대체합니다. 예를 들어,

thrust::reduce(...) 

는

thrust::reduce_wrapper(...) 

그런 다음 나는 두 결과 객체 파일을 함께 연결할 것되었다.