Running `cl-mem`: ``` Running write test. NIR validation failed after r600::r600_nir_split_64bit_io in ../src/gallium/drivers/r600/sfn/sfn_nir.cpp 1 errors: shader: MESA_SHADER_KERNEL source_sha1: {0x00000000, 0x00000000, 0x00000000, 0x00000000, 0x00000000} workgroup-size: 0, 0, 0 (variable) shared-size: 0 inputs: 0 outputs: 0 uniforms: 65 ubos: 1 shared: 0 ray queries: 0 decl_var ubo INTERP_MODE_NONE vec4[65] uniform_0 (0, 0, 0) decl_var uniform INTERP_MODE_NONE uint64_t @0 (0, 0, 0) decl_var uniform INTERP_MODE_NONE u64vec4x0a32B base_global_invocation_id (1, 32, 0) decl_var uniform INTERP_MODE_NONE uint8_t work_dim (2, 64, 0) decl_function __wrapped_test0 (0 params) impl __wrapped_test0 { block block_0: /* preds: */ vec1 32 ssa_0 = load_const (0x00000000 = 0.000000) vec1 64 ssa_1 = intrinsic load_ubo (ssa_0, ssa_0) (access=0, align_mul=8, align_offset=0, range_base=0, range=8) vec1 32 ssa_2 = load_const (0x00000100 = 0.000000) vec1 32 ssa_3 = load_const (0xffffffff = -nan) vec1 32 ssa_4 = load_const (0x00000080 = 0.000000) vec1 32 ssa_5 = load_const (0x00000020 = 0.000000) vec2 64 ssa_6 = intrinsic load_ubo (ssa_0, ssa_5) (access=0, align_mul=8, align_offset=0, range_base=0, range=24) vec1 32 ssa_71 = load_const (0x00000010 = 0.000000) vec1 32 ssa_72 = iadd ssa_5, ssa_71 vec1 64 ssa_73 = intrinsic load_ubo (ssa_0, ssa_72) (access=0, align_mul=8, align_offset=16, range_base=16, range=24) error: nir_intrinsic_align_offset(instr) < nir_intrinsic_align_mul(instr) (../src/compiler/nir/nir_validate.c:669) vec1 64 ssa_74 = mov ssa_6.y vec1 64 ssa_75 = mov ssa_6.x vec3 64 ssa_76 = vec3 ssa_75, ssa_74, ssa_73 vec3 32 ssa_7 = intrinsic load_workgroup_size () () vec3 64 ssa_8 = intrinsic load_workgroup_id () () vec3 32 ssa_9 = intrinsic load_local_invocation_id () () vec1 32 ssa_10 = unpack_64_2x32_split_x ssa_8.x vec1 32 ssa_11 = unpack_64_2x32_split_y ssa_8.x vec1 32 ssa_12 = umul_high ssa_10, ssa_7.x vec1 32 ssa_13 = imul ssa_10, ssa_7.x vec1 32 ssa_14 = imul ssa_11, ssa_7.x vec1 32 ssa_15 = iadd ssa_12, ssa_14 vec1 32 ssa_16 = iadd ssa_13, ssa_9.x vec1 1 ssa_17 = ult ssa_16, ssa_13 vec1 32 ssa_18 = b2i32 ssa_17 vec1 32 ssa_19 = iadd ssa_18, ssa_15 vec1 32 ssa_20 = unpack_64_2x32_split_x ssa_76.x vec1 32 ssa_21 = unpack_64_2x32_split_y ssa_76.x vec1 32 ssa_22 = iadd ssa_16, ssa_20 vec1 1 ssa_23 = ult ssa_22, ssa_16 vec1 32 ssa_24 = b2i32 ssa_23 vec1 32 ssa_25 = iadd ssa_19, ssa_21 vec1 32 ssa_26 = iadd ssa_24, ssa_25 vec1 32 ssa_27 = load_const (0x000000ff = 0.000000) vec1 32 ssa_28 = iand ssa_22, ssa_27 vec1 32 ssa_29 = load_const (0x00000008 = 0.000000) vec1 32 ssa_30 = load_const (0x00000018 = 0.000000) vec1 32 ssa_31 = ushr ssa_22, ssa_29 vec1 32 ssa_32 = ishl ssa_26, ssa_30 vec1 32 ssa_33 = ior ssa_31, ssa_32 vec1 32 ssa_34 = load_const (0x00000010 = 0.000000) vec1 32 ssa_35 = ishl ssa_22, ssa_34 vec1 32 ssa_36 = ishl ssa_26, ssa_34 vec1 32 ssa_37 = ushr ssa_22, ssa_34 vec1 32 ssa_38 = ior ssa_36, ssa_37 vec1 64 ssa_39 = pack_64_2x32_split ssa_35, ssa_38 vec1 32 ssa_40 = load_const (0x0000007f = 0.000000) /* succs: block_1 */ loop { block block_1: /* preds: block_0 block_9 */ vec1 32 ssa_41 = phi block_0: ssa_4, block_9: ssa_42 vec1 32 ssa_42 = phi block_0: ssa_40, block_9: ssa_70 vec1 1 ssa_43 = ieq ssa_41, ssa_0 /* succs: block_2 block_3 */ if ssa_43 { block block_2: /* preds: block_1 */ break /* succs: block_10 */ } else { block block_3: /* preds: block_1 */ /* succs: block_4 */ } block block_4: /* preds: block_3 */ vec1 32 ssa_44 = ishl ssa_33, ssa_30 vec1 32 ssa_45 = unpack_64_2x32_split_x ssa_1 vec1 32 ssa_46 = unpack_64_2x32_split_y ssa_1 vec1 32 ssa_47 = iadd ssa_45, ssa_44 vec1 1 ssa_48 = ult ssa_47, ssa_45 vec1 32 ssa_49 = b2i32 ssa_48 vec1 32 ssa_50 = iadd ssa_49, ssa_46 /* succs: block_5 */ loop { block block_5: /* preds: block_4 block_8 */ vec1 32 ssa_51 = phi block_4: ssa_0, block_8: ssa_69 vec1 32 ssa_52 = load_const (0x00200000 = 0.000000) vec1 1 ssa_53 = uge ssa_51, ssa_52 /* succs: block_6 block_7 */ if ssa_53 { block block_6: /* preds: block_5 */ break /* succs: block_9 */ } else { block block_7: /* preds: block_5 */ /* succs: block_8 */ } block block_8: /* preds: block_7 */ vec1 32 ssa_54 = iadd ssa_51, ssa_28 vec1 1 ssa_55 = ult ssa_54, ssa_51 vec1 32 ssa_56 = b2i32 ssa_55 vec1 32 ssa_57 = load_const (0x00000003 = 0.000000) vec1 32 ssa_58 = load_const (0x0000001d = 0.000000) vec1 32 ssa_59 = ishl ssa_54, ssa_57 vec1 32 ssa_60 = ishl ssa_56, ssa_57 vec1 32 ssa_61 = ushr ssa_54, ssa_58 vec1 32 ssa_62 = ior ssa_60, ssa_61 vec1 32 ssa_63 = iadd ssa_47, ssa_59 vec1 1 ssa_64 = ult ssa_63, ssa_47 vec1 32 ssa_65 = b2i32 ssa_64 vec1 32 ssa_66 = iadd ssa_50, ssa_62 vec1 32 ssa_67 = iadd ssa_65, ssa_66 vec1 64 ssa_68 = pack_64_2x32_split ssa_63, ssa_67 intrinsic store_global (ssa_39, ssa_68) (wrmask=x /*1*/, access=0, align_mul=8, align_offset=0) vec1 32 ssa_69 = iadd ssa_51, ssa_2 /* succs: block_5 */ } block block_9: /* preds: block_6 */ vec1 32 ssa_70 = iadd ssa_42, ssa_3 /* succs: block_1 */ } block block_10: /* preds: block_2 */ /* succs: block_11 */ block block_11: } Thread 6 "rusticl queue t" received signal SIGABRT, Aborted. [Switching to Thread 0x7fffd2e6a640 (LWP 2011660)] __pthread_kill_implementation (no_tid=0, signo=6, threadid=140736731719232) at ./nptl/pthread_kill.c:44 44 ./nptl/pthread_kill.c: No such file or directory. (gdb) thread apply all backtrace Thread 8 (Thread 0x7fffd2327640 (LWP 2011662) "cl-mem:disk$1"): #0 __futex_abstimed_wait_common64 (private=0, cancel=true, abstime=0x0, op=393, expected=0, futex_word=0x555555656018) at ./nptl/futex-internal.c:57 #1 __futex_abstimed_wait_common (cancel=true, private=0, abstime=0x0, clockid=0, expected=0, futex_word=0x555555656018) at ./nptl/futex-internal.c:87 #2 __GI___futex_abstimed_wait_cancelable64 (futex_word=futex_word@entry=0x555555656018, expected=expected@entry=0, clockid=clockid@entry=0, abstime=abstime@entry=0x0, private=private@entry=0) at ./nptl/futex-internal.c:139 #3 0x00007ffff7e0dac1 in __pthread_cond_wait_common (abstime=0x0, clockid=0, mutex=0x555555655fc8, cond=0x555555655ff0) at ./nptl/pthread_cond_wait.c:503 #4 ___pthread_cond_wait (cond=0x555555655ff0, mutex=0x555555655fc8) at ./nptl/pthread_cond_wait.c:627 #5 0x00007ffff518b55e in cnd_wait (cond=0x555555655ff0, mtx=0x555555655fc8) at ../src/c11/impl/threads_posix.c:135 #6 0x00007ffff5114a56 in util_queue_thread_func (input=0x55555af90b50) at ../src/util/u_queue.c:289 #7 0x00007ffff518b261 in impl_thrd_routine (p=0x55555ada5d60) at ../src/c11/impl/threads_posix.c:67 #8 0x00007ffff7e0eb43 in start_thread (arg=) at ./nptl/pthread_create.c:442 #9 0x00007ffff7ea0a00 in clone3 () at ../sysdeps/unix/sysv/linux/x86_64/clone3.S:81 Thread 7 (Thread 0x7fffd2b28640 (LWP 2011661) "cl-mem:disk$0"): #0 __futex_abstimed_wait_common64 (private=0, cancel=true, abstime=0x0, op=393, expected=0, futex_word=0x55555608fa8c) at ./nptl/futex-internal.c:57 #1 __futex_abstimed_wait_common (cancel=true, private=0, abstime=0x0, clockid=0, expected=0, futex_word=0x55555608fa8c) at ./nptl/futex-internal.c:87 #2 __GI___futex_abstimed_wait_cancelable64 (futex_word=futex_word@entry=0x55555608fa8c, expected=expected@entry=0, clockid=clockid@entry=0, abstime=abstime@entry=0x0, private=private@entry=0) at ./nptl/futex-internal.c:139 #3 0x00007ffff7e0dac1 in __pthread_cond_wait_common (abstime=0x0, clockid=0, mutex=0x55555608fa38, cond=0x55555608fa60) at ./nptl/pthread_cond_wait.c:503 #4 ___pthread_cond_wait (cond=0x55555608fa60, mutex=0x55555608fa38) at ./nptl/pthread_cond_wait.c:627 #5 0x00007ffff518b55e in cnd_wait (cond=0x55555608fa60, mtx=0x55555608fa38) at ../src/c11/impl/threads_posix.c:135 #6 0x00007ffff5114a56 in util_queue_thread_func (input=0x55555a8c7390) at ../src/util/u_queue.c:289 #7 0x00007ffff518b261 in impl_thrd_routine (p=0x55555a8ebcd0) at ../src/c11/impl/threads_posix.c:67 #8 0x00007ffff7e0eb43 in start_thread (arg=) at ./nptl/pthread_create.c:442 #9 0x00007ffff7ea0a00 in clone3 () at ../sysdeps/unix/sysv/linux/x86_64/clone3.S:81 Thread 6 (Thread 0x7fffd2e6a640 (LWP 2011660) "rusticl queue t"): #0 __pthread_kill_implementation (no_tid=0, signo=6, threadid=140736731719232) at ./nptl/pthread_kill.c:44 #1 __pthread_kill_internal (signo=6, threadid=140736731719232) at ./nptl/pthread_kill.c:78 #2 __GI___pthread_kill (threadid=140736731719232, signo=signo@entry=6) at ./nptl/pthread_kill.c:89 #3 0x00007ffff7dbc476 in __GI_raise (sig=sig@entry=6) at ../sysdeps/posix/raise.c:26 #4 0x00007ffff7da27f3 in __GI_abort () at ./stdlib/abort.c:79 #5 0x00007ffff6118b7b in dump_errors (state=0x7fffd2e68b20, when=0x7ffff7822040 "after r600::r600_nir_split_64bit_io in ../src/gallium/drivers/r600/sfn/sfn_nir.cpp") at ../src/compiler/nir/nir_validate.c:1765 #6 0x00007ffff6118f0e in nir_validate_shader (shader=0x7fffc403cb90, when=0x7ffff7822040 "after r600::r600_nir_split_64bit_io in ../src/gallium/drivers/r600/sfn/sfn_nir.cpp") at ../src/compiler/nir/nir_validate.c:1827 #7 0x00007ffff635fc6b in r600_shader_from_nir (rctx=0x55555de3ae40, pipeshader=0x7fffc4037440, key=0x7fffd2e6901c) at ../src/gallium/drivers/r600/sfn/sfn_nir.cpp:762 #8 0x00007ffff61d3fba in r600_pipe_shader_create (ctx=0x55555de3ae40, shader=0x7fffc4037440, key=...) at ../src/gallium/drivers/r600/r600_shader.c:218 #9 0x00007ffff620bb61 in r600_shader_select (ctx=0x55555de3ae40, sel=0x7fffc4034060, dirty=0x7fffd2e69147, precompile=true) at ../src/gallium/drivers/r600/r600_state_common.c:959 #10 0x00007ffff61974d0 in evergreen_create_compute_state (ctx=0x55555de3ae40, cso=0x7fffd2e691c8) at ../src/gallium/drivers/r600/evergreen_compute.c:451 #11 0x00007ffff4d45804 in mesa_rust::pipe::context::PipeContext::create_compute_state (self=0x7fffd2e69ac0, nir=0x555556a5d4e8, static_local_mem=0) at ../src/gallium/frontends/rusticl/mesa/pipe/context.rs:272 #12 0x00007ffff4c5dffd in rusticl::core::kernel::{impl#4}::launch::{closure#0} (q=0x55555d357c18, ctx=0x7fffd2e69ac0) at ../src/gallium/frontends/rusticl/core/kernel.rs:1007 #13 0x00007ffff4c7058d in alloc::boxed::{impl#46}::call<(&alloc::sync::Arc, &mesa_rust::pipe::context::PipeContext), dyn core::ops::function::Fn<(&alloc::sync::Arc, &mesa_rust::pipe::context::PipeContext), Output=core::result::Result<(), i32>>, alloc::alloc::Global> (self=0x55555d357c40, args=...) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/alloc/src/boxed.rs:1868 #14 0x00007ffff4c8901e in rusticl::core::event::{impl#2}::call::{closure#0} (w=0x55555d357c40) at ../src/gallium/frontends/rusticl/core/event.rs:168 #15 0x00007ffff4cb9848 in core::option::Option<&alloc::boxed::Box, &mesa_rust::pipe::context::PipeContext), Output=core::result::Result<(), i32>>, alloc::alloc::Global>>::map_or<&alloc::boxed::Box, &mesa_rust::pipe::context::PipeContext), Output=core::result::Result<(), i32>>, alloc::alloc::Global>, i32, rusticl::core::event::{impl#2}::call::{closure#0}> (self=..., default=2, f=...) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/core/src/option.rs:946 #16 0x00007ffff4c88f54 in rusticl::core::event::Event::call (self=0x55555d357c00, ctx=0x7fffd2e69ac0) at ../src/gallium/frontends/rusticl/core/event.rs:164 #17 0x00007ffff4d10ffe in rusticl::core::queue::{impl#0}::new::{closure#0} () at ../src/gallium/frontends/rusticl/core/queue.rs:65 #18 0x00007ffff4c777fe in std::sys_common::backtrace::__rust_begin_short_backtrace (f=...) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/std/src/sys_common/backtrace.rs:123 #19 0x00007ffff4cda8f1 in std::thread::{impl#0}::spawn_unchecked::{closure#1}::{closure#0} () at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/std/src/thread/mod.rs:477 #20 0x00007ffff4c51631 in core::panic::unwind_safe::{impl#23}::call_once<(), std::thread::{impl#0}::spawn_unchecked::{closure#1}::{closure#0}> (self=..., _args=()) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/core/src/panic/unwind_safe.rs:271 #21 0x00007ffff4c63832 in std::panicking::try::do_call, ()> (data=0x7fffd2e69c08) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/std/src/panicking.rs:406 #22 0x00007ffff4c641fb in __rust_try () from install/lib/x86_64-linux-gnu/libRusticlOpenCL.so.1 #23 0x00007ffff4c63720 in std::panicking::try<(), core::panic::unwind_safe::AssertUnwindSafe> (f=...) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/std/src/panicking.rs:370 #24 0x00007ffff4c97c21 in std::panic::catch_unwind, ()> (f=...) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/std/src/panic.rs:133 #25 0x00007ffff4cda679 in std::thread::{impl#0}::spawn_unchecked::{closure#1} () at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/std/src/thread/mod.rs:476 #26 0x00007ffff4d020ee in core::ops::function::FnOnce::call_once () at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/core/src/ops/function.rs:227 #27 0x00007ffff5024b83 in alloc::boxed::{impl#44}::call_once<(), dyn core::ops::function::FnOnce<(), Output=()>, alloc::alloc::Global> () at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/alloc/src/boxed.rs:1854 #28 alloc::boxed::{impl#44}::call_once<(), alloc::boxed::Box, alloc::alloc::Global>, alloc::alloc::Global> () at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/alloc/src/boxed.rs:1854 #29 std::sys::unix::thread::{impl#2}::new::thread_start () at library/std/src/sys/unix/thread.rs:108 #30 0x00007ffff7e0eb43 in start_thread (arg=) at ./nptl/pthread_create.c:442 #31 0x00007ffff7ea0a00 in clone3 () at ../sysdeps/unix/sysv/linux/x86_64/clone3.S:81 Thread 5 (Thread 0x7fffd36bd640 (LWP 2011659) "cl-mem:disk$0"): #0 __futex_abstimed_wait_common64 (private=0, cancel=true, abstime=0x0, op=393, expected=0, futex_word=0x55555566df08) at ./nptl/futex-internal.c:57 #1 __futex_abstimed_wait_common (cancel=true, private=0, abstime=0x0, clockid=0, expected=0, futex_word=0x55555566df08) at ./nptl/futex-internal.c:87 #2 __GI___futex_abstimed_wait_cancelable64 (futex_word=futex_word@entry=0x55555566df08, expected=expected@entry=0, clockid=clockid@entry=0, abstime=abstime@entry=0x0, private=private@entry=0) at ./nptl/futex-internal.c:139 #3 0x00007ffff7e0dac1 in __pthread_cond_wait_common (abstime=0x0, clockid=0, mutex=0x55555566deb8, cond=0x55555566dee0) at ./nptl/pthread_cond_wait.c:503 #4 ___pthread_cond_wait (cond=0x55555566dee0, mutex=0x55555566deb8) at ./nptl/pthread_cond_wait.c:627 #5 0x00007ffff518b55e in cnd_wait (cond=0x55555566dee0, mtx=0x55555566deb8) at ../src/c11/impl/threads_posix.c:135 #6 0x00007ffff5114a56 in util_queue_thread_func (input=0x55555566da90) at ../src/util/u_queue.c:289 #7 0x00007ffff518b261 in impl_thrd_routine (p=0x55555566da70) at ../src/c11/impl/threads_posix.c:67 #8 0x00007ffff7e0eb43 in start_thread (arg=) at ./nptl/pthread_create.c:442 #9 0x00007ffff7ea0a00 in clone3 () at ../sysdeps/unix/sysv/linux/x86_64/clone3.S:81 Thread 4 (Thread 0x7fffd3fff640 (LWP 2011658) "cl-mem:rcs0"): #0 __futex_abstimed_wait_common64 (private=0, cancel=true, abstime=0x0, op=393, expected=0, futex_word=0x55555566d378) at ./nptl/futex-internal.c:57 #1 __futex_abstimed_wait_common (cancel=true, private=0, abstime=0x0, clockid=0, expected=0, futex_word=0x55555566d378) at ./nptl/futex-internal.c:87 #2 __GI___futex_abstimed_wait_cancelable64 (futex_word=futex_word@entry=0x55555566d378, expected=expected@entry=0, clockid=clockid@entry=0, abstime=abstime@entry=0x0, private=private@entry=0) at ./nptl/futex-internal.c:139 #3 0x00007ffff7e0dac1 in __pthread_cond_wait_common (abstime=0x0, clockid=0, mutex=0x55555566d328, cond=0x55555566d350) at ./nptl/pthread_cond_wait.c:503 #4 ___pthread_cond_wait (cond=0x55555566d350, mutex=0x55555566d328) at ./nptl/pthread_cond_wait.c:627 #5 0x00007ffff518b55e in cnd_wait (cond=0x55555566d350, mtx=0x55555566d328) at ../src/c11/impl/threads_posix.c:135 #6 0x00007ffff5114a56 in util_queue_thread_func (input=0x55555566d540) at ../src/util/u_queue.c:289 #7 0x00007ffff518b261 in impl_thrd_routine (p=0x55555566dab0) at ../src/c11/impl/threads_posix.c:67 #8 0x00007ffff7e0eb43 in start_thread (arg=) at ./nptl/pthread_create.c:442 #9 0x00007ffff7ea0a00 in clone3 () at ../sysdeps/unix/sysv/linux/x86_64/clone3.S:81 Thread 3 (Thread 0x7fffd8870640 (LWP 2011657) "cl-mem:disk$0"): #0 __futex_abstimed_wait_common64 (private=0, cancel=true, abstime=0x0, op=393, expected=0, futex_word=0x555555656018) at ./nptl/futex-internal.c:57 #1 __futex_abstimed_wait_common (cancel=true, private=0, abstime=0x0, clockid=0, expected=0, futex_word=0x555555656018) at ./nptl/futex-internal.c:87 #2 __GI___futex_abstimed_wait_cancelable64 (futex_word=futex_word@entry=0x555555656018, expected=expected@entry=0, clockid=clockid@entry=0, abstime=abstime@entry=0x0, private=private@entry=0) at ./nptl/futex-internal.c:139 #3 0x00007ffff7e0dac1 in __pthread_cond_wait_common (abstime=0x0, clockid=0, mutex=0x555555655fc8, cond=0x555555655ff0) at ./nptl/pthread_cond_wait.c:503 #4 ___pthread_cond_wait (cond=0x555555655ff0, mutex=0x555555655fc8) at ./nptl/pthread_cond_wait.c:627 #5 0x00007ffff518b55e in cnd_wait (cond=0x555555655ff0, mtx=0x555555655fc8) at ../src/c11/impl/threads_posix.c:135 #6 0x00007ffff5114a56 in util_queue_thread_func (input=0x555555657610) at ../src/util/u_queue.c:289 #7 0x00007ffff518b261 in impl_thrd_routine (p=0x5555556575f0) at ../src/c11/impl/threads_posix.c:67 #8 0x00007ffff7e0eb43 in start_thread (arg=) at ./nptl/pthread_create.c:442 #9 0x00007ffff7ea0a00 in clone3 () at ../sysdeps/unix/sysv/linux/x86_64/clone3.S:81 Thread 2 (Thread 0x7fffd91b2640 (LWP 2011656) "cl-mem:rcs0"): #0 __futex_abstimed_wait_common64 (private=0, cancel=true, abstime=0x0, op=393, expected=0, futex_word=0x555555654ef8) at ./nptl/futex-internal.c:57 #1 __futex_abstimed_wait_common (cancel=true, private=0, abstime=0x0, clockid=0, expected=0, futex_word=0x555555654ef8) at ./nptl/futex-internal.c:87 #2 __GI___futex_abstimed_wait_cancelable64 (futex_word=futex_word@entry=0x555555654ef8, expected=expected@entry=0, clockid=clockid@entry=0, abstime=abstime@entry=0x0, private=private@entry=0) at ./nptl/futex-internal.c:139 #3 0x00007ffff7e0dac1 in __pthread_cond_wait_common (abstime=0x0, clockid=0, mutex=0x555555654ea8, cond=0x555555654ed0) at ./nptl/pthread_cond_wait.c:503 #4 ___pthread_cond_wait (cond=0x555555654ed0, mutex=0x555555654ea8) at ./nptl/pthread_cond_wait.c:627 #5 0x00007ffff518b55e in cnd_wait (cond=0x555555654ed0, mtx=0x555555654ea8) at ../src/c11/impl/threads_posix.c:135 #6 0x00007ffff5114a56 in util_queue_thread_func (input=0x555555652660) at ../src/util/u_queue.c:289 #7 0x00007ffff518b261 in impl_thrd_routine (p=0x555555652680) at ../src/c11/impl/threads_posix.c:67 #8 0x00007ffff7e0eb43 in start_thread (arg=) at ./nptl/pthread_create.c:442 #9 0x00007ffff7ea0a00 in clone3 () at ../sysdeps/unix/sysv/linux/x86_64/clone3.S:81 Thread 1 (Thread 0x7ffff7d65740 (LWP 2002944) "cl-mem"): #0 __futex_abstimed_wait_common64 (private=1498531040, cancel=true, abstime=0x7fffffffce28, op=137, expected=0, futex_word=0x55555d981448) at ./nptl/futex-internal.c:57 #1 __futex_abstimed_wait_common (cancel=true, private=1498531040, abstime=0x7fffffffce28, clockid=-188114648, expected=0, futex_word=0x55555d981448) at ./nptl/futex-internal.c:87 #2 __GI___futex_abstimed_wait_cancelable64 (futex_word=futex_word@entry=0x55555d981448, expected=expected@entry=0, clockid=clockid@entry=1, abstime=abstime@entry=0x7fffffffce28, private=private@entry=0) at ./nptl/futex-internal.c:139 #3 0x00007ffff7e0df1b in __pthread_cond_wait_common (abstime=0x7fffffffce28, clockid=1, mutex=0x555558a8b840, cond=0x55555d981420) at ./nptl/pthread_cond_wait.c:503 #4 ___pthread_cond_timedwait64 (cond=0x55555d981420, mutex=0x555558a8b840, abstime=0x7fffffffce28) at ./nptl/pthread_cond_wait.c:652 #5 0x00007ffff501c7d5 in std::sys::unix::condvar::Condvar::wait_timeout () at library/std/src/sys/unix/condvar.rs:114 #6 0x00007ffff4c7789a in std::sys_common::condvar::Condvar::wait_timeout (self=0x55555d357cc0, mutex=0x55555d357c50, dur=...) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/std/src/sys_common/condvar.rs:56 #7 0x00007ffff4c77636 in std::sync::condvar::Condvar::wait_timeout (self=0x55555d357cc0, guard=..., dur=...) at /rustc/9d1b2106e23b1abd32fce1f17267604a5102f57a/library/std/src/sync/condvar.rs:385 #8 0x00007ffff4c88dc1 in rusticl::core::event::Event::wait (self=0x55555d357c00) at ../src/gallium/frontends/rusticl/core/event.rs:147 #9 0x00007ffff4d115cb in rusticl::core::queue::Queue::flush (self=0x555560292f30, wait=true) at ../src/gallium/frontends/rusticl/core/queue.rs:91 #10 0x00007ffff4c4a141 in rusticl::api::queue::finish_queue (command_queue=0x555560292f30) at ../src/gallium/frontends/rusticl/api/queue.rs:198 #11 0x00007ffff4c4639e in rusticl::api::icd::cl_finish (command_queue=0x555560292f30) at ../src/gallium/frontends/rusticl/api/icd.rs:936 #12 0x0000555555556fd9 in run_opencl (tests=0x7fffffffd340, queue=0x555560292f30, ctx=0x555557d47960) at main.c:410 #13 run_bench () at main.c:573 #14 0x0000555555556568 in main (argc=1, argv=0x7fffffffd8f8) at main.c:646 ```