Home
last modified time | relevance | path

Searched refs:prog_mask (Results 1 – 6 of 6) sorted by relevance

/third_party/mesa3d/src/intel/compiler/
Dbrw_simd_selection.c58 assert(!test_bit(prog_data->prog_mask, simd)); in brw_simd_should_compile()
88 if (simd > 0 && test_bit(prog_data->prog_mask, simd - 1) && in brw_simd_should_compile()
108 if (!INTEL_DEBUG(DEBUG_DO32) && prog_data->prog_mask) { in brw_simd_should_compile()
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()
149 assert((prog_data->prog_mask & ~0x7u) == 0); in brw_simd_select()
151 prog_data->prog_mask & ~prog_data->prog_spilled; in brw_simd_select()
157 else if (prog_data->prog_mask) in brw_simd_select()
158 return ffs(prog_data->prog_mask) - 1; in brw_simd_select()
181 cloned.prog_mask = 0; in brw_simd_select_for_workgroup_size()
[all …]
Dtest_simd_selection.cpp145 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD16 | 1u << SIMD32); in TEST_F()
170 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD16 | 1u << SIMD32); in TEST_F()
194 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD16 | 1u << SIMD32); in TEST_F()
218 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD32); in TEST_F()
241 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD32); in TEST_F()
Dbrw_mesh.cpp247 if (prog_data->base.prog_mask) { in brw_compile_task()
248 unsigned first = ffs(prog_data->base.prog_mask) - 1; in brw_compile_task()
252 const bool allow_spilling = !prog_data->base.prog_mask; in brw_compile_task()
268 prog_data->base.prog_mask = 1 << selected_simd; in brw_compile_task()
760 if (prog_data->base.prog_mask) { in brw_compile_mesh()
761 unsigned first = ffs(prog_data->base.prog_mask) - 1; in brw_compile_mesh()
765 const bool allow_spilling = !prog_data->base.prog_mask; in brw_compile_mesh()
781 prog_data->base.prog_mask = 1 << selected_simd; in brw_compile_mesh()
Dbrw_compiler.h1059 unsigned prog_mask; member
1091 assert(prog_data->prog_mask & (1 << index)); in brw_cs_prog_data_prog_offset()
Dintel_clc.c166 PROG_DATA_FIELD("%u", prog_mask); in print_cs_prog_data_fields()
Dbrw_fs.cpp7819 if (prog_data->prog_mask) { in brw_compile_cs()
7820 unsigned first = ffs(prog_data->prog_mask) - 1; in brw_compile_cs()
7824 const bool allow_spilling = !prog_data->prog_mask || in brw_compile_cs()
7855 prog_data->prog_mask = 1 << selected_simd; in brw_compile_cs()
7871 if (prog_data->prog_mask & (1u << simd)) { in brw_compile_cs()