• Home
  • Raw
  • Download

Lines Matching full:simd

51                         unsigned simd,  in brw_simd_should_compile()  argument
58 assert(!test_bit(prog_data->prog_mask, simd)); in brw_simd_should_compile()
61 const unsigned width = 8u << simd; in brw_simd_should_compile()
69 if (test_bit(prog_data->prog_spilled, simd)) { in brw_simd_should_compile()
71 mem_ctx, "SIMD%u skipped because would spill", width); in brw_simd_should_compile()
83 mem_ctx, "SIMD%u skipped because required dispatch width is %u", in brw_simd_should_compile()
88 if (simd > 0 && test_bit(prog_data->prog_mask, simd - 1) && in brw_simd_should_compile()
91 mem_ctx, "SIMD%u skipped because workgroup size %u already fits in SIMD%u", in brw_simd_should_compile()
98 mem_ctx, "SIMD%u can't fit all %u invocations in %u threads", in brw_simd_should_compile()
122 if (unlikely(env_skip[simd])) { in brw_simd_should_compile()
124 mem_ctx, "SIMD%u skipped because INTEL_DEBUG=no%u", in brw_simd_should_compile()
133 brw_simd_mark_compiled(unsigned simd, struct brw_cs_prog_data *prog_data, bool spilled) in brw_simd_mark_compiled() argument
135 assert(!test_bit(prog_data->prog_mask, simd)); in brw_simd_mark_compiled()
137 prog_data->prog_mask |= 1u << simd; in brw_simd_mark_compiled()
139 /* If a SIMD spilled, all the larger ones would spill too. */ in brw_simd_mark_compiled()
141 for (unsigned i = simd; i < 3; i++) in brw_simd_mark_compiled()
186 for (unsigned simd = 0; simd < 3; simd++) { in brw_simd_select_for_workgroup_size() local
190 if (brw_simd_should_compile(mem_ctx, simd, devinfo, &cloned, in brw_simd_select_for_workgroup_size()
191 0 /* required_dispatch_width */, &error[simd]) && in brw_simd_select_for_workgroup_size()
192 test_bit(prog_data->prog_mask, simd)) { in brw_simd_select_for_workgroup_size()
193 brw_simd_mark_compiled(simd, &cloned, test_bit(prog_data->prog_spilled, simd)); in brw_simd_select_for_workgroup_size()