Home
last modified time | relevance | path

Searched refs:instance_rate_inputs (Results 1 - 13 of 13) sorted by relevance

/third_party/mesa3d/src/amd/compiler/
H A Daco_shader_info.h42 uint32_t instance_rate_inputs; member
162 uint32_t instance_rate_inputs; member
H A Daco_instruction_selection.cpp5517 if (ctx->options->key.vs.instance_rate_inputs & (1u << location)) {
12388 u_foreach_bit(i, key->state.instance_rate_inputs & attrib_mask)
12393 bool needs_vertex_index = ~key->state.instance_rate_inputs & attrib_mask;
12411 if (key->state.instance_rate_inputs & (1u << loc)) {
/third_party/mesa3d/src/amd/vulkan/
H A Dradv_aco_shader_info.h113 ASSIGN_VS_STATE_FIELD(instance_rate_inputs); in radv_aco_convert_vs_prolog_key()
142 ASSIGN_FIELD(vs.instance_rate_inputs); in radv_aco_convert_pipe_key()
H A Dradv_shader.h74 uint32_t instance_rate_inputs; member
384 uint32_t instance_rate_inputs; member
H A Dradv_cmd_buffer.c2983 radv_instance_rate_prolog_index(unsigned num_attributes, uint32_t instance_rate_inputs) in radv_instance_rate_prolog_index() argument
3003 unsigned count = util_bitcount(instance_rate_inputs); in radv_instance_rate_prolog_index()
3007 unsigned first = ffs(instance_rate_inputs) - 1; in radv_instance_rate_prolog_index()
3019 uint32_t instance_rate_inputs : 1; member
3068 uint32_t instance_rate_inputs = state->instance_rate_inputs & attribute_mask; in lookup_vs_prolog() local
3093 (!vs_shader->info.vs.as_ls || !instance_rate_inputs) && in lookup_vs_prolog()
3095 if (!instance_rate_inputs) { in lookup_vs_prolog()
3098 util_bitcount(instance_rate_inputs) == in lookup_vs_prolog()
3099 (util_last_bit(instance_rate_inputs) in lookup_vs_prolog()
[all...]
H A Dradv_shader_info.c254 if (key->vs.instance_rate_inputs & (1u << attrib_index)) { in gather_info_input_decl_vs()
H A Dradv_private.h1710 unsigned radv_instance_rate_prolog_index(unsigned num_attributes, uint32_t instance_rate_inputs);
1950 uint32_t instance_rate_inputs;
H A Dradv_shader.c1301 if (pl_key->vs.instance_rate_inputs) in radv_lower_ngg()
1341 pl_key->vs.instance_rate_inputs); in radv_lower_ngg()
H A Dradv_nir_to_llvm.c406 if (ctx->options->key.vs.instance_rate_inputs & (1u << attrib_index)) { in load_vs_input()
H A Dradv_pipeline.c1537 info.instance_rate_inputs |= 1u << location; in radv_pipeline_init_vertex_input_info()
3318 key.vs.instance_rate_inputs = info->vi.instance_rate_inputs; in radv_generate_graphics_pipeline_key()
H A Dradv_device.c2993 state.instance_rate_inputs = 0; in radv_device_init_vs_prologs()
3011 state.instance_rate_inputs = u_bit_consecutive(start, count); in radv_device_init_vs_prologs()
3020 radv_instance_rate_prolog_index(num_attributes, state.instance_rate_inputs)); in radv_device_init_vs_prologs()
/third_party/mesa3d/src/amd/common/
H A Dac_nir.h131 uint32_t instance_rate_inputs);
H A Dac_nir_lower_ngg.c67 uint32_t instance_rate_inputs; member
720 if (state->instance_rate_inputs & in cleanup_culling_shader_after_dce()
1375 uint32_t instance_rate_inputs) in ac_nir_lower_ngg_nogs()
1403 .instance_rate_inputs = instance_rate_inputs, in ac_nir_lower_ngg_nogs()
1362 ac_nir_lower_ngg_nogs(nir_shader *shader, enum radeon_family family, unsigned max_num_es_vertices, unsigned num_vertices_per_primitives, unsigned max_workgroup_size, unsigned wave_size, bool can_cull, bool early_prim_export, bool passthrough, bool export_prim_id, bool provoking_vtx_last, bool use_edgeflags, bool has_prim_query, uint32_t instance_rate_inputs) ac_nir_lower_ngg_nogs() argument

Completed in 64 milliseconds