Attachment 106718 Details for Bug 84232 – Stack trace

Stack trace

crash2.txt (text/plain), 5.56 KB, created by Vitaliy Filippov on 2014-09-23 09:19:54 UTC

(hide)

Description:

Filename:

MIME Type:

Creator: Vitaliy Filippov

Created: 2014-09-23 09:19:54 UTC

Size: 5.56 KB

patch

obsolete

>Program received signal SIGSEGV, Segmentation fault.
>[Switching to Thread 0x7fffb6ffd700 (LWP 28067)]
>0x00007fffc53a79ca in llvm::Use::get (this=0x18) at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/include/llvm/IR/Use.h:95
>95        Value *get() const { return Val; }
>(gdb) bt
>#0  0x00007fffc53a79ca in llvm::Use::get (this=0x18) at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/include/llvm/IR/Use.h:95
>#1  0x00007fffc540eb9f in llvm::PHINode::getOperand (this=0x7fff6cc6bba0, i_nocapture=1)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/include/llvm/IR/Instructions.h:2262
>#2  0x00007fffc540eafc in llvm::PHINode::getIncomingValue (this=0x7fff6cc6bba0, i=1)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/include/llvm/IR/Instructions.h:2159
>#3  0x00007fffc690a07e in (anonymous namespace)::SIAnnotateControlFlow::handleLoopCondition (this=0x7fff6d893950, Cond=0x7fff6cc6bba0, Broken=0x7fff6c9002a0)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/Target/R600/SIAnnotateControlFlow.cpp:214
>#4  0x00007fffc690a5c1 in (anonymous namespace)::SIAnnotateControlFlow::handleLoop (this=0x7fff6d893950, Term=0x7fff6c0f0758)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/Target/R600/SIAnnotateControlFlow.cpp:269
>#5  0x00007fffc690a964 in (anonymous namespace)::SIAnnotateControlFlow::runOnFunction (this=0x7fff6d893950, F=...)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/Target/R600/SIAnnotateControlFlow.cpp:306
>#6  0x00007fffc559d0d1 in llvm::FPPassManager::runOnFunction (this=0x7fff6d8957a0, F=...)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/IR/LegacyPassManager.cpp:1545
>#7  0x00007fffc559d25e in llvm::FPPassManager::runOnModule (this=0x7fff6d8957a0, M=...)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/IR/LegacyPassManager.cpp:1565
>#8  0x00007fffc559d622 in (anonymous namespace)::MPPassManager::runOnModule (this=0x7fff6d8ae430, M=...)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/IR/LegacyPassManager.cpp:1623
>#9  0x00007fffc559dcb9 in llvm::legacy::PassManagerImpl::run (this=0x7fff6d883c50, M=...)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/IR/LegacyPassManager.cpp:1730
>#10 0x00007fffc559def7 in llvm::legacy::PassManager::run (this=0x7fffb6ffc150, M=...)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/IR/LegacyPassManager.cpp:1767
>#11 0x00007fffc5df66a2 in LLVMTargetMachineEmit (T=0x7fff6d249340, M=0x7fff6c17b0f0, OS=..., codegen=LLVMObjectFile, ErrorMessage=0x7fffb6ffc2a0)
>    at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/Target/TargetMachineC.cpp:217
>#12 0x00007fffc5df687e in LLVMTargetMachineEmitToMemoryBuffer (T=0x7fff6d249340, M=0x7fff6c17b0f0, codegen=LLVMObjectFile, ErrorMessage=0x7fffb6ffc2a0, 
>    OutMemBuf=0x7fffb6ffc2a8) at /var/home/vitali/setup/llvm-toolchain-3.5-3.5/lib/Target/TargetMachineC.cpp:243
>#13 0x00007fffc41fc89d in radeon_llvm_compile (M=0x7fff6c17b0f0, binary=0x7fffb6ffc350, gpu_family=0x1 <error: Cannot access memory at address 0x1>, dump=0)
>    at ../../../../../../src/gallium/drivers/radeon/radeon_llvm_emit.c:156
>#14 0x00007fffc420c443 in si_compile_llvm (sctx=0x7fffb8048650, shader=0x7fff6c18bec0, mod=0x7fff6c17b0f0)
>    at ../../../../../../src/gallium/drivers/radeonsi/si_shader.c:2561
>#15 0x00007fffc4202a57 in si_create_compute_state (ctx=0x7fffb8048650, cso=<optimized out>) at ../../../../../../src/gallium/drivers/radeonsi/si_compute.c:85
>#16 0x00007fffc7756720 in clover::kernel::exec_context::bind (this=this@entry=0x7fff8c002338, _q=...)
>    at ../../../../../../src/gallium/state_trackers/clover/core/kernel.cpp:190
>#17 0x00007fffc77570e2 in clover::kernel::launch (this=<optimized out>, q=..., grid_offset=..., grid_size=std::vector of length 2, capacity 2 = {...}, 
>    block_size=std::vector of length 2, capacity 2 = {...}) at ../../../../../../src/gallium/state_trackers/clover/core/kernel.cpp:73
>#18 0x00007fffc77530e0 in clover::event::trigger (this=this@entry=0x7fff6c015d10) at ../../../../../../src/gallium/state_trackers/clover/core/event.cpp:42
>#19 0x00007fffc7753ca0 in trigger (this=0x7fff6c015d10) at ../../../../../../src/gallium/state_trackers/clover/core/event.cpp:85
>#20 clover::hard_event::hard_event(clover::command_queue&, unsigned int, clover::ref_vector<clover::event> const&, std::function<void (clover::event&)>) (
>    this=0x7fff6c015d10, q=..., command=4592, deps=..., action=...) at ../../../../../../src/gallium/state_trackers/clover/core/event.cpp:84
>#21 0x00007fffc774041e in create<clover::hard_event, clover::command_queue&, int, clover::ref_vector<clover::event>&, clEnqueueNDRangeKernel(cl_command_queue, cl_kernel, cl_uint, const size_t*, const size_t*, const size_t*, cl_uint, _cl_event* const*, _cl_event**)::<lambda(clover::event&)> > ()
>    at ../../../../../../src/gallium/state_trackers/clover/util/pointer.hpp:230
>#22 clEnqueueNDRangeKernel (d_q=0x7fffb80521e8, d_kern=0x7fff8c002308, dims=<optimized out>, d_grid_offset=<optimized out>, d_grid_size=<optimized out>, 
>    d_block_size=<optimized out>, num_deps=0, d_deps=0x0, rd_ev=0x0) at ../../../../../../src/gallium/state_trackers/clover/api/kernel.cpp:285
>#23 0x0000000001667e69 in ccl::OpenCLDevice::enqueue_kernel(ccl::_cl_kernel*, unsigned long, unsigned long) ()
>#24 0x000000000166eba1 in ccl::OpenCLDevice::path_trace(ccl::RenderTile&, int) ()
>#25 0x000000000166ee84 in ccl::OpenCLDevice::thread_run(ccl::DeviceTask*) ()
>#26 0x000000000193660e in ccl::DedicatedTaskPool::thread_run() ()
>#27 0x0000000001640c29 in ccl::thread::run(void*) ()
>#28 0x00007ffff59930a4 in start_thread (arg=0x7fffb6ffd700) at pthread_create.c:309
>#29 0x00007ffff04d5c2d in clone () at ../sysdeps/unix/sysv/linux/x86_64/clone.S:111

Actions: View

Attachments on bug 84232: 106717 | 106718 | 107527 | 107681 | 108266

Use of freedesktop.org services, including Bugzilla, is subject to our Code of Conduct. How we collect and use information is described in our Privacy Policy.