Home
last modified time | relevance | path

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

/external/mesa3d/src/intel/compiler/elk/
Delk_simd_selection.cpp164 cs_prog_data->prog_mask |= 1u << simd; in elk_simd_mark_compiled()
206 simd_state.compiled[i] = test_bit(prog_data->prog_mask, i); in elk_simd_select_for_workgroup_size()
217 cloned.prog_mask = 0; in elk_simd_select_for_workgroup_size()
230 test_bit(prog_data->prog_mask, simd)) { in elk_simd_select_for_workgroup_size()
Delk_test_simd_selection.cpp144 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD16 | 1u << SIMD32); in TEST_F()
169 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD16 | 1u << SIMD32); in TEST_F()
193 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD16 | 1u << SIMD32); in TEST_F()
217 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD32); in TEST_F()
240 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD32); in TEST_F()
Delk_compiler.h1111 unsigned prog_mask; member
1141 assert(prog_data->prog_mask & (1 << index)); in elk_cs_prog_data_prog_offset()
Delk_fs.cpp7108 prog_data->prog_mask = 1 << selected_simd; in elk_compile_cs()
7121 uint32_t max_dispatch_width = 8u << (util_last_bit(prog_data->prog_mask) - 1); in elk_compile_cs()
7125 if (prog_data->prog_mask & (1u << simd)) { in elk_compile_cs()
/external/mesa3d/src/intel/compiler/
Dbrw_simd_selection.cpp204 cs_prog_data->prog_mask |= 1u << simd; in brw_simd_mark_compiled()
246 simd_state.compiled[i] = test_bit(prog_data->prog_mask, i); in brw_simd_select_for_workgroup_size()
257 cloned.prog_mask = 0; in brw_simd_select_for_workgroup_size()
270 test_bit(prog_data->prog_mask, simd)) { in brw_simd_select_for_workgroup_size()
Dtest_simd_selection.cpp144 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD16 | 1u << SIMD32); in TEST_F()
169 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD16 | 1u << SIMD32); in TEST_F()
193 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD16 | 1u << SIMD32); in TEST_F()
217 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD8 | 1u << SIMD32); in TEST_F()
240 ASSERT_EQ(prog_data->prog_mask, 1u << SIMD32); in TEST_F()
Dbrw_compile_cs.cpp229 prog_data->prog_mask = 1 << selected_simd; in brw_compile_cs()
242 uint32_t max_dispatch_width = 8u << (util_last_bit(prog_data->prog_mask) - 1); in brw_compile_cs()
246 if (prog_data->prog_mask & (1u << simd)) { in brw_compile_cs()
Dbrw_compile_mesh.cpp397 if (prog_data->base.prog_mask) { in brw_compile_task()
398 unsigned first = ffs(prog_data->base.prog_mask) - 1; in brw_compile_task()
421 prog_data->base.prog_mask = 1 << selected_simd; in brw_compile_task()
1706 if (prog_data->base.prog_mask) { in brw_compile_mesh()
1707 unsigned first = ffs(prog_data->base.prog_mask) - 1; in brw_compile_mesh()
1730 prog_data->base.prog_mask = 1 << selected_simd; in brw_compile_mesh()
Dbrw_compiler.h872 unsigned prog_mask; member
902 assert(prog_data->prog_mask & (1 << index)); in brw_cs_prog_data_prog_offset()
Dintel_clc.c185 PROG_DATA_FIELD("%u", prog_mask); in print_cs_prog_data_fields()
/external/mesa3d/src/gallium/drivers/iris/
Diris_context.h376 unsigned prog_mask; member
394 assert(prog_data->prog_mask & (1 << index)); in iris_cs_data_prog_offset()
Diris_program.c154 iris->prog_mask = brw->prog_mask; in iris_apply_brw_cs_prog_data()
354 iris->prog_mask = elk->prog_mask; in iris_apply_elk_cs_prog_data()