81 brw_simd_should_compile(brw_simd_selection_state &state, unsigned simd)  in brw_simd_should_compile()  argument
83    assert(simd < SIMD_COUNT);  in brw_simd_should_compile()
84    assert(!state.compiled[simd]);  in brw_simd_should_compile()
88    const unsigned width = 8u << simd;  in brw_simd_should_compile()
91       state.error[simd] = "Different than required dispatch width";  in brw_simd_should_compile()
102       if (state.spilled[simd]) {  in brw_simd_should_compile()
103          state.error[simd] = "Would spill";  in brw_simd_should_compile()
115          if (simd > min_simd && workgroup_size <= (width / 2)) {  in brw_simd_should_compile()
116             state.error[simd] = "Workgroup size already fits in smaller SIMD";  in brw_simd_should_compile()
121             state.error[simd] = "Would need more than max_threads to fit all invocations";  in brw_simd_should_compile()
132             state.error[simd] = "SIMD32 not required (use INTEL_DEBUG=do32 to force)";  in brw_simd_should_compile()
139       state.error[simd] = "SIMD8 not supported on Xe2+";  in brw_simd_should_compile()
144       state.error[simd] = "Ray queries not supported";  in brw_simd_should_compile()
149       state.error[simd] = "Bindless shader calls not supported";  in brw_simd_should_compile()
184    if (unlikely(env_skip[simd])) {  in brw_simd_should_compile()
185       state.error[simd] = "Disabled by INTEL_DEBUG environment variable";  in brw_simd_should_compile()
193 brw_simd_mark_compiled(brw_simd_selection_state &state, unsigned simd, bool spilled)  in brw_simd_mark_compiled()  argument
195    assert(simd < SIMD_COUNT);  in brw_simd_mark_compiled()
196    assert(!state.compiled[simd]);  in brw_simd_mark_compiled()
200    state.compiled[simd] = true;  in brw_simd_mark_compiled()
202       cs_prog_data->prog_mask |= 1u << simd;  in brw_simd_mark_compiled()
204    /* If a SIMD spilled, all the larger ones would spill too. */  in brw_simd_mark_compiled()
206       for (unsigned i = simd; i < SIMD_COUNT; i++) {  in brw_simd_mark_compiled()
263    for (unsigned simd = 0; simd < SIMD_COUNT; simd++) {  in brw_simd_select_for_workgroup_size()  local
267       if (brw_simd_should_compile(simd_state, simd) &&  in brw_simd_select_for_workgroup_size()
268           test_bit(prog_data->prog_mask, simd)) {  in brw_simd_select_for_workgroup_size()
269          brw_simd_mark_compiled(simd_state, simd, test_bit(prog_data->prog_spilled, simd));  in brw_simd_select_for_workgroup_size()