[Openmp-dev] launch of entry point was ok, but followed by a kernel execution error

Itaru Kitayama via Openmp-dev openmp-dev at lists.llvm.org
Mon Dec 2 16:39:17 PST 2019


Below is an excerpt from my CUDA GDB session (with debugging messages
enabled):

[...]
Libomptarget --> Mapping exists with HstPtrBegin=0x00003fffffffb320,
TgtPtrBegin=0x0000110028400400, Size=176, RefCount=8
Libomptarget --> Obtained target argument 0x0000110028400400 from host
pointer 0x00003fffffffb320
Libomptarget --> Launching target execution
__omp_offloading_3b_807ece55__ZN4nest20EventDeliveryManager15deliver_events_INS_9SpikeDataEEEbiRKSt6vectorIT_SaIS4_EE_l662
with pointer 0x00000000142af950 (index=1).
Target CUDA RTL --> Setting CUDA threads per block to default 128
Target CUDA RTL --> Using requested number of teams 1
Target CUDA RTL --> Launch kernel with 1 blocks and 128 threads
Target CUDA RTL --> Launch of entry point at 0x00000000142af950 successful!

CUDA Exception: Warp Illegal Address
The exception was triggered at PC 0x143224f8

Thread 1 "nest" received signal CUDA_EXCEPTION_14, Warp Illegal Address.
[Switching focus to CUDA kernel 0, grid 2, block (0,0,0), thread (0,0,0),
device 0, sm 0, warp 1, lane 0]
0x0000000014322508 in
nest::Connector<nest::StaticConnection<nest::TargetIdentifierPtrRport>
>::send_offload ()
(cuda-gdb) where
#0  0x0000000014322508 in
nest::Connector<nest::StaticConnection<nest::TargetIdentifierPtrRport>
>::send_offload ()
#1  0x00000000143163f0 in
__omp_offloading_3b_807ece55__ZN4nest20EventDeliveryManager15deliver_events_INS_9SpikeDataEEEbiRKSt6vectorIT_SaIS4_EE_l662<<<(1,1,1),(128,1,1)>>>
()
    at
/p/project/cpcp0/pcp0151/projects/nest-simulator/nestkernel/event_delivery_manager.cpp:704
(cuda-gdb)

How do I debug this issue?
-------------- next part --------------
An HTML attachment was scrubbed...
URL: <http://lists.llvm.org/pipermail/openmp-dev/attachments/20191203/f73d3644/attachment.html>


More information about the Openmp-dev mailing list