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