Lines Matching refs:info
1776 nir->info.inputs_read & ~nir->info.per_primitive_inputs;
1784 if (nir->info.per_primitive_inputs) {
1786 nir->info.inputs_read & nir->info.per_primitive_inputs;
1913 nir->info.separate_shader, 1);
1955 * See compile_sf_prog() for more info.
2105 8 * vue_prog_data->urb_read_length * nir->info.gs.vertices_in;
3497 unsigned execution_mode = this->nir->info.float_controls_execution_mode;
5933 if (nir->info.outputs_written & BITFIELD64_BIT(FRAG_RESULT_DEPTH)) {
5970 payload.num_regs += nir->info.gs.vertices_in;
5981 if (8 * vue_prog_data->urb_read_length * nir->info.gs.vertices_in >
5984 ROUND_DOWN_TO(max_push_components / nir->info.gs.vertices_in, 8) / 8;
6054 stage_abbrev, dispatch_width, nir->info.name, iteration, pass_num); \
6068 stage_abbrev, dispatch_width, nir->info.name);
6731 (nir->info.tess.tcs_vertices_out % 8) != 0;
6736 brw_imm_ud(nir->info.tess.tcs_vertices_out), BRW_CONDITIONAL_L);
6892 if (nir->info.inputs_read > 0 ||
6893 BITSET_TEST(nir->info.system_values_read, SYSTEM_VALUE_FRAG_COORD) ||
6894 (nir->info.outputs_read > 0 && !wm_key->coherent_fb_fetch)) {
6916 if (nir->info.writes_memory)
7205 if (shader->info.outputs_written & BITFIELD64_BIT(FRAG_RESULT_DEPTH)) {
7206 switch (shader->info.fs.depth_layout) {
7306 prog_data->uses_kill = shader->info.fs.uses_discard ||
7307 shader->info.fs.uses_demote ||
7310 (shader->info.outputs_written & BITFIELD64_BIT(FRAG_RESULT_SAMPLE_MASK));
7314 shader->info.outputs_written & BITFIELD64_BIT(FRAG_RESULT_STENCIL);
7319 shader->info.fs.uses_sample_shading);
7323 BITSET_TEST(shader->info.system_values_read, SYSTEM_VALUE_SAMPLE_MASK_IN);
7335 (BITSET_TEST(shader->info.system_values_read,
7337 BITSET_TEST(shader->info.system_values_read,
7341 prog_data->has_render_target_reads = shader->info.outputs_read != 0ull;
7343 prog_data->early_fragment_tests = shader->info.fs.early_fragment_tests;
7344 prog_data->post_depth_coverage = shader->info.fs.post_depth_coverage;
7345 prog_data->inner_coverage = shader->info.fs.inner_coverage;
7357 !shader->info.fs.uses_sample_shading &&
7367 shader->info.fs.needs_quad_helper_invocations ||
7368 shader->info.fs.needs_all_helper_invocations ||
7372 BITSET_TEST(shader->info.system_values_read, SYSTEM_VALUE_FRAG_COORD);
7374 BITSET_TEST(shader->info.system_values_read, SYSTEM_VALUE_FRAG_COORD) &&
7377 BITSET_TEST(shader->info.system_values_read, SYSTEM_VALUE_FRAG_COORD) &&
7408 prog_data->base.ray_queries = nir->info.ray_queries;
7482 if (nir->info.ray_queries > 0)
7598 nir->info.label ?
7599 nir->info.label : "unnamed",
7600 nir->info.name));
7745 if (!b->shader->info.workgroup_size_variable) {
7746 unsigned local_workgroup_size = b->shader->info.workgroup_size[0] *
7747 b->shader->info.workgroup_size[1] *
7748 b->shader->info.workgroup_size[2];
7779 prog_data->base.total_shared = nir->info.shared_size;
7780 prog_data->base.ray_queries = nir->info.ray_queries;
7783 if (!nir->info.workgroup_size_variable) {
7784 prog_data->local_size[0] = nir->info.workgroup_size[0];
7785 prog_data->local_size[1] = nir->info.workgroup_size[1];
7786 prog_data->local_size[2] = nir->info.workgroup_size[2];
7790 brw_required_dispatch_width(&nir->info);
7825 nir->info.workgroup_size_variable;
7854 if (!nir->info.workgroup_size_variable)
7863 nir->info.label ?
7864 nir->info.label : "unnamed",
7865 nir->info.name);
7896 struct brw_cs_dispatch_info info = {};
7907 info.group_size = sizes[0] * sizes[1] * sizes[2];
7908 info.simd_size = 8u << simd;
7909 info.threads = DIV_ROUND_UP(info.group_size, info.simd_size);
7911 const uint32_t remainder = info.group_size & (info.simd_size - 1);
7913 info.right_mask = ~0u >> (32 - remainder);
7915 info.right_mask = ~0u >> (32 - info.simd_size);
7917 return info;
7933 prog_data->base.stage = shader->info.stage;
8039 prog_data->base.stage = shader->info.stage;
8040 prog_data->base.ray_queries = shader->info.ray_queries;
8046 false, shader->info.stage);
8049 shader->info.label ?
8050 shader->info.label : "unnamed",
8051 gl_shader_stage_name(shader->info.stage),
8052 shader->info.name);
8067 shader->info.label ?
8068 shader->info.label : "unnamed",
8069 gl_shader_stage_name(shader->info.stage),
8070 i, shader->info.name);