Lines Matching defs:info
1355 gs_state_nodes[0] = dxil_get_metadata_int32(&ctx->mod, dxil_get_input_primitive(s->info.gs.input_primitive));
1356 gs_state_nodes[1] = dxil_get_metadata_int32(&ctx->mod, s->info.gs.vertices_out);
1357 gs_state_nodes[2] = dxil_get_metadata_int32(&ctx->mod, MAX2(s->info.gs.active_stream_mask, 1));
1358 gs_state_nodes[3] = dxil_get_metadata_int32(&ctx->mod, dxil_get_primitive_topology(s->info.gs.output_primitive));
1359 gs_state_nodes[4] = dxil_get_metadata_int32(&ctx->mod, s->info.gs.invocations);
1396 get_tessellator_output_primitive(const struct shader_info *info)
1398 if (info->tess.point_mode)
1400 if (info->tess._primitive_mode == TESS_PRIMITIVE_ISOLINES)
1405 if (info->tess.ccw)
1417 hs_state_nodes[2] = dxil_get_metadata_int32(&ctx->mod, ctx->shader->info.tess.tcs_vertices_out);
1418 hs_state_nodes[3] = dxil_get_metadata_int32(&ctx->mod, get_tessellator_domain(ctx->shader->info.tess._primitive_mode));
1419 hs_state_nodes[4] = dxil_get_metadata_int32(&ctx->mod, get_tessellator_partitioning(ctx->shader->info.tess.spacing));
1420 hs_state_nodes[5] = dxil_get_metadata_int32(&ctx->mod, get_tessellator_output_primitive(&ctx->shader->info));
1431 ds_state_nodes[0] = dxil_get_metadata_int32(&ctx->mod, get_tessellator_domain(ctx->shader->info.tess._primitive_mode));
1432 ds_state_nodes[1] = dxil_get_metadata_int32(&ctx->mod, ctx->shader->info.tess.tcs_vertices_out);
1441 const struct dxil_mdnode *threads_x = dxil_get_metadata_int32(&ctx->mod, MAX2(s->info.workgroup_size[0], 1));
1442 const struct dxil_mdnode *threads_y = dxil_get_metadata_int32(&ctx->mod, MAX2(s->info.workgroup_size[1], 1));
1443 const struct dxil_mdnode *threads_z = dxil_get_metadata_int32(&ctx->mod, MAX2(s->info.workgroup_size[2], 1));
1462 if (ctx->shader->info.stage == MESA_SHADER_FRAGMENT &&
1463 ctx->shader->info.fs.early_fragment_tests)
1984 const nir_op_info *info = &nir_op_infos[alu->op];
1988 if (is_double(info->output_type, nir_dest_bit_size(alu->dest.dest)))
1993 if (is_double(info->input_types[0], nir_src_bit_size(alu->src[0].src)))
2038 const nir_op_info *info = &nir_op_infos[alu->op];
2040 enum overload_type overload = get_overload(info->input_types[0], src_bits);
2054 const nir_op_info *info = &nir_op_infos[alu->op];
2055 assert(info->output_type == info->input_types[0]);
2056 assert(info->output_type == info->input_types[1]);
2060 enum overload_type overload = get_overload(info->output_type, dst_bits);
2077 const nir_op_info *info = &nir_op_infos[alu->op];
2083 assert(get_overload(info->output_type, dst_bits) == get_overload(info->input_types[0], dst_bits));
2084 assert(get_overload(info->output_type, dst_bits) == get_overload(info->input_types[1], dst_bits));
2085 assert(get_overload(info->output_type, dst_bits) == get_overload(info->input_types[2], dst_bits));
2087 enum overload_type overload = get_overload(info->output_type, dst_bits);
2738 if (ctx->mod.info.has_per_sample_input) {
2763 unsigned num_coords = ctx->shader->info.tess._primitive_mode == TESS_PRIMITIVE_TRIANGLES ? 3 : 2;
4200 assert(ctx->mod.info.has_per_sample_input ||
4203 if (ctx->mod.info.has_per_sample_input)
5234 if (ctx->shader->info.num_ubos) {
5238 unsigned ubo1_array_size = ctx->shader->info.num_ubos -
5248 !emit_cbv(ctx, ctx->shader->info.num_ubos - 1, 0, ubo_size, 1, "__ubo_state_vars"))
5423 if (ctx->shader->info.shared_size && shader_has_shared_ops(ctx->shader)) {
5437 size = ALIGN_POT(ctx->shader->info.shared_size, sizeof(uint32_t));
5448 if (ctx->shader->info.stage == MESA_SHADER_KERNEL) {
5472 for (unsigned i = 0; i < ctx->shader->info.num_ssbos; ++i) {
5484 if (ctx->shader->info.num_ssbos &&
5485 !emit_uav(ctx, 0, 2, ctx->shader->info.num_ssbos, DXIL_COMP_TYPE_INVALID,
5499 ctx->mod.info.has_per_sample_input =
5500 BITSET_TEST(ctx->shader->info.system_values_read, SYSTEM_VALUE_SAMPLE_ID);
5501 if (!ctx->mod.info.has_per_sample_input && ctx->shader->info.stage == MESA_SHADER_FRAGMENT) {
5504 ctx->mod.info.has_per_sample_input = true;
5511 ctx->shader->info.clip_distance_array_size : ctx->opts->input_clip_size;
5519 if (ctx->shader->info.stage == MESA_SHADER_FRAGMENT) {
5525 } else if (ctx->shader->info.stage == MESA_SHADER_VERTEX ||
5526 ctx->shader->info.stage == MESA_SHADER_TESS_EVAL) {
5527 if (ctx->shader->info.outputs_written &
5542 switch (s->info.stage) {
5643 state->state.psv1.psv0.vs.output_position_present = ctx->mod.info.has_out_position;
5647 state->state.psv1.psv0.ps.depth_output = ctx->mod.info.has_out_depth;
5649 ctx->mod.info.has_per_sample_input;
5652 state->state.num_threads_x = MAX2(ctx->shader->info.workgroup_size[0], 1);
5653 state->state.num_threads_y = MAX2(ctx->shader->info.workgroup_size[1], 1);
5654 state->state.num_threads_z = MAX2(ctx->shader->info.workgroup_size[2], 1);
5657 state->state.psv1.max_vertex_count = ctx->shader->info.gs.vertices_out;
5658 state->state.psv1.psv0.gs.input_primitive = dxil_get_input_primitive(ctx->shader->info.gs.input_primitive);
5659 state->state.psv1.psv0.gs.output_toplology = dxil_get_primitive_topology(ctx->shader->info.gs.output_primitive);
5660 state->state.psv1.psv0.gs.output_stream_mask = MAX2(ctx->shader->info.gs.active_stream_mask, 1);
5661 state->state.psv1.psv0.gs.output_position_present = ctx->mod.info.has_out_position;
5665 state->state.psv1.psv0.hs.output_control_point_count = ctx->shader->info.tess.tcs_vertices_out;
5666 state->state.psv1.psv0.hs.tessellator_domain = get_tessellator_domain(ctx->shader->info.tess._primitive_mode);
5667 state->state.psv1.psv0.hs.tessellator_output_primitive = get_tessellator_output_primitive(&ctx->shader->info);
5671 state->state.psv1.psv0.ds.input_control_point_count = ctx->shader->info.tess.tcs_vertices_out;
5672 state->state.psv1.psv0.ds.tessellator_domain = get_tessellator_domain(ctx->shader->info.tess._primitive_mode);
5673 state->state.psv1.psv0.ds.output_position_present = ctx->mod.info.has_out_position;
5745 if (ctx->shader->info.stage == MESA_SHADER_FRAGMENT &&
5746 ctx->shader->info.inputs_read &&
5747 !BITSET_TEST(ctx->shader->info.system_values_read, SYSTEM_VALUE_SAMPLE_ID)) {
5764 BITSET_SET(ctx->shader->info.system_values_read, SYSTEM_VALUE_SAMPLE_ID);
5768 struct sysvalue_name *info = &possible_sysvalues[i];
5769 if (info->only_in_shader != MESA_SHADER_NONE &&
5770 info->only_in_shader != ctx->shader->info.stage)
5772 if (BITSET_TEST(ctx->shader->info.system_values_read, info->value)) {
5773 if (!append_input_or_sysvalue(ctx, info->slot,
5774 info->value, info->name,
5853 if (s->info.stage <= MESA_SHADER_FRAGMENT) {
5855 s->info.stage == MESA_SHADER_VERTEX ?
5858 s->info.stage == MESA_SHADER_FRAGMENT ?