Attachment 135736 Details for Bug 103915 – thread apply all bt full with git master 043d14db30.

thread apply all bt full with git master 043d14db30.

undertale-full-bt.txt (text/plain), 76.21 KB, created by John Steele Scott on 2017-11-27 11:34:54 UTC

(hide)

Description:

Filename:

MIME Type:

Creator: John Steele Scott

Created: 2017-11-27 11:34:54 UTC

Size: 76.21 KB

patch

obsolete

>
>Thread 9 (Thread 0xe88a3b40 (LWP 7283)):
>#0  0xf7eeedc9 in __kernel_vsyscall ()
>No symbol table info available.
>#1  0xf7b8db9b in pthread_cond_wait@@GLIBC_2.3.2 () at ../sysdeps/unix/sysv/linux/i386/pthread_cond_wait.S:187
>No locals.
>#2  0xf009209a in cnd_wait (mtx=0x8ee1450, cond=0x8ee1468) at ../../include/c11/threads_posix.h:155
>No locals.
>#3  util_queue_thread_func (input=<optimized out>) at u_queue.c:255
>        job = <optimized out>
>        queue = 0x8ee144c
>        thread_index = <optimized out>
>#4  0xf7b8827a in start_thread (arg=0xe88a3b40) at pthread_create.c:333
>        __res = <optimized out>
>        pd = 0xe88a3b40
>        now = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {-138821632, 0, 4001536, -393595864, 65852459, 1720630293}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x0, 0x0}, data = {prev = 0x0, cleanup = 0x0, canceltype = 0}}}
>        not_first_call = 0
>        pagesize_m1 = <optimized out>
>        sp = <optimized out>
>        freesize = <optimized out>
>        __PRETTY_FUNCTION__ = "start_thread"
>#5  0xf76a3b56 in clone () at ../sysdeps/unix/sysv/linux/i386/clone.S:110
>No locals.
>
>Thread 8 (Thread 0xf7376700 (LWP 7275)):
>#0  0xf7eeedc9 in __kernel_vsyscall ()
>No symbol table info available.
>#1  0xf769f627 in syscall () at ../sysdeps/unix/sysv/linux/i386/syscall.S:29
>No locals.
>#2  0xf0091d99 in sys_futex (val3=-1, addr2=0x0, timeout=0x0, val1=2, op=9, addr1=0x8f3f330) at ../../src/util/futex.h:38
>No locals.
>#3  futex_wait (timeout=0x0, value=2, addr=0x8f3f330) at ../../src/util/futex.h:50
>No locals.
>#4  do_futex_fence_wait (fence=fence@entry=0x8f3f330, timeout=timeout@entry=false, abs_timeout=0) at u_queue.c:114
>        v = <optimized out>
>        ts = {tv_sec = 0, tv_nsec = 0}
>#5  0xf0092282 in _util_queue_fence_wait (fence=0x8f3f330) at u_queue.c:129
>No locals.
>#6  0xf032895b in util_queue_fence_wait (fence=0x8f3f330) at ../../../../src/util/u_queue.h:160
>No locals.
>#7  si_shader_select_with_key (sscreen=0x8e25030, state=state@entry=0x8e40868, compiler_state=compiler_state@entry=0xffb5431c, key=0xffb541d4, thread_index=-1) at si_state_shaders.c:1616
>        sel = 0x8f3f328
>        previous_stage_sel = 0x0
>        current = 0xffb541d4
>        iter = <optimized out>
>        shader = <optimized out>
>        is_pure_monolithic = <optimized out>
>#8  0xf0328b40 in si_shader_select (ctx=ctx@entry=0x8e3fed0, state=state@entry=0x8e40868, compiler_state=compiler_state@entry=0xffb5431c) at si_state_shaders.c:1792
>        sctx = 0x8e3fed0
>        key = {part = {vs = {prolog = {instance_divisor_is_one = 0, instance_divisor_is_fetched = 0, ls_vgpr_fix = 0}}, tcs = {ls_prolog = {instance_divisor_is_one = 0, instance_divisor_is_fetched = 0, ls_vgpr_fix = 0}, ls = 0x0, epilog = {prim_mode = 0, invoc0_tess_factors_are_def = 0, tes_reads_tess_factors = 0}}, gs = {vs_prolog = {instance_divisor_is_one = 0, instance_divisor_is_fetched = 0, ls_vgpr_fix = 0}, es = 0x0, prolog = {tri_strip_adj_fix = 0}}, ps = {prolog = {color_two_side = 0, flatshade_colors = 0, poly_stipple = 0, force_persp_sample_interp = 0, force_linear_sample_interp = 0, force_persp_center_interp = 0, force_linear_center_interp = 0, bc_optimize_for_persp = 0, bc_optimize_for_linear = 0, samplemask_log_ps_iter = 0}, epilog = {spi_shader_col_format = 0, color_is_int8 = 0, color_is_int10 = 0, last_cbuf = 0, alpha_func = 0, alpha_to_one = 0, poly_line_smoothing = 0, clamp_color = 0}}}, as_es = 0, as_ls = 0, mono = {vs_fix_fetch = '\000' <repeats 15 times>, u = {ff_tcs_inputs_to_copy = 0, vs_export_prim_id = 0, ps = {interpolate_at_sample_force_center = 0}}}, opt = {kill_outputs = 0, clip_disable = 0, prefer_mono = 0}}
>#9  0xf032b0b7 in si_update_shaders (sctx=0x8e3fed0) at si_state_shaders.c:3320
>        ctx = 0x8e3fed0
>        compiler_state = {tm = 0x8e4c218, debug = {async = false, debug_message = 0x0, data = 0x0}, is_debug_context = false}
>        rs = 0x8e4b8c0
>        old_clip_disable = false
>        old_ps = 0x0
>        old_spi_shader_col_format = 0
>        r = <optimized out>
>#10 0xf0323ac3 in si_draw_vbo (ctx=<optimized out>, info=<optimized out>) at si_state_draw.c:1323
>        sctx = 0x8e3fed0
>        rs = <optimized out>
>        indexbuf = 0x0
>        dirty_tex_counter = <optimized out>
>        rast_prim = <optimized out>
>        index_size = 0
>        index_offset = 0
>#11 0xf0324131 in si_draw_rectangle (blitter=0x8e0a428, vertex_elements_cso=0x8dc8d00, get_vs=0xf01a8170 <get_vs_passthrough_pos_generic>, x1=0, y1=0, x2=640, y2=480, depth=1, num_instances=1, type=UTIL_BLITTER_ATTRIB_COLOR, attrib=0xffb54498) at si_state_draw.c:1547
>        sctx = 0x8e3fed0
>        info = {index_size = 0 '\000', mode = PIPE_PRIM_MAX, primitive_restart = 0, has_user_indices = 0, vertices_per_patch = 0 '\000', start = 0, count = 3, start_instance = 0, instance_count = 1, drawid = 0, index_bias = 0, min_index = 0, max_index = 0, restart_index = 0, index = {resource = 0x0, user = 0x0}, indirect = 0x0, count_from_stream_output = 0x0}
>#12 0xf01aae68 in util_blitter_clear_custom (blitter=0x8e0a428, width=640, height=480, num_layers=1, clear_buffers=7, color=0x8ee156c, depth=1, stencil=0, custom_dsa=0x0, custom_blend=0x0) at util/u_blitter.c:1411
>        get_vs = 0xf01a8170 <get_vs_passthrough_pos_generic>
>        ctx = 0x8e0a428
>        pipe = <optimized out>
>        sr = {ref_value = "\000"}
>        attrib = {color = {0, 0, 0, 0}, texcoord = {x1 = 0, y1 = 0, x2 = 0, y2 = 0, z = -2.17094271e+29, w = -2.9037431e+29}}
>        pass_generic = true
>        type = UTIL_BLITTER_ATTRIB_COLOR
>#13 0xf01aaf83 in util_blitter_clear (blitter=<optimized out>, width=<optimized out>, height=<optimized out>, num_layers=<optimized out>, clear_buffers=<optimized out>, color=<optimized out>, depth=<optimized out>, stencil=0) at util/u_blitter.c:1428
>No locals.
>#14 0xf02eb412 in si_clear (ctx=0x8e3fed0, buffers=<optimized out>, color=0x8ee156c, depth=1, stencil=0) at si_blit.c:917
>        sctx = 0x8e3fed0
>        fb = 0x8e40368
>        zsbuf = 0x8f39e48
>        zstex = <optimized out>
>#15 0xf01d4361 in tc_call_clear (pipe=0x8e3fed0, payload=0x8ee1568) at util/u_threaded_context.c:2253
>        p = 0x8ee1568
>#16 0xf01d51cf in tc_batch_execute (thread_index=0, job=0x8ee1500) at util/u_threaded_context.c:96
>        iter = <optimized out>
>        batch = 0x1908
>        pipe = <optimized out>
>        last = <optimized out>
>#17 _tc_sync (tc=tc@entry=0x8ee1250, func=<optimized out>, info=<optimized out>) at util/u_threaded_context.c:207
>        last = <optimized out>
>        next = 0x8ee1500
>        synced = <optimized out>
>#18 0xf01d7567 in tc_texture_subdata (_pipe=0x8ee1250, resource=0x8f3b5c0, level=0, usage=0, box=0xffb546a8, data=0x8f3aef0, stride=64, layer_stride=1024) at util/u_threaded_context.c:1717
>        pipe = 0x8e3fed0
>        size = 1024
>#19 0xeffae4da in st_TexSubImage (ctx=0x8ee8e48, dims=2, texImage=<optimized out>, xoffset=0, yoffset=<optimized out>, zoffset=0, width=16, height=<optimized out>, depth=1, format=6408, type=5121, pixels=0x8f3aef0, unpack=0x8f01618) at state_tracker/st_cb_texture.c:1434
>        box = {x = 0, y = 0, z = 0, width = 16, height = 16, depth = 1}
>        stride = 64
>        layer_stride = 1024
>        data = <optimized out>
>        pipe = 0x8ee1250
>        screen = 0x8e25030
>        dst = 0x8f3b5c0
>        src = 0x0
>        src_templ = {reference = {count = 10}, screen = 0x4, width0 = 0, height0 = 10, depth0 = 0, array_size = 36864, format = 61546, target = 67, last_level = 0, nr_samples = 0, usage = 0, bind = 4026185117, flags = 150033976, next = 0x2}
>        transfer = 0x402
>        blit = {dst = {resource = 0x0, level = 0, box = {x = 16, y = 16, z = 1, width = 1, height = 1, depth = 0}, format = PIPE_FORMAT_NONE}, src = {resource = 0xa, level = 16, box = {x = 1, y = 0, z = -2185, width = -143548912, height = -28672, depth = -3990}, format = 4026432946}, mask = 3553, filter = 16, scissor_enable = 16 '\020', scissor = {minx = 1, miny = 0, maxx = 18204, maxy = 65461}, window_rectangle_include = 22 '\026', num_window_rectangles = 4290070296, window_rectangles = {{minx = 18202, miny = 65461, maxx = 16, maxy = 0}, {minx = 16, miny = 0, maxx = 1, maxy = 0}, {minx = 16, miny = 0, maxx = 3, maxy = 0}, {minx = 2, miny = 16, maxx = 1, maxy = 1}, {minx = 16, miny = 0, maxx = 32071, maxy = 61438}, {minx = 36864, miny = 61546, maxx = 40648, maxy = 2291}, {minx = 47132, miny = 61434, maxx = 22072, maxy = 2289}, {minx = 46528, miny = 2291, maxx = 40648, maxy = 2291}}, render_condition_enable = 96 '`', alpha_blend = 45 '-'}
>        src_format = <optimized out>
>        mesa_src_format = <optimized out>
>        gl_target = 3553
>        bind = <optimized out>
>        map = <optimized out>
>        dstz = 0
>        dst_level = 0
>#20 0xeffaff8c in st_TexImage (ctx=0x8ee8e48, dims=2, texImage=0x8f39ec8, format=6408, type=5121, pixels=0x8f3aef0, unpack=0x8f01618) at state_tracker/st_cb_texture.c:1651
>        unpack = 0x8f01618
>        type = 5121
>        texImage = 0x8f39ec8
>        ctx = 0x8ee8e48
>        pixels = 0x8f3aef0
>        format = 6408
>        dims = 2
>#21 0xeff2f5a5 in teximage (no_error=false, pixels=0x8f3aef0, imageSize=0, type=5121, format=6408, border=0, depth=<optimized out>, height=<optimized out>, width=<optimized out>, internalFormat=6408, level=0, target=3553, dims=2, compressed=0 '\000', ctx=0x8ee8e48) at main/teximage.c:3032
>        texImage = <optimized out>
>        func = 0xf03e420f "glTexImage"
>        unpack = 0x8f01618
>        texObj = 0x8f3b308
>        unpack_no_border = {Alignment = 110, RowLength = 0, SkipPixels = 119, SkipRows = 0, ImageHeight = -267862018, SkipImages = 2, SwapBytes = 2 '\002', LsbFirst = 0 '\000', Invert = 0 '\000', CompressedBlockWidth = -144524311, CompressedBlockHeight = -143196160, CompressedBlockDepth = -143194240, CompressedBlockSize = 2, BufferObj = 0x2}
>        texFormat = MESA_FORMAT_R8G8B8A8_UNORM
>        dimensionsOK = true
>        sizeOK = <optimized out>
>#22 teximage_err (ctx=0x8ee8e48, compressed=compressed@entry=0 '\000', dims=dims@entry=2, target=3553, level=0, internalFormat=<optimized out>, width=16, height=16, depth=1, border=<optimized out>, format=6408, type=5121, imageSize=0, pixels=0x8f3aef0) at main/teximage.c:3059
>No locals.
>#23 0xeff30f4a in _mesa_TexImage2D (target=3553, level=0, internalFormat=6408, width=16, height=16, border=0, format=6408, type=5121, pixels=0x8f3aef0) at main/teximage.c:3097
>No locals.
>#24 0x08303d5d in ?? ()
>No symbol table info available.
>#25 0x08302a5e in ?? ()
>No symbol table info available.
>#26 0x08303c2e in ?? ()
>No symbol table info available.
>#27 0x083027c4 in ?? ()
>No symbol table info available.
>#28 0x0830287f in ?? ()
>No symbol table info available.
>#29 0x082fd629 in ?? ()
>No symbol table info available.
>#30 0x081001fa in ?? ()
>No symbol table info available.
>#31 0x081be8c3 in ?? ()
>No symbol table info available.
>#32 0x082f7eda in ?? ()
>No symbol table info available.
>#33 0x0831d356 in ?? ()
>No symbol table info available.
>#34 0xf75d4276 in __libc_start_main (main=0x831d180, argc=1, argv=0xffb560b4, init=0x8351350, fini=0x83513c0, rtld_fini=0xf7f00080 <_dl_fini>, stack_end=0xffb560ac) at ../csu/libc-start.c:291
>        result = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {0, 1, -143196160, 0, 2102031365, -1391568876}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x1, 0x8051504}, data = {prev = 0x0, cleanup = 0x0, canceltype = 1}}}
>        not_first_call = <optimized out>
>#35 0x08051525 in ?? ()
>No symbol table info available.
>
>Thread 7 (Thread 0xeb108b40 (LWP 7278)):
>#0  0xf7eeedc9 in __kernel_vsyscall ()
>No symbol table info available.
>#1  0xf7b8db9b in pthread_cond_wait@@GLIBC_2.3.2 () at ../sysdeps/unix/sysv/linux/i386/pthread_cond_wait.S:187
>No locals.
>#2  0xf009209a in cnd_wait (mtx=0x8e25478, cond=0x8e25490) at ../../include/c11/threads_posix.h:155
>No locals.
>#3  util_queue_thread_func (input=<optimized out>) at u_queue.c:255
>        job = <optimized out>
>        queue = 0x8e25474
>        thread_index = <optimized out>
>#4  0xf7b8827a in start_thread (arg=0xeb108b40) at pthread_create.c:333
>        __res = <optimized out>
>        pd = 0xeb108b40
>        now = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {-138821632, 0, 4001536, -351239128, 915199020, 1720630293}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x0, 0x0}, data = {prev = 0x0, cleanup = 0x0, canceltype = 0}}}
>        not_first_call = 0
>        pagesize_m1 = <optimized out>
>        sp = <optimized out>
>        freesize = <optimized out>
>        __PRETTY_FUNCTION__ = "start_thread"
>#5  0xf76a3b56 in clone () at ../sysdeps/unix/sysv/linux/i386/clone.S:110
>No locals.
>
>Thread 6 (Thread 0xe9104b40 (LWP 7282)):
>#0  0xf7eeedc9 in __kernel_vsyscall ()
>No symbol table info available.
>#1  0xf7b8db9b in pthread_cond_wait@@GLIBC_2.3.2 () at ../sysdeps/unix/sysv/linux/i386/pthread_cond_wait.S:187
>No locals.
>#2  0xf009209a in cnd_wait (mtx=0x8e2552c, cond=0x8e25544) at ../../include/c11/threads_posix.h:155
>No locals.
>#3  util_queue_thread_func (input=<optimized out>) at u_queue.c:255
>        job = <optimized out>
>        queue = 0x8e25528
>        thread_index = <optimized out>
>#4  0xf7b8827a in start_thread (arg=0xe9104b40) at pthread_create.c:333
>        __res = <optimized out>
>        pd = 0xe9104b40
>        now = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {-138821632, 0, 4001536, -384809944, 923587624, 1720630293}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x0, 0x0}, data = {prev = 0x0, cleanup = 0x0, canceltype = 0}}}
>        not_first_call = 0
>        pagesize_m1 = <optimized out>
>        sp = <optimized out>
>        freesize = <optimized out>
>        __PRETTY_FUNCTION__ = "start_thread"
>#5  0xf76a3b56 in clone () at ../sysdeps/unix/sysv/linux/i386/clone.S:110
>No locals.
>
>Thread 5 (Thread 0xe9905b40 (LWP 7281)):
>#0  0xf7eeedc9 in __kernel_vsyscall ()
>No symbol table info available.
>#1  0xf7b8db9b in pthread_cond_wait@@GLIBC_2.3.2 () at ../sysdeps/unix/sysv/linux/i386/pthread_cond_wait.S:187
>No locals.
>#2  0xf009209a in cnd_wait (mtx=0x8e2552c, cond=0x8e25544) at ../../include/c11/threads_posix.h:155
>No locals.
>#3  util_queue_thread_func (input=<optimized out>) at u_queue.c:255
>        job = <optimized out>
>        queue = 0x8e25528
>        thread_index = <optimized out>
>#4  0xf7b8827a in start_thread (arg=0xe9905b40) at pthread_create.c:333
>        __res = <optimized out>
>        pd = 0xe9905b40
>        now = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {-138821632, 0, 4001536, -376417240, 925684777, 1720630293}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x0, 0x0}, data = {prev = 0x0, cleanup = 0x0, canceltype = 0}}}
>        not_first_call = 0
>        pagesize_m1 = <optimized out>
>        sp = <optimized out>
>        freesize = <optimized out>
>        __PRETTY_FUNCTION__ = "start_thread"
>#5  0xf76a3b56 in clone () at ../sysdeps/unix/sysv/linux/i386/clone.S:110
>No locals.
>
>Thread 4 (Thread 0xec24bb40 (LWP 7276)):
>#0  0xf7eeedc9 in __kernel_vsyscall ()
>No symbol table info available.
>#1  0xf7b8db9b in pthread_cond_wait@@GLIBC_2.3.2 () at ../sysdeps/unix/sysv/linux/i386/pthread_cond_wait.S:187
>No locals.
>#2  0xf009209a in cnd_wait (mtx=0x8e24920, cond=0x8e24938) at ../../include/c11/threads_posix.h:155
>No locals.
>#3  util_queue_thread_func (input=<optimized out>) at u_queue.c:255
>        job = <optimized out>
>        queue = 0x8e2491c
>        thread_index = <optimized out>
>#4  0xf7b8827a in start_thread (arg=0xec24bb40) at pthread_create.c:333
>        __res = <optimized out>
>        pd = 0xec24bb40
>        now = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {-138821632, 0, 4001536, -333138904, 1592579106, 1720630293}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x0, 0x0}, data = {prev = 0x0, cleanup = 0x0, canceltype = 0}}}
>        not_first_call = 0
>        pagesize_m1 = <optimized out>
>        sp = <optimized out>
>        freesize = <optimized out>
>        __PRETTY_FUNCTION__ = "start_thread"
>#5  0xf76a3b56 in clone () at ../sysdeps/unix/sysv/linux/i386/clone.S:110
>No locals.
>
>Thread 3 (Thread 0xea106b40 (LWP 7280)):
>#0  0xec96f824 in llvm::TerminatorInst::getNumSuccessors() const () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#1  0xed6b1856 in llvm::PopulateLoopsDFS<llvm::BasicBlock, llvm::Loop>::traverse(llvm::BasicBlock*) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#2  0xed6b5367 in llvm::LoopInfoBase<llvm::BasicBlock, llvm::Loop>::analyze(llvm::DominatorTreeBase<llvm::BasicBlock, false> const&) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#3  0xed6b5465 in llvm::LoopInfoWrapperPass::runOnFunction(llvm::Function&) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#4  0xec99651b in llvm::FPPassManager::runOnFunction(llvm::Function&) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#5  0xed5f4d0a in ?? () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#6  0xec996f2a in llvm::legacy::PassManagerImpl::run(llvm::Module&) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#7  0xec99710f in llvm::legacy::PassManager::run(llvm::Module&) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#8  0xec91214c in LLVMRunPassManager () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#9  0xf031689c in si_llvm_optimize_module (ctx=0xea10433c) at si_shader_tgsi_setup.c:1391
>        gallivm = 0xea105070
>        triple = <optimized out>
>        target_library_info = 0xf71ed300
>#10 0xf030bdfc in si_compile_tgsi_shader (sscreen=0x8e25030, tm=0x8e2c0e8, shader=0xe7900470, is_monolithic=false, debug=0x8f3e410) at si_shader.c:6628
>        sel = 0x8f3e400
>        ctx = {bld_base = {base = {gallivm = 0xea105070, type = {floating = 1, fixed = 0, sign = 1, norm = 0, width = 32, length = 1}, elem_type = 0xe7900aa4, vec_type = 0xe7900aa4, int_elem_type = 0xe7900b54, int_vec_type = 0xe7900b54, undef = 0xf722b790, zero = 0xf5e91300, one = 0xf5e91500}, uint_bld = {gallivm = 0xea105070, type = {floating = 0, fixed = 0, sign = 0, norm = 0, width = 32, length = 1}, elem_type = 0xe7900b54, vec_type = 0xe7900b54, int_elem_type = 0xe7900b54, int_vec_type = 0xe7900b54, undef = 0xf722aa90, zero = 0xf73702e0, one = 0xf7370220}, int_bld = {gallivm = 0xea105070, type = {floating = 0, fixed = 0, sign = 1, norm = 0, width = 32, length = 1}, elem_type = 0xe7900b54, vec_type = 0xe7900b54, int_elem_type = 0xe7900b54, int_vec_type = 0xe7900b54, undef = 0xf722aa90, zero = 0xf73702e0, one = 0xf7370220}, dbl_bld = {gallivm = 0xea105070, type = {floating = 1, fixed = 0, sign = 1, norm = 0, width = 64, length = 1}, elem_type = 0xe7900ab4, vec_type = 0xe7900ab4, int_elem_type = 0xe7900b64, int_vec_type = 0xe7900b64, undef = 0xf722b0b0, zero = 0xf5e91900, one = 0xf5e938c0}, uint64_bld = {gallivm = 0xea105070, type = {floating = 0, fixed = 0, sign = 0, norm = 0, width = 64, length = 1}, elem_type = 0xe7900b64, vec_type = 0xe7900b64, int_elem_type = 0xe7900b64, int_vec_type = 0xe7900b64, undef = 0xf722bad0, zero = 0xf7370460, one = 0xf736fca0}, int64_bld = {gallivm = 0xea105070, type = {floating = 0, fixed = 0, sign = 1, norm = 0, width = 64, length = 1}, elem_type = 0xe7900b64, vec_type = 0xe7900b64, int_elem_type = 0xe7900b64, int_vec_type = 0xe7900b64, undef = 0xf722bad0, zero = 0xf7370460, one = 0xf736fca0}, op_actions = {{fetch_args = 0x0, emit = 0xf030f380 <emit_arl>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0230da0 <mov_emit>, intr_name = 0x0}, {fetch_args = 0xf0230fc0 <lit_fetch_args>, emit = 0xf0232120 <lit_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0231b70 <rcp_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030eb30 <emit_rsq>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0230e10 <exp_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0231fe0 <log_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231bc0 <mul_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231d30 <add_emit>, intr_name = 0x0}, {fetch_args = 0xf0231120 <dp3_fetch_args>, emit = 0xf02318b0 <dp3_emit>, intr_name = 0x0}, {fetch_args = 0xf0231100 <dp4_fetch_args>, emit = 0xf0231810 <dp4_emit>, intr_name = 0x0}, {fetch_args = 0xf0231020 <dst_fetch_args>, emit = 0xf02317d0 <dst_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469356 "llvm.minnum.f32"}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469346 "llvm.maxnum.f32"}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231780 <mad_emit>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231c00 <lrp_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231780 <mad_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf046938e "llvm.sqrt.f32"}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469322 "llvm.amdgcn.ldexp.f32"}, {fetch_args = 0x0, emit = 0xf02313a0 <f2u64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231430 <f2i64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f700 <emit_frac>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469249 "llvm.floor.f32"}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469373 "llvm.rint.f32"}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469314 "llvm.exp2.f32"}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469338 "llvm.log2.f32"}, {fetch_args = 0xf02311a0 <scalar_binary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469366 "llvm.pow.f32"}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231320 <u2i64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fcff0 <clock_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231360 <i2i64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469289 "llvm.cos.f32"}, {fetch_args = 0x0, emit = 0xf02fe120 <si_llvm_emit_ddxy>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fe120 <si_llvm_emit_ddxy>, intr_name = 0x0}, {fetch_args = 0xf0231d70 <kilp_fetch_args>, emit = 0xf030ee10 <kil_emit>, intr_name = 0x0}, {fetch_args = 0xf030e6e0 <pk2h_fetch_args>, emit = 0xf030eb80 <emit_pk2h>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02313a0 <f2u64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231430 <f2i64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469381 "llvm.sin.f32"}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02311f0 <u642d_emit>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf030e6b0 <up2h_fetch_args>, emit = 0xf030e5d0 <emit_up2h>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231240 <u642f_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02312e0 <i642f_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02314b0 <arr_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231290 <i642d_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f490 <emit_ssg>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030eac0 <emit_cmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f890 <emit_fdiv>, intr_name = 0x0}, {fetch_args = 0xf0231140 <dp2_fetch_args>, emit = 0xf0231930 <dp2_emit>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0313fb0 <brk_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0314ac0 <if_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0314a60 <uif_emit>, intr_name = 0x0}, {fetch_args = 0xf02fdec0 <read_invoc_fetch_args>, emit = 0xf02fdf10 <read_lane_emit>, intr_name = 0xf04680d3 "llvm.amdgcn.readlane"}, {fetch_args = 0x0, emit = 0xf03148b0 <else_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf03140f0 <endif_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fe120 <si_llvm_emit_ddxy>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fe120 <si_llvm_emit_ddxy>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf046927b "llvm.ceil.f32"}, {fetch_args = 0x0, emit = 0xf030eee0 <emit_i2f>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ec00 <emit_not>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf046939c "llvm.trunc.f32"}, {fetch_args = 0x0, emit = 0xf030e9f0 <emit_shl>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fdfa0 <ballot_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030edd0 <emit_and>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ebc0 <emit_or>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ec90 <emit_mod>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e8b0 <emit_xor>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312b80 <txq_fetch_args>, emit = 0xf03107f0 <txq_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0313f50 <cont_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf03053d0 <si_tgsi_emit_vertex>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0301fa0 <si_llvm_emit_primitive>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0314960 <bgnloop_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0314080 <endloop_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0312a80 <si_llvm_emit_txqs>, intr_name = 0x0}, {fetch_args = 0xf0312200 <resq_fetch_args>, emit = 0xf0310700 <resq_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fdf10 <read_lane_emit>, intr_name = 0xf04680b9 "llvm.amdgcn.readfirstlane"}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f000 <emit_fcmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f000 <emit_fcmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f000 <emit_fcmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f000 <emit_fcmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030a350 <membar_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf030ed10 <kill_if_fetch_args>, emit = 0xf030ee10 <kil_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0230d90 <end_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf04692b2 "llvm.fma.f64"}, {fetch_args = 0x0, emit = 0xf030f340 <emit_f2i>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f210 <emit_idiv>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e7e0 <emit_minmax_int>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e7e0 <emit_minmax_int>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f140 <emit_ineg>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f100 <emit_ishr>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f300 <emit_f2u>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e8f0 <emit_u2f>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e9b0 <emit_uadd>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e970 <emit_udiv>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231730 <umad_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e7e0 <emit_minmax_int>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e7e0 <emit_minmax_int>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e930 <emit_umod>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231540 <umul_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e590 <emit_ushr>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0} <repeats 14 times>, {fetch_args = 0x0, emit = 0xf0230da0 <mov_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e760 <emit_ucmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f180 <emit_iabs>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f490 <emit_ssg>, intr_name = 0x0}, {fetch_args = 0xf03124e0 <load_fetch_args>, emit = 0xf03114d0 <load_emit>, intr_name = 0x0}, {fetch_args = 0xf03122e0 <store_fetch_args>, emit = 0xf03117f0 <store_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0309300 <si_llvm_emit_barrier>, intr_name = 0x0}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf049e5b6 "add"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf0406eca "swap"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf046962e "cmpswap"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf049e5d4 "and"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf049e5f2 "or"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf049e60f "xor"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf041d4d5 "umin"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf041d4fb "umax"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf0469636 "smin"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf046963b "smax"}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231b30 <imul_hi_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231af0 <umul_hi_emit>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f250 <emit_bfe>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f250 <emit_bfe>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f790 <emit_bfi>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469267 "llvm.bitreverse.i32"}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf046818c "llvm.ctpop.i32"}, {fetch_args = 0x0, emit = 0xf030ecd0 <emit_lsb>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f1d0 <emit_imsb>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ec50 <emit_umsb>, intr_name = 0x0}, {fetch_args = 0xf0302010 <interp_fetch_args>, emit = 0xf03073c0 <build_interp_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0302010 <interp_fetch_args>, emit = 0xf03073c0 <build_interp_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0302010 <interp_fetch_args>, emit = 0xf03073c0 <build_interp_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231990 <f2d_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02319d0 <d2f_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469296 "llvm.fabs.f64"}, {fetch_args = 0x0, emit = 0xf030f6c0 <emit_dneg>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231d30 <add_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231bc0 <mul_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231a80 <fmax_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231a10 <fmin_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f080 <emit_dcmp>, intr_name = 0x0}...}, rsq_action = {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, sqrt_action = {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, drsq_action = {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, dsqrt_action = {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, info = 0x8f3e564, emit_fetch_funcs = {0x0, 0xf0308480 <fetch_constant>, 0xf03150d0 <si_llvm_emit_fetch>, 0xf03150d0 <si_llvm_emit_fetch>, 0xf03150d0 <si_llvm_emit_fetch>, 0x0, 0x0, 0xf03150d0 <si_llvm_emit_fetch>, 0xf0315ee0 <fetch_system_value>, 0x0, 0x0, 0x0, 0x0, 0x0, 0x0}, emit_swizzle = 0xf0314780 <emit_swizzle>, emit_debug = 0x0, emit_store = 0xf0315800 <si_llvm_emit_store>, emit_declaration = 0xf03141f0 <emit_declaration>, emit_immediate = 0xf0313ea0 <emit_immediate>, userdata = 0x0, soa = 1 '\001', pc = -1, instructions = 0xe7944bd0, max_instructions = 256, num_instructions = 2, emit_prologue = 0x0, emit_epilogue = 0xf02fcca0 <si_tgsi_emit_epilogue>}, gallivm = {module_name = 0x0, module = 0xe7901580, engine = 0x0, target = 0x0, passmgr = 0x8ce5128, context = 0x8ce5058, builder = 0xf5e91100, memorymgr = 0x0, code = 0x0, compiled = 0}, ac = {context = 0x8ce5058, module = 0xe7901580, builder = 0xf5e91100, voidt = 0xe7900a74, i1 = 0xe7900b24, i8 = 0xe7900b34, i16 = 0xe7900b44, i32 = 0xe7900b54, i64 = 0xe7900b64, f16 = 0xe7900a94, f32 = 0xe7900aa4, f64 = 0xe7900ab4, v2i32 = 0xe7901c18, v3i32 = 0xe7901c34, v4i32 = 0xe7901c50, v2f32 = 0xe7901c6c, v4f32 = 0xe7901c88, v8i32 = 0xe7901ca4, i32_0 = 0xf73702e0, i32_1 = 0xf7370220, f32_0 = 0xf5e91300, f32_1 = 0xf5e91500, i1true = 0xf736fc00, i1false = 0xf736fbe0, range_md_kind = 4, invariant_load_md_kind = 6, uniform_md_kind = 23, fpmath_md_kind = 3, fpmath_md_2p5_ulp = 0xf736fc40, empty_md = 0xf736fc80, chip_class = VI, lds = 0x0}, shader = 0xe7900470, screen = 0x8e25030, type = 1, num_const_buffers = 0, num_shader_buffers = 0, num_images = 0, num_samplers = 0, separate_prolog = true, abi = {base_vertex = 0x0, start_instance = 0x0, draw_id = 0x0, vertex_id = 0x0, instance_id = 0x0, gs_prim_id = 0x0, gs_invocation_id = 0x0, frag_pos = {0xe7904aa8, 0xe7904ac0, 0xe7904ad8, 0xe7904af0}, front_face = 0xe7904b08, ancillary = 0xe7904b20, sample_coverage = 0xe7904b38, inputs = 0x0, emit_outputs = 0xf02fecb0 <si_llvm_return_fs_outputs>, emit_vertex = 0x0, load_ubo = 0xf02fcf70 <load_ubo>, load_ssbo = 0xf02ff7c0 <load_ssbo>, load_sampler_desc = 0x0, clamp_shadow_reference = false}, load_input = 0xf0308a00 <declare_input_fs>, input_decls = {{Declaration = {Type = 0, NrTokens = 4, File = 2, UsageMask = 15, Dimension = 0, Semantic = 1, Interpolate = 1, Invariant = 0, Local = 0, Array = 0, Atomic = 0, MemType = 0, Padding = 0}, Range = {First = 0, Last = 0}, Dim = {Index2D = 0, Padding = 0}, Interp = {Interpolate = 0, Location = 0, CylindricalWrap = 0, Padding = 0}, Semantic = {Name = 5, Index = 0, StreamX = 0, StreamY = 0, StreamZ = 0, StreamW = 0}, Image = {Resource = 0, Raw = 0, Writable = 0, Format = 0, Padding = 0}, SamplerView = {Resource = 0, ReturnTypeX = 0, ReturnTypeY = 0, ReturnTypeZ = 0, ReturnTypeW = 0}, Array = {ArrayID = 0, Padding = 0}}, {Declaration = {Type = 0, NrTokens = 0, File = 0, UsageMask = 0, Dimension = 0, Semantic = 0, Interpolate = 0, Invariant = 0, Local = 0, Array = 0, Atomic = 0, MemType = 0, Padding = 0}, Range = {First = 0, Last = 0}, Dim = {Index2D = 0, Padding = 0}, Interp = {Interpolate = 0, Location = 0, CylindricalWrap = 0, Padding = 0}, Semantic = {Name = 0, Index = 0, StreamX = 0, StreamY = 0, StreamZ = 0, StreamW = 0}, Image = {Resource = 0, Raw = 0, Writable = 0, Format = 0, Padding = 0}, SamplerView = {Resource = 0, ReturnTypeX = 0, ReturnTypeY = 0, ReturnTypeZ = 0, ReturnTypeW = 0}, Array = {ArrayID = 0, Padding = 0}} <repeats 31 times>}, inputs = {0x0 <repeats 128 times>}, outputs = {{0xf5e95f4c, 0xf5e9640c, 0xf5e9630c, 0xf5e9334c}, {0x0, 0x0, 0x0, 0x0} <repeats 127 times>}, addrs = {{0x0, 0x0, 0x0, 0x0} <repeats 16 times>}, temps = 0x0, temps_count = 0, system_values = {0x0 <repeats 11 times>}, imms = 0x0, imms_num = 0, flow = 0x0, flow_depth = 0, flow_depth_max = 0, merged_wrap_if_state = {gallivm = 0x0, condition = 0x0, entry_block = 0x0, true_block = 0x0, false_block = 0x0, merge_block = 0x0}, temp_arrays = 0x0, temp_array_allocas = 0x0, undef_alloca = 0x0, main_fn = 0xf5e14f04, return_type = 0xe7901d80, param_rw_buffers = 0, param_const_and_shader_buffers = 2, param_samplers_and_images = 3, param_bindless_samplers_and_images = 1, param_merged_wave_info = 0, param_merged_scratch_offset = 0, param_vertex_buffers = 0, param_rel_auto_id = 0, param_vs_prim_id = 0, param_vertex_index0 = 0, param_vs_state_bits = 0, param_vs_blit_inputs = 0, param_streamout_config = 0, param_streamout_write_index = 0, param_streamout_offset = {0, 0, 0, 0}, param_tcs_offchip_layout = 0, param_tcs_out_lds_offsets = 0, param_tcs_out_lds_layout = 0, param_tcs_offchip_addr_base64k = 0, param_tcs_factor_addr_base64k = 0, param_tcs_offchip_offset = 0, param_tcs_factor_offset = 0, param_tcs_patch_id = 0, param_tcs_rel_ids = 0, param_tes_u = 0, param_tes_v = 0, param_tes_rel_patch_id = 0, param_tes_patch_id = 0, param_es2gs_offset = 0, param_gs2vs_offset = 0, param_gs_wave_id = 0, gs_vtx_offset = {0x0, 0x0, 0x0, 0x0, 0x0, 0x0}, param_gs_vtx01_offset = 0, param_gs_vtx23_offset = 0, param_gs_vtx45_offset = 0, param_grid_size = 0, param_block_size = 0, param_block_id = {0, 0, 0}, param_thread_id = 0, tm = 0x8e2c0e8, range_md_kind = 0, fpmath_md_kind = 3, fpmath_md_2p5_ulp = 0xf736fc40, esgs_ring = 0x0, gsvs_ring = {0x0, 0x0, 0x0, 0x0}, invoc0_tess_factors = {0x0, 0x0, 0x0, 0x0, 0x0, 0x0}, gs_next_vertex = {0x0, 0x0, 0x0, 0x0}, postponed_kill = 0x0, return_value = 0xf5e16118, voidt = 0xe7900a74, i1 = 0xe7900b24, i8 = 0xe7900b34, i32 = 0xe7900b54, i64 = 0xe7900b64, i128 = 0xe7900b74, f32 = 0xe7900aa4, v2i32 = 0xe7901c18, v4i32 = 0xe7901c50, v4f32 = 0xe7901c88, v8i32 = 0xe7901ca4, i32_0 = 0xf73702e0, i32_1 = 0xf7370220}
>        r = -1
>#11 0xf03293ce in si_init_shader_selector_async (job=0x8f3e400, thread_index=2) at si_state_shaders.c:1884
>        shader = 0xe7900470
>        tgsi_binary = 0xe7900588
>        sel = 0x8f3e400
>        sscreen = 0x8e25030
>        tm = 0x8e2c0e8
>        debug = 0x8f3e410
>        i = <optimized out>
>#12 0xf009214b in util_queue_thread_func (input=<optimized out>) at u_queue.c:271
>        job = <optimized out>
>        queue = 0x8e25474
>        thread_index = <optimized out>
>#13 0xf7b8827a in start_thread (arg=0xea106b40) at pthread_create.c:333
>        __res = <optimized out>
>        pd = 0xea106b40
>        now = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {-138821632, 0, 4001536, -368024536, 927781934, 1720630293}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x0, 0x0}, data = {prev = 0x0, cleanup = 0x0, canceltype = 0}}}
>        not_first_call = 0
>        pagesize_m1 = <optimized out>
>        sp = <optimized out>
>        freesize = <optimized out>
>        __PRETTY_FUNCTION__ = "start_thread"
>#14 0xf76a3b56 in clone () at ../sysdeps/unix/sysv/linux/i386/clone.S:110
>No locals.
>
>Thread 2 (Thread 0xeb909b40 (LWP 7277)):
>#0  0xf7d1b858 in ?? () from /lib/i386-linux-gnu/libz.so.1
>No symbol table info available.
>#1  0xf7d1c65f in ?? () from /lib/i386-linux-gnu/libz.so.1
>No symbol table info available.
>#2  0xf7d1d3c8 in deflate () from /lib/i386-linux-gnu/libz.so.1
>No symbol table info available.
>#3  0xf008ab11 in deflate_and_write_to_disk (in_data=<optimized out>, in_data_size=4294709148, dest=dest@entry=32, filename=<optimized out>) at disk_cache.c:748
>        have = <optimized out>
>        remaining = -258148
>        out = <error reading variable out (value requires 262144 bytes, which is more than max-value-size)>
>        strm = {next_in = 0xe7b0df1c "\001\030", avail_in = 0, total_in = 3996, next_out = 0xeb8c9232 "\223`d`\270\275\363\325\\\001\006\006\006\021\006,\300\201\201\241\374\003\003\303\001(\327\005J\377'\022p\t\360\360\202Ô\314\027`f\250\023df\252\023bf\251\023ff\253\203Y\321\tÄe\361\271\371e\361I\306F\361\251\306F\ne\006:\ne\206f\n\326\n\346\256\006\006\006Æ\006\\\350*\fA*\314!*\214\200*\f1T\030\201TX@T\230", avail_out = 262142, total_out = 2, msg = 0x0, state = 0xe7e006f8, zalloc = 0xf7d27620, zfree = 0xf7d27650, opaque = 0x0, data_type = 2, adler = 2827579661, reserved = 0}
>        ret = <optimized out>
>        compressed_size = 0
>        flush = 4
>#4  0xf008b17a in cache_put (job=0xe7b0cf50, thread_index=0) at disk_cache.c:961
>        fd = <optimized out>
>        fd_final = <optimized out>
>        err = <optimized out>
>        ret = <optimized out>
>        i = <optimized out>
>        filename = 0xe7e00608 "/pool/toojays/steam/steamapps/shadercache/391540/mesa_shader_cache/b0/4f3565048437e13e8837f74819f56bb402d839"
>        filename_tmp = 0xe7e00680 "/pool/toojays/steam/steamapps/shadercache/391540/mesa_shader_cache/b0/4f3565048437e13e8837f74819f56bb402d839.tmp"
>        dc_job = 0xe7b0cf50
>        cf_data = {crc32 = 2171317959, uncompressed_size = 3996}
>        file_size = <optimized out>
>        sb = {st_dev = 3834310627626856546, __pad1 = 13360, __st_ino = 828716851, st_mode = 943220019, st_nlink = 929445683, st_uid = 959526964, st_gid = 1647719782, st_rdev = 4121700086964040802, __pad2 = 0, st_size = 200, st_blksize = 4096, st_blocks = 8, st_atim = {tv_sec = 149044624, tv_nsec = 1}, st_mtim = {tv_sec = 129, tv_nsec = -138867118}, st_ctim = {tv_sec = 0, tv_nsec = 0}, st_ino = 17850224977886429184}
>#5  0xf009214b in util_queue_thread_func (input=<optimized out>) at u_queue.c:271
>        job = <optimized out>
>        queue = 0x8e23d8c
>        thread_index = <optimized out>
>#6  0xf7b8827a in start_thread (arg=0xeb909b40) at pthread_create.c:333
>        __res = <optimized out>
>        pd = 0xeb909b40
>        now = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {-138821632, 0, 4001536, -342846424, 917296173, 1720630293}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x0, 0x0}, data = {prev = 0x0, cleanup = 0x0, canceltype = 0}}}
>        not_first_call = 0
>        pagesize_m1 = <optimized out>
>        sp = <optimized out>
>        freesize = <optimized out>
>        __PRETTY_FUNCTION__ = "start_thread"
>#7  0xf76a3b56 in clone () at ../sysdeps/unix/sysv/linux/i386/clone.S:110
>No locals.
>
>Thread 1 (Thread 0xea907b40 (LWP 7279)):
>#0  0xec97f513 in ?? () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#1  0xec84a8a7 in llvm::FoldingSetBase::FindNodeOrInsertPos(llvm::FoldingSetNodeID const&, void*&) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#2  0xec8cd44f in llvm::AttributeSetNode::get(llvm::LLVMContext&, llvm::ArrayRef<llvm::Attribute>) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#3  0xec8cdc32 in llvm::AttributeSetNode::get(llvm::LLVMContext&, llvm::AttrBuilder const&) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#4  0xec8cdc81 in llvm::AttributeSet::get(llvm::LLVMContext&, llvm::AttrBuilder const&) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#5  0xec8ce76d in llvm::AttributeList::addAttributes(llvm::LLVMContext&, unsigned int, llvm::AttrBuilder const&) const () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#6  0xec8cebcf in llvm::AttributeList::addAttribute(llvm::LLVMContext&, unsigned int, llvm::Attribute) const () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#7  0xec95150a in llvm::Function::addAttribute(unsigned int, llvm::Attribute) () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#8  0xec909850 in LLVMAddAttributeAtIndex () from /usr/lib/i386-linux-gnu/libLLVM-5.0.so.1
>No symbol table info available.
>#9  0xf021b9ca in lp_add_function_attr (function_or_call=<optimized out>, attr_idx=<optimized out>, attr=<optimized out>) at gallivm/lp_bld_intr.c:198
>        module = <optimized out>
>        ctx = <optimized out>
>        kind_id = <optimized out>
>        llvm_attr = 0xf722ab10
>#10 0xf02fe225 in si_create_function (ctx=ctx@entry=0xea90533c, name=name@entry=0xf03c4f4e "main", returns=returns@entry=0xea904c28, num_returns=0, fninfo=0xea904e68, max_workgroup_size=0) at si_shader.c:4202
>        P = 0xe7d07a80
>        i = 3
>#11 0xf0300651 in create_function (ctx=ctx@entry=0xea90533c) at si_shader.c:4712
>        shader = <optimized out>
>        fninfo = {types = {0xe7d0079c, 0xe7d007cc, 0xe7d08464, 0xe7d08464, 0xe7d083b4, 0xe7d083b4, 0xe7d083b4, 0xe7d083b4, 0xe7d083b4, 0xe7d08464, 0xe7d08464, 0xe7d08464, 0xe7d08464, 0xe7d08464, 0xe7d08464, 0xe7d08044, 0x8, 0xec815003 <llvm::APInt::tcLSB(unsigned long long const*, unsigned int)+115>, 0x1, 0x0, 0xd7402f1a, 0x2250b12d, 0xec804fa7 <llvm::detail::IEEEFloat::assign(llvm::detail::IEEEFloat const&)+7>, 0xf76e2ef5 <__memset_sse2_rep+37>, 0xefcd3ff4, 0xed558ccd, 0xea905120, 0x0, 0xec811449 <llvm::hash_code llvm::hash_combine<unsigned char, unsigned char, unsigned int, short, llvm::hash_code>(unsigned char const&, unsigned char const&, unsigned int const&, short const&, llvm::hash_code const&)+9>, 0xefcd3ff4, 0xea904f34, 0xea90501c, 0xea90512c, 0xec811d26 <llvm::detail::hash_value(llvm::detail::IEEEFloat const&)+166>, 0xea90501c, 0xea904f33, 0xea904f32, 0xee6fefcc, 0xea90512c, 0xea904f34, 0xea90512c, 0xec811ced <llvm::detail::hash_value(llvm::detail::IEEEFloat const&)+109>, 0xea904f34, 0xea905124, 0xea90512c, 0xec804c38 <llvm::detail::IEEEFloat::significandParts() const+24>, 0xea905050, 0xea90503c, 0xea90512c, 0xec80595e <llvm::detail::IEEEFloat::roundAwayFromZero(llvm::APFloatBase::roundingMode, llvm::lostFraction, unsigned int) const+174>, 0x2005040, 0x8af4e2d7, 0xea905050, 0xec80563e <llvm::detail::IEEEFloat::significandMSB() const+46>, 0xea905054, 0x1, 0xec805819 <llvm::detail::IEEEFloat::handleOverflow(llvm::APFloatBase::roundingMode)+9>, 0xefcd3ff4, 0xea905050, 0x2, 0x2, 0xec805b5d <llvm::detail::IEEEFloat::normalize(llvm::APFloatBase::roundingMode, llvm::lostFraction)+445>, 0xea905050, 0x0, 0xea905050, 0xec804c0a <llvm::detail::IEEEFloat::significandParts()+26>, 0xea905120, 0x0, 0xd7402f1a, 0x2250b12d, 0xec804bf7 <llvm::detail::IEEEFloat::significandParts()+7>, 0x0, 0xe607241e, 0x4db994be, 0xea90503c, 0x1, 0x0, 0xec805c65 <llvm::detail::IEEEFloat::IEEEFloat(llvm::fltSemantics const&, unsigned long long)+101>, 0xec804a27 <llvm::detail::IEEEFloat::freeSignificand()+7>, 0xefcd3ff4, 0xea90503c, 0xec804b18 <llvm::detail::IEEEFloat::~IEEEFloat()+24>, 0xea90503c, 0xe7d13b20, 0x8, 0xefcd3ff4, 0xea905120, 0xec804b06 <llvm::detail::IEEEFloat::~IEEEFloat()+6>, 0xefcd3ff4, 0xec804bc6, 0xea90503c, 0xea905120, 0xec8048d5 <llvm::APFloatBase::PPCDoubleDouble()+5>, 0xec804bb9, 0xd38ba671, 0xa8ba2ba4, 0xe7d13b18, 0xec8f5f8a, 0xea90503c, 0xe7d13b1c}, assign = {0x0, 0x0, 0x0, 0x0, 0x0, 0x0, 0x0, 0x0, 0x0, 0xea906144, 0xea906148, 0x0, 0x0, 0x0, 0x0, 0xea905124, 0xec821179 <llvm::hash_value(llvm::APInt const&)+9>, 0xefcd3ff4, 0x40, 0xe7d08044, 0xec821179 <llvm::hash_value(llvm::APInt const&)+9>, 0xefcd3ff4, 0x40, 0xe7d08044, 0xea9050dc, 0xec8f5d3f, 0xea90508c, 0xea905124, 0xe7d016f0, 0x0, 0x1, 0x3f, 0xe7d016f0, 0x0, 0x1, 0x3f, 0xec8f5cf9, 0xa4abacb5, 0xea905114, 0xe7d08044, 0xec8f5cf9, 0xe7d07ff8, 0xea905124, 0xe7d08044, 0xea9050dc, 0xec8f827d <llvm::ConstantInt::get(llvm::LLVMContext&, llvm::APInt const&)+45>, 0xe7d08044, 0xea905124, 0xea9050dc, 0xe7d08100, 0xe7d07e40, 0xefcd3ff4, 0xe7d01a40, 0xe7d01a20, 0xec804ba7, 0xe7d07ff8, 0xec8f8259 <llvm::ConstantInt::get(llvm::LLVMContext&, llvm::APInt const&)+9>, 0xe7d01a40, 0xea905114, 0x0, 0xec8f8259 <llvm::ConstantInt::get(llvm::LLVMContext&, llvm::APInt const&)+9>, 0xefcd3ff4, 0xea905124, 0x0, 0xe7d08464, 0xec8f84b0 <llvm::ConstantInt::get(llvm::IntegerType*, unsigned long long, bool)+96>, 0x8ce5110, 0xea905124, 0x0, 0x0, 0xea90533c, 0x0, 0x1, 0x0, 0xee6fefc8, 0x1, 0x0, 0x20, 0xea90533c, 0x4, 0xec8f8459 <llvm::ConstantInt::get(llvm::IntegerType*, unsigned long long, bool)+9>, 0xefcd3ff4, 0xea90533c, 0x4, 0xe7d083b4, 0xec907a2c <LLVMConstInt+44>, 0xe7d08464, 0x1, 0x0, 0x0, 0xe7d08464, 0xec907a08 <LLVMConstInt+8>, 0xf06a9000, 0xf03163c6 <si_llvm_context_init+950>, 0xe7d08464, 0x1, 0x0, 0x0, 0x8ce5128, 0xf762e096 <__GI___libc_free+6>}, num_sgpr_params = 9, num_params = 15}
>        returns = {0xf762a6eb <_int_free+11>, 0xefcd3ff4, 0xe7d70860, 0xf71ed100, 0xf5e14660, 0xf7770000, 0x20, 0x0, 0xe7d14698, 0x834f7c4, 0xf5e93380, 0x1, 0x0, 0x834ff7f <operator delete(void*)+15>, 0xf5e93380, 0xe7d0f558, 0xe7d6fd18, 0xedd0a388, 0xf5e93380, 0xedd090c6, 0xf762a6eb <_int_free+11>, 0xefcd3ff4, 0xe7d14118, 0xf71ed200, 0xebb223e7, 0x5e1cbccf, 0x0, 0xcf245d39, 0xed558ccd, 0x0, 0xe7d14100, 0x0, 0xe7d12868, 0x834f7c4, 0xf722acf0, 0x0, 0xf722acf0, 0xefcd3ff4, 0xea904eac, 0xefd556e8 <guard variable for llvm::hashing::detail::get_execution_seed()::seed>, 0xefd556f0 <llvm::hashing::detail::get_execution_seed()::seed>, 0xec8114cb <llvm::hash_code llvm::hash_combine<unsigned char, unsigned char, unsigned int, short, llvm::hash_code>(unsigned char const&, unsigned char const&, unsigned int const&, short const&, llvm::hash_code const&)+139>, 0xea904ce4, 0xc, 0xed558ccd, 0x0, 0xea904fb4, 0x350002, 0x0, 0xcf245d39, 0x880, 0x0, 0xe7d1f008, 0xe7d119c0, 0xf722acd0, 0x1, 0xf722acd0, 0xf7770000, 0x208, 0x0, 0xf5e14600, 0x834f7c4, 0xf722b940, 0xe7d4a728, 0xf722b940, 0x834ff7f <operator delete(void*)+15>, 0xf722b940, 0xefcd3ff4, 0x8, 0xec815003 <llvm::APInt::tcLSB(unsigned long long const*, unsigned int)+115>, 0x1, 0x0, 0xf762a139 <malloc_consolidate+9>, 0xe7d4a728, 0xec9b5147 <llvm::Pass::~Pass()+7>, 0xf76e2ef5 <__memset_sse2_rep+37>, 0xefcd3ff4, 0xed558ccd, 0xea904fb0, 0x0, 0xec811449 <llvm::hash_code llvm::hash_combine<unsigned char, unsigned char, unsigned int, short, llvm::hash_code>(unsigned char const&, unsigned char const&, unsigned int const&, short const&, llvm::hash_code const&)+9>, 0xefcd3ff4, 0xea904dc4, 0xea904eac, 0xea904fbc, 0xec811d26 <llvm::detail::hash_value(llvm::detail::IEEEFloat const&)+166>, 0xea904eac, 0xea904dc3, 0xea904dc2, 0xee6fefc0, 0xea904fbc, 0xea904dc4, 0xea904fbc, 0xec811ced <llvm::detail::hash_value(llvm::detail::IEEEFloat const&)+109>, 0xea904dc4, 0xea904fb4, 0xea904fbc, 0xec804c38 <llvm::detail::IEEEFloat::significandParts() const+24>, 0xea904ee0, 0xea904ecc, 0xea904fbc, 0xec80595e <llvm::detail::IEEEFloat::roundAwayFromZero(llvm::APFloatBase::roundingMode, llvm::lostFraction, unsigned int) const+174>, 0x2004ed0, 0xcf245d39, 0xefcd3ff4, 0xec815003 <llvm::APInt::tcLSB(unsigned long long const*, unsigned int)+115>, 0x1, 0x0, 0xec805819 <llvm::detail::IEEEFloat::handleOverflow(llvm::APFloatBase::roundingMode)+9>, 0xefcd3ff4, 0xea904ee0, 0xf76e2ef5 <__memset_sse2_rep+37>, 0xefcd3ff4, 0xec816c5a <llvm::APInt::tcShiftRight(unsigned long long*, unsigned int, unsigned int)+314>, 0xea904f4c, 0x0, 0x30c9fa77, 0x282d89d7, 0x10000, 0x8af4e2d7, 0xed558ccd, 0x0, 0xea904f40, 0x1, 0x0, 0x0, 0xec804bf7 <llvm::detail::IEEEFloat::significandParts()+7>, 0xefcd3ff4, 0xea904f40, 0xefcd3ff4, 0xea90501c, 0xefd556e8 <guard variable for llvm::hashing::detail::get_execution_seed()::seed>, 0xefd556f0 <llvm::hashing::detail::get_execution_seed()::seed>, 0xec8114cb <llvm::hash_code llvm::hash_combine<unsigned char, unsigned char, unsigned int, short, llvm::hash_code>(unsigned char const&, unsigned char const&, unsigned int const&, short const&, llvm::hash_code const&)+139>, 0xea904e54, 0xc, 0xed558ccd, 0x0, 0xea905124, 0x180002, 0x10000, 0x8af4e2d7, 0xf5e90e94, 0x1}
>        i = <optimized out>
>        num_return_sgprs = <optimized out>
>        num_returns = <optimized out>
>        num_prolog_vgprs = 2
>        type = <optimized out>
>        vs_blit_property = <optimized out>
>        v3i32 = <optimized out>
>#12 0xf0309f3b in si_compile_tgsi_main (ctx=ctx@entry=0xea90533c, is_monolithic=is_monolithic@entry=false) at si_shader.c:5788
>        shader = 0xe7d06e40
>        sel = 0x8f3f328
>        bld_base = 0xea90533c
>#13 0xf030bdb1 in si_compile_tgsi_shader (sscreen=0x8e25030, tm=0x8e2bb00, shader=0xe7d06e40, is_monolithic=false, debug=0x8f3f338) at si_shader.c:6443
>        sel = 0x8f3f328
>        ctx = {bld_base = {base = {gallivm = 0xea906070, type = {floating = 1, fixed = 0, sign = 1, norm = 0, width = 32, length = 1}, elem_type = 0xe7d083b4, vec_type = 0xe7d083b4, int_elem_type = 0xe7d08464, int_vec_type = 0xe7d08464, undef = 0xf722b7d0, zero = 0xf5e90f80, one = 0xf5e90f40}, uint_bld = {gallivm = 0xea906070, type = {floating = 0, fixed = 0, sign = 0, norm = 0, width = 32, length = 1}, elem_type = 0xe7d08464, vec_type = 0xe7d08464, int_elem_type = 0xe7d08464, int_vec_type = 0xe7d08464, undef = 0xf722b800, zero = 0xf73701e0, one = 0xf736fb00}, int_bld = {gallivm = 0xea906070, type = {floating = 0, fixed = 0, sign = 1, norm = 0, width = 32, length = 1}, elem_type = 0xe7d08464, vec_type = 0xe7d08464, int_elem_type = 0xe7d08464, int_vec_type = 0xe7d08464, undef = 0xf722b800, zero = 0xf73701e0, one = 0xf736fb00}, dbl_bld = {gallivm = 0xea906070, type = {floating = 1, fixed = 0, sign = 1, norm = 0, width = 64, length = 1}, elem_type = 0xe7d083c4, vec_type = 0xe7d083c4, int_elem_type = 0xe7d08474, int_vec_type = 0xe7d08474, undef = 0xf722a940, zero = 0xf5e90ec0, one = 0xf5e90e80}, uint64_bld = {gallivm = 0xea906070, type = {floating = 0, fixed = 0, sign = 0, norm = 0, width = 64, length = 1}, elem_type = 0xe7d08474, vec_type = 0xe7d08474, int_elem_type = 0xe7d08474, int_vec_type = 0xe7d08474, undef = 0xf722ac80, zero = 0xf736fda0, one = 0xf736fdc0}, int64_bld = {gallivm = 0xea906070, type = {floating = 0, fixed = 0, sign = 1, norm = 0, width = 64, length = 1}, elem_type = 0xe7d08474, vec_type = 0xe7d08474, int_elem_type = 0xe7d08474, int_vec_type = 0xe7d08474, undef = 0xf722ac80, zero = 0xf736fda0, one = 0xf736fdc0}, op_actions = {{fetch_args = 0x0, emit = 0xf030f380 <emit_arl>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0230da0 <mov_emit>, intr_name = 0x0}, {fetch_args = 0xf0230fc0 <lit_fetch_args>, emit = 0xf0232120 <lit_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0231b70 <rcp_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030eb30 <emit_rsq>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0230e10 <exp_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0231fe0 <log_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231bc0 <mul_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231d30 <add_emit>, intr_name = 0x0}, {fetch_args = 0xf0231120 <dp3_fetch_args>, emit = 0xf02318b0 <dp3_emit>, intr_name = 0x0}, {fetch_args = 0xf0231100 <dp4_fetch_args>, emit = 0xf0231810 <dp4_emit>, intr_name = 0x0}, {fetch_args = 0xf0231020 <dst_fetch_args>, emit = 0xf02317d0 <dst_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469356 "llvm.minnum.f32"}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469346 "llvm.maxnum.f32"}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231780 <mad_emit>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231c00 <lrp_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231780 <mad_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf046938e "llvm.sqrt.f32"}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469322 "llvm.amdgcn.ldexp.f32"}, {fetch_args = 0x0, emit = 0xf02313a0 <f2u64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231430 <f2i64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f700 <emit_frac>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469249 "llvm.floor.f32"}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469373 "llvm.rint.f32"}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469314 "llvm.exp2.f32"}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469338 "llvm.log2.f32"}, {fetch_args = 0xf02311a0 <scalar_binary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469366 "llvm.pow.f32"}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231320 <u2i64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fcff0 <clock_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231360 <i2i64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469289 "llvm.cos.f32"}, {fetch_args = 0x0, emit = 0xf02fe120 <si_llvm_emit_ddxy>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fe120 <si_llvm_emit_ddxy>, intr_name = 0x0}, {fetch_args = 0xf0231d70 <kilp_fetch_args>, emit = 0xf030ee10 <kil_emit>, intr_name = 0x0}, {fetch_args = 0xf030e6e0 <pk2h_fetch_args>, emit = 0xf030eb80 <emit_pk2h>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02313a0 <f2u64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231430 <f2i64_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469381 "llvm.sin.f32"}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ea30 <emit_set_cond>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02311f0 <u642d_emit>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf030e6b0 <up2h_fetch_args>, emit = 0xf030e5d0 <emit_up2h>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231240 <u642f_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02312e0 <i642f_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02314b0 <arr_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231290 <i642d_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f490 <emit_ssg>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030eac0 <emit_cmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f890 <emit_fdiv>, intr_name = 0x0}, {fetch_args = 0xf0231140 <dp2_fetch_args>, emit = 0xf0231930 <dp2_emit>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0313fb0 <brk_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0314ac0 <if_emit>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0xf0314a60 <uif_emit>, intr_name = 0x0}, {fetch_args = 0xf02fdec0 <read_invoc_fetch_args>, emit = 0xf02fdf10 <read_lane_emit>, intr_name = 0xf04680d3 "llvm.amdgcn.readlane"}, {fetch_args = 0x0, emit = 0xf03148b0 <else_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf03140f0 <endif_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fe120 <si_llvm_emit_ddxy>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fe120 <si_llvm_emit_ddxy>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf046927b "llvm.ceil.f32"}, {fetch_args = 0x0, emit = 0xf030eee0 <emit_i2f>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ec00 <emit_not>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf046939c "llvm.trunc.f32"}, {fetch_args = 0x0, emit = 0xf030e9f0 <emit_shl>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fdfa0 <ballot_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030edd0 <emit_and>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ebc0 <emit_or>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ec90 <emit_mod>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e8b0 <emit_xor>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312b80 <txq_fetch_args>, emit = 0xf03107f0 <txq_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0313f50 <cont_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf03053d0 <si_tgsi_emit_vertex>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0301fa0 <si_llvm_emit_primitive>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0314960 <bgnloop_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0314080 <endloop_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0312a80 <si_llvm_emit_txqs>, intr_name = 0x0}, {fetch_args = 0xf0312200 <resq_fetch_args>, emit = 0xf0310700 <resq_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02fdf10 <read_lane_emit>, intr_name = 0xf04680b9 "llvm.amdgcn.readfirstlane"}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f000 <emit_fcmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f000 <emit_fcmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f000 <emit_fcmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f000 <emit_fcmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030a350 <membar_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf030ed10 <kill_if_fetch_args>, emit = 0xf030ee10 <kil_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0230d90 <end_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf04692b2 "llvm.fma.f64"}, {fetch_args = 0x0, emit = 0xf030f340 <emit_f2i>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f210 <emit_idiv>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e7e0 <emit_minmax_int>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e7e0 <emit_minmax_int>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f140 <emit_ineg>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f100 <emit_ishr>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f300 <emit_f2u>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e8f0 <emit_u2f>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e9b0 <emit_uadd>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e970 <emit_udiv>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231730 <umad_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e7e0 <emit_minmax_int>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e7e0 <emit_minmax_int>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e930 <emit_umod>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231540 <umul_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e590 <emit_ushr>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ef20 <emit_icmp>, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0x0, intr_name = 0x0}, {fetch_args = 0xf0231160 <scalar_unary_fetch_args>, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0} <repeats 14 times>, {fetch_args = 0x0, emit = 0xf0230da0 <mov_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030e760 <emit_ucmp>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f180 <emit_iabs>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f490 <emit_ssg>, intr_name = 0x0}, {fetch_args = 0xf03124e0 <load_fetch_args>, emit = 0xf03114d0 <load_emit>, intr_name = 0x0}, {fetch_args = 0xf03122e0 <store_fetch_args>, emit = 0xf03117f0 <store_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0309300 <si_llvm_emit_barrier>, intr_name = 0x0}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf049e5b6 "add"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf0406eca "swap"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf046962e "cmpswap"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf049e5d4 "and"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf049e5f2 "or"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf049e60f "xor"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf041d4d5 "umin"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf041d4fb "umax"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf0469636 "smin"}, {fetch_args = 0xf0312040 <atomic_fetch_args>, emit = 0xf0310080 <atomic_emit>, intr_name = 0xf046963b "smax"}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231b30 <imul_hi_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231af0 <umul_hi_emit>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0312c20 <tex_fetch_args>, emit = 0xf0310a80 <build_tex_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f250 <emit_bfe>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f250 <emit_bfe>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f790 <emit_bfi>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469267 "llvm.bitreverse.i32"}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf046818c "llvm.ctpop.i32"}, {fetch_args = 0x0, emit = 0xf030ecd0 <emit_lsb>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f1d0 <emit_imsb>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030ec50 <emit_umsb>, intr_name = 0x0}, {fetch_args = 0xf0302010 <interp_fetch_args>, emit = 0xf03073c0 <build_interp_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0302010 <interp_fetch_args>, emit = 0xf03073c0 <build_interp_intrinsic>, intr_name = 0x0}, {fetch_args = 0xf0302010 <interp_fetch_args>, emit = 0xf03073c0 <build_interp_intrinsic>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231990 <f2d_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf02319d0 <d2f_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f440 <build_tgsi_intrinsic_nomem>, intr_name = 0xf0469296 "llvm.fabs.f64"}, {fetch_args = 0x0, emit = 0xf030f6c0 <emit_dneg>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231d30 <add_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231bc0 <mul_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231a80 <fmax_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf0231a10 <fmin_emit>, intr_name = 0x0}, {fetch_args = 0x0, emit = 0xf030f080 <emit_dcmp>, intr_name = 0x0}...}, rsq_action = {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, sqrt_action = {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, drsq_action = {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, dsqrt_action = {fetch_args = 0x0, emit = 0x0, intr_name = 0x0}, info = 0x8f3f48c, emit_fetch_funcs = {0x0, 0xf0308480 <fetch_constant>, 0xf03150d0 <si_llvm_emit_fetch>, 0xf03150d0 <si_llvm_emit_fetch>, 0xf03150d0 <si_llvm_emit_fetch>, 0x0, 0x0, 0xf03150d0 <si_llvm_emit_fetch>, 0xf0315ee0 <fetch_system_value>, 0x0, 0x0, 0x0, 0x0, 0x0, 0x0}, emit_swizzle = 0xf0314780 <emit_swizzle>, emit_debug = 0x0, emit_store = 0xf0315800 <si_llvm_emit_store>, emit_declaration = 0xf03141f0 <emit_declaration>, emit_immediate = 0xf0313ea0 <emit_immediate>, userdata = 0x0, soa = 1 '\001', pc = 0, instructions = 0x0, max_instructions = 0, num_instructions = 0, emit_prologue = 0x0, emit_epilogue = 0xf02fcca0 <si_tgsi_emit_epilogue>}, gallivm = {module_name = 0x0, module = 0xe7d05468, engine = 0x0, target = 0x0, passmgr = 0x0, context = 0x8ce5110, builder = 0xf5e90fc0, memorymgr = 0x0, code = 0x0, compiled = 0}, ac = {context = 0x8ce5110, module = 0xe7d05468, builder = 0xf5e90fc0, voidt = 0xe7d08384, i1 = 0xe7d08434, i8 = 0xe7d08444, i16 = 0xe7d08454, i32 = 0xe7d08464, i64 = 0xe7d08474, f16 = 0xe7d083a4, f32 = 0xe7d083b4, f64 = 0xe7d083c4, v2i32 = 0xe7d006d8, v3i32 = 0xe7d006f4, v4i32 = 0xe7d00710, v2f32 = 0xe7d0072c, v4f32 = 0xe7d00748, v8i32 = 0xe7d00764, i32_0 = 0xf73701e0, i32_1 = 0xf736fb00, f32_0 = 0xf5e90f80, f32_1 = 0xf5e90f40, i1true = 0xf736fce0, i1false = 0xf736fcc0, range_md_kind = 4, invariant_load_md_kind = 6, uniform_md_kind = 23, fpmath_md_kind = 3, fpmath_md_2p5_ulp = 0xf736fd20, empty_md = 0xf736fd60, chip_class = VI, lds = 0x0}, shader = 0xe7d06e40, screen = 0x8e25030, type = 0, num_const_buffers = 0, num_shader_buffers = 0, num_images = 0, num_samplers = 0, separate_prolog = true, abi = {base_vertex = 0x0, start_instance = 0x0, draw_id = 0x0, vertex_id = 0x0, instance_id = 0x0, gs_prim_id = 0x0, gs_invocation_id = 0x0, frag_pos = {0x0, 0x0, 0x0, 0x0}, front_face = 0x0, ancillary = 0x0, sample_coverage = 0x0, inputs = 0x0, emit_outputs = 0xf0305c00 <si_llvm_emit_vs_epilogue>, emit_vertex = 0x0, load_ubo = 0xf02fcf70 <load_ubo>, load_ssbo = 0xf02ff7c0 <load_ssbo>, load_sampler_desc = 0x0, clamp_shadow_reference = false}, load_input = 0xf0307250 <declare_input_vs>, input_decls = {{Declaration = {Type = 0, NrTokens = 0, File = 0, UsageMask = 0, Dimension = 0, Semantic = 0, Interpolate = 0, Invariant = 0, Local = 0, Array = 0, Atomic = 0, MemType = 0, Padding = 0}, Range = {First = 0, Last = 0}, Dim = {Index2D = 0, Padding = 0}, Interp = {Interpolate = 0, Location = 0, CylindricalWrap = 0, Padding = 0}, Semantic = {Name = 0, Index = 0, StreamX = 0, StreamY = 0, StreamZ = 0, StreamW = 0}, Image = {Resource = 0, Raw = 0, Writable = 0, Format = 0, Padding = 0}, SamplerView = {Resource = 0, ReturnTypeX = 0, ReturnTypeY = 0, ReturnTypeZ = 0, ReturnTypeW = 0}, Array = {ArrayID = 0, Padding = 0}} <repeats 32 times>}, inputs = {0x0 <repeats 128 times>}, outputs = {{0x0, 0x0, 0x0, 0x0} <repeats 128 times>}, addrs = {{0x0, 0x0, 0x0, 0x0} <repeats 16 times>}, temps = 0x0, temps_count = 0, system_values = {0x0 <repeats 11 times>}, imms = 0x0, imms_num = 0, flow = 0x0, flow_depth = 0, flow_depth_max = 0, merged_wrap_if_state = {gallivm = 0x0, condition = 0x0, entry_block = 0x0, true_block = 0x0, false_block = 0x0, merge_block = 0x0}, temp_arrays = 0x0, temp_array_allocas = 0x0, undef_alloca = 0x0, main_fn = 0xf5e15b04, return_type = 0xe7d08384, param_rw_buffers = 0, param_const_and_shader_buffers = 0, param_samplers_and_images = 0, param_bindless_samplers_and_images = 1, param_merged_wave_info = 0, param_merged_scratch_offset = 0, param_vertex_buffers = 0, param_rel_auto_id = 0, param_vs_prim_id = 11, param_vertex_index0 = 13, param_vs_state_bits = 0, param_vs_blit_inputs = 2, param_streamout_config = 0, param_streamout_write_index = 0, param_streamout_offset = {0, 0, 0, 0}, param_tcs_offchip_layout = 0, param_tcs_out_lds_offsets = 0, param_tcs_out_lds_layout = 0, param_tcs_offchip_addr_base64k = 0, param_tcs_factor_addr_base64k = 0, param_tcs_offchip_offset = 0, param_tcs_factor_offset = 0, param_tcs_patch_id = 0, param_tcs_rel_ids = 0, param_tes_u = 0, param_tes_v = 0, param_tes_rel_patch_id = 0, param_tes_patch_id = 0, param_es2gs_offset = 0, param_gs2vs_offset = 0, param_gs_wave_id = 0, gs_vtx_offset = {0x0, 0x0, 0x0, 0x0, 0x0, 0x0}, param_gs_vtx01_offset = 0, param_gs_vtx23_offset = 0, param_gs_vtx45_offset = 0, param_grid_size = 0, param_block_size = 0, param_block_id = {0, 0, 0}, param_thread_id = 0, tm = 0x8e2bb00, range_md_kind = 0, fpmath_md_kind = 3, fpmath_md_2p5_ulp = 0xf736fd20, esgs_ring = 0x0, gsvs_ring = {0x0, 0x0, 0x0, 0x0}, invoc0_tess_factors = {0x0, 0x0, 0x0, 0x0, 0x0, 0x0}, gs_next_vertex = {0x0, 0x0, 0x0, 0x0}, postponed_kill = 0x0, return_value = 0xf722b7a0, voidt = 0xe7d08384, i1 = 0xe7d08434, i8 = 0xe7d08444, i32 = 0xe7d08464, i64 = 0xe7d08474, i128 = 0xe7d08484, f32 = 0xe7d083b4, v2i32 = 0xe7d006d8, v4i32 = 0xe7d00710, v4f32 = 0xe7d00748, v8i32 = 0xe7d00764, i32_0 = 0xf73701e0, i32_1 = 0xf736fb00}
>        r = -1
>#14 0xf03293ce in si_init_shader_selector_async (job=0x8f3f328, thread_index=1) at si_state_shaders.c:1884
>        shader = 0xe7d06e40
>        tgsi_binary = 0xe7d074c0
>        sel = 0x8f3f328
>        sscreen = 0x8e25030
>        tm = 0x8e2bb00
>        debug = 0x8f3f338
>        i = <optimized out>
>#15 0xf009214b in util_queue_thread_func (input=<optimized out>) at u_queue.c:271
>        job = <optimized out>
>        queue = 0x8e25474
>        thread_index = <optimized out>
>#16 0xf7b8827a in start_thread (arg=0xea907b40) at pthread_create.c:333
>        __res = <optimized out>
>        pd = 0xea907b40
>        now = <optimized out>
>        unwind_buf = {cancel_jmp_buf = {{jmp_buf = {-138821632, 0, 4001536, -359631832, 929879087, 1720630293}, mask_was_saved = 0}}, priv = {pad = {0x0, 0x0, 0x0, 0x0}, data = {prev = 0x0, cleanup = 0x0, canceltype = 0}}}
>        not_first_call = 0
>        pagesize_m1 = <optimized out>
>        sp = <optimized out>
>        freesize = <optimized out>
>        __PRETTY_FUNCTION__ = "start_thread"
>#17 0xf76a3b56 in clone () at ../sysdeps/unix/sysv/linux/i386/clone.S:110
>No locals.

Actions: View

Attachments on bug 103915: 135727 | 135736 | 135784 | 136894 | 136895

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.