/third_party/mesa3d/src/compiler/glsl/ |
H A D | ir_clone.cpp | 31 ir_rvalue::clone(void *mem_ctx, struct hash_table *) const in clone() argument 34 return error_value(mem_ctx); in clone() 41 ir_variable::clone(void *mem_ctx, struct hash_table *ht) const in clone() argument 43 ir_variable *var = new(mem_ctx) ir_variable(this->type, this->name, in clone() 63 var->constant_value = this->constant_value->clone(mem_ctx, ht); in clone() 67 this->constant_initializer->clone(mem_ctx, ht); in clone() 78 ir_swizzle::clone(void *mem_ctx, struct hash_table *ht) const in clone() argument 80 return new(mem_ctx) ir_swizzle(this->val->clone(mem_ctx, ht), this->mask); in clone() 84 ir_return::clone(void *mem_ctx, struc argument 95 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 106 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 112 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 120 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 136 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 148 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 164 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 178 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 193 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 201 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 211 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 260 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 268 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 293 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 310 clone_prototype(void *mem_ctx, struct hash_table *ht) const clone_prototype() argument 332 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 420 clone_ir_list(void *mem_ctx, exec_list *out, const exec_list *in) clone_ir_list() argument [all...] |
H A D | lower_mat_op_to_vec.cpp | 45 this->mem_ctx = NULL; in ir_mat_op_to_vec_visitor() 64 void *mem_ctx; member in __anon7189::ir_mat_op_to_vec_visitor 108 return new(mem_ctx) ir_swizzle(val, row, 0, 0, 0, 1); in get_element() 114 val = val->clone(mem_ctx, NULL); in get_column() 117 val = new(mem_ctx) ir_dereference_array(val, in get_column() 118 new(mem_ctx) ir_constant(row)); in get_column() 135 expr = new(mem_ctx) ir_expression(ir_binop_mul, in do_mul_mat_mat() 143 mul_expr = new(mem_ctx) ir_expression(ir_binop_mul, in do_mul_mat_mat() 146 expr = new(mem_ctx) ir_expression(ir_binop_add, in do_mul_mat_mat() 151 assign = new(mem_ctx) ir_assignmen in do_mul_mat_mat() [all...] |
H A D | builtin_int64.h | 2 udivmod64(void *mem_ctx, builtin_available_predicate avail) in udivmod64() argument 5 new(mem_ctx) ir_function_signature(glsl_type::uvec4_type, avail); in udivmod64() 6 ir_factory body(&sig->body, mem_ctx); in udivmod64() 11 ir_variable *const r000C = new(mem_ctx) ir_variable(glsl_type::uvec2_type, "n", ir_var_function_in); in udivmod64() 13 ir_variable *const r000D = new(mem_ctx) ir_variable(glsl_type::uvec2_type, "d", ir_var_function_in); in udivmod64() 15 ir_variable *const r000E = new(mem_ctx) ir_variable(glsl_type::int_type, "i", ir_var_auto); in udivmod64() 17 ir_variable *const r000F = new(mem_ctx) ir_variable(glsl_type::uint64_t_type, "n64", ir_var_auto); in udivmod64() 19 ir_variable *const r0010 = new(mem_ctx) ir_variable(glsl_type::int_type, "log2_denom", ir_var_auto); in udivmod64() 21 ir_variable *const r0011 = new(mem_ctx) ir_variable(glsl_type::uvec2_type, "quot", ir_var_auto); in udivmod64() 23 body.emit(assign(r0011, ir_constant::zero(mem_ctx, glsl_typ in udivmod64() 213 udiv64(void *mem_ctx, builtin_available_predicate avail) udiv64() argument 422 idiv64(void *mem_ctx, builtin_available_predicate avail) idiv64() argument 671 umod64(void *mem_ctx, builtin_available_predicate avail) umod64() argument 886 imod64(void *mem_ctx, builtin_available_predicate avail) imod64() argument [all...] |
H A D | lower_discard.cpp | 151 replace_discard(void *mem_ctx, ir_variable *var, ir_discard *ir) in replace_discard() argument 157 condition = new(mem_ctx) ir_constant(true); in replace_discard() 160 new(mem_ctx) ir_assignment(new(mem_ctx) ir_dereference_variable(var), in replace_discard() 176 void *mem_ctx = ralloc_parent(ir); in visit_leave() local 178 ir_variable *temp = new(mem_ctx) ir_variable(glsl_type::bool_type, in visit_leave() 182 new(mem_ctx) ir_assignment(new(mem_ctx) ir_dereference_variable(temp), in visit_leave() 183 new(mem_ctx) ir_constant(false)); in visit_leave() 189 replace_discard(mem_ctx, tem in visit_leave() [all...] |
H A D | lower_discard_flow.cpp | 57 mem_ctx = ralloc_parent(discarded); in lower_discard_flow_visitor() 72 void *mem_ctx; member in __anon7183::lower_discard_flow_visitor 91 ir_dereference *lhs = new(mem_ctx) ir_dereference_variable(discarded); in visit_enter() 96 ir->condition = new(mem_ctx) ir_dereference_variable(discarded); in visit_enter() 98 rhs = new(mem_ctx) ir_constant(true); in visit_enter() 100 ir_assignment *assign = new(mem_ctx) ir_assignment(lhs, rhs); in visit_enter() 120 ir_dereference *lhs = new(mem_ctx) ir_dereference_variable(discarded); in visit_enter() 121 ir_rvalue *rhs = new(mem_ctx) ir_constant(false); in visit_enter() 122 ir_assignment *assign = new(mem_ctx) ir_assignment(lhs, rhs); in visit_enter() 131 ir_rvalue *if_condition = new(mem_ctx) ir_dereference_variabl in generate_discard_break() 143 void *mem_ctx = ir; lower_discard_flow() local [all...] |
H A D | opt_array_splitting.cpp | 56 this->mem_ctx = NULL; in variable_entry() 78 void *mem_ctx; member in __anon7202::opt_array_splitting::variable_entry 94 this->mem_ctx = ralloc_context(NULL); in ir_array_reference_visitor() 101 ralloc_free(mem_ctx); in ~ir_array_reference_visitor() 118 void *mem_ctx; member in __anon7202::ir_array_reference_visitor 171 variable_entry *entry = new(mem_ctx) variable_entry(var); in get_variable_entry() 364 *deref = new(entry->mem_ctx) in split_deref() 373 ir_variable *temp = new(entry->mem_ctx) ir_variable(deref_array->type, in split_deref() 377 *deref = new(entry->mem_ctx) ir_dereference_variable(temp); in split_deref() 409 void *mem_ctx in visit_leave() local 446 void *mem_ctx = ralloc_context(NULL); optimize_split_arrays() local [all...] |
H A D | opt_structure_splitting.cpp | 53 this->mem_ctx = NULL; in variable_entry() 70 void *mem_ctx; member in __anon7215::variable_entry 78 this->mem_ctx = ralloc_context(NULL); in ir_structure_reference_visitor() 84 ralloc_free(mem_ctx); in ~ir_structure_reference_visitor() 98 void *mem_ctx; member in __anon7215::ir_structure_reference_visitor 116 variable_entry *entry = new(mem_ctx) variable_entry(var); in get_variable_entry() 239 *deref = new(entry->mem_ctx) ir_dereference_variable(entry->components[i]); in split_deref() 269 void *mem_ctx = lhs_entry ? lhs_entry->mem_ctx : rhs_entry->mem_ctx; in visit_leave() local 323 void *mem_ctx = ralloc_context(NULL); do_structure_splitting() local [all...] |
H A D | lower_vector_derefs.cpp | 35 vector_deref_visitor(void *mem_ctx, gl_shader_stage shader_stage) in vector_deref_visitor() argument 37 factory(&factory_instructions, mem_ctx) in vector_deref_visitor() 78 void *mem_ctx = ralloc_parent(ir); in visit_enter() local 80 deref->array_index->constant_expression_value(mem_ctx); in visit_enter() 98 ir->set_lhs(new(mem_ctx) ir_dereference_variable(src_temp)); in visit_enter() 106 ir_constant::zero(factory.mem_ctx, deref->array_index->type); in visit_enter() 109 ir_rvalue *const lhs_clone = new_lhs->clone(factory.mem_ctx, NULL); in visit_enter() 111 new(mem_ctx) ir_dereference_variable(src_temp); in visit_enter() 122 new(mem_ctx) ir_assignment(swizzle(lhs_clone, i, 1), in visit_enter() 130 ir->rhs = new(mem_ctx) ir_expressio in visit_enter() 189 void *mem_ctx = ralloc_parent(deref); handle_rvalue() local [all...] |
H A D | ir_constant_expression.cpp | 689 ir_expression::constant_expression_value(void *mem_ctx, in constant_expression_value() argument 692 assert(mem_ctx); in constant_expression_value() 705 this->operands[operand]->constant_expression_value(mem_ctx, in constant_expression_value() 725 op[operand] = new(mem_ctx) ir_constant(float_type, &f); in constant_expression_value() 740 op[operand] = new(mem_ctx) ir_constant(int_type, &d); in constant_expression_value() 755 op[operand] = new(mem_ctx) ir_constant(uint_type, &d); in constant_expression_value() 828 return new(mem_ctx) ir_constant(op[0]->has_value(op[1])); in constant_expression_value() 830 return new(mem_ctx) ir_constant(!op[0]->has_value(op[1])); in constant_expression_value() 845 return new(mem_ctx) ir_constant(this->type, &f); in constant_expression_value() 852 return new(mem_ctx) ir_constan in constant_expression_value() 876 constant_expression_value(void *mem_ctx, struct hash_table *variable_context) constant_expression_value() argument 914 constant_expression_value(void *mem_ctx, struct hash_table *variable_context) constant_expression_value() argument 942 constant_expression_value(void *mem_ctx, struct hash_table *variable_context) constant_expression_value() argument 1016 constant_expression_value(void *mem_ctx, struct hash_table *) constant_expression_value() argument 1043 constant_expression_value(void *mem_ctx, struct hash_table *variable_context) constant_expression_value() argument 1053 constant_expression_evaluate_expression_list(void *mem_ctx, const struct exec_list &body, struct hash_table *variable_context, ir_constant **result) constant_expression_evaluate_expression_list() argument 1164 constant_expression_value(void *mem_ctx, exec_list *actual_parameters, struct hash_table *variable_context) constant_expression_value() argument [all...] |
H A D | lower_named_interface_blocks.cpp | 83 process_array_ir(void * const mem_ctx, in process_array_ir() argument 91 return new(mem_ctx) ir_dereference_array(deref_var, in process_array_ir() 94 deref_array = (ir_dereference_array *) process_array_ir(mem_ctx, in process_array_ir() 97 return new(mem_ctx) ir_dereference_array(deref_array, in process_array_ir() 107 void * const mem_ctx; member in __anon7190::flatten_named_interface_blocks_declarations 110 flatten_named_interface_blocks_declarations(void *mem_ctx) in flatten_named_interface_blocks_declarations() argument 111 : mem_ctx(mem_ctx), in flatten_named_interface_blocks_declarations() 158 ralloc_asprintf(mem_ctx, "%s %s.%s.%s", in run() 168 ralloc_strdup(mem_ctx, iface_ in run() 318 lower_named_interface_blocks(void *mem_ctx, gl_linked_shader *shader) lower_named_interface_blocks() argument [all...] |
H A D | lower_blend_equation_advanced.cpp | 36 #define imm1(x) new(mem_ctx) ir_constant((float) (x), 1) 37 #define imm3(x) new(mem_ctx) ir_constant((float) (x), 3) 56 void *mem_ctx = ralloc_parent(src); in blend_overlay() local 84 void *mem_ctx = ralloc_parent(src); in blend_colordodge() local 99 void *mem_ctx = ralloc_parent(src); in blend_colorburn() local 114 void *mem_ctx = ralloc_parent(src); in blend_hardlight() local 128 void *mem_ctx = ralloc_parent(src); in blend_softlight() local 164 void *mem_ctx = ralloc_parent(src); in blend_exclusion() local 191 void *mem_ctx = ralloc_parent(c); in lumv3() local 194 return dot(c, new(mem_ctx) ir_constan in lumv3() 218 void *mem_ctx = f->mem_ctx; set_lum() local 250 void *mem_ctx = f->mem_ctx; set_lum_sat() local 282 void *mem_ctx = f.mem_ctx; calc_blend_result() local 433 void *mem_ctx = ralloc_parent(var); deref_output() local 476 void *mem_ctx = ralloc_parent(sh->ir); lower_blend_equation_advanced() local [all...] |
H A D | link_uniform_block_active_visitor.cpp | 29 process_block(void *mem_ctx, struct hash_table *ht, ir_variable *var) in process_block() argument 44 rzalloc(mem_ctx, struct link_uniform_block_active); in process_block() 97 process_arrays(void *mem_ctx, ir_dereference_array *ir, in process_arrays() argument 102 process_arrays(mem_ctx, ir->array->as_dereference_array(), block); in process_arrays() 104 *ub_array_ptr = rzalloc(mem_ctx, struct uniform_block_array_elements); in process_arrays() 127 ub_array->array_elements = reralloc(mem_ctx, in process_arrays() 141 ub_array->array_elements = reralloc(mem_ctx, in process_arrays() 177 process_block(this->mem_ctx, this->ht, var); in visit() 198 *ub_array = rzalloc(this->mem_ctx, struct uniform_block_array_elements); in visit() 200 (*ub_array)->array_elements = reralloc(this->mem_ctx, in visit() [all...] |
H A D | ir_builder.cpp | 42 var = new(mem_ctx) ir_variable(type, name, ir_var_temporary); in make_temp() 57 void *mem_ctx = ralloc_parent(lhs.val); in assign() local 59 ir_assignment *assign = new(mem_ctx) ir_assignment(lhs.val, in assign() 69 void *mem_ctx = ralloc_parent(retval.val); in ret() local 70 return new(mem_ctx) ir_return(retval.val); in ret() 76 void *mem_ctx = ralloc_parent(a.val); in swizzle() local 78 return new(mem_ctx) ir_swizzle(a.val, in swizzle() 89 void *mem_ctx = ralloc_parent(a.val); in swizzle_for_size() local 98 return new(mem_ctx) ir_swizzle(a.val, s, components); in swizzle_for_size() 170 void *mem_ctx in expr() local 178 void *mem_ctx = ralloc_parent(a.val); expr() local 186 void *mem_ctx = ralloc_parent(a.val); expr() local 601 void *mem_ctx = ralloc_parent(a.val); bitfield_insert() local 612 void *mem_ctx = ralloc_parent(condition.val); if_tree() local 627 void *mem_ctx = ralloc_parent(condition.val); if_tree() local [all...] |
H A D | ir.h | 111 virtual ir_instruction *clone(void *mem_ctx, 221 virtual ir_rvalue *clone(void *mem_ctx, struct hash_table *) const; 230 virtual ir_constant *constant_expression_value(void *mem_ctx, 310 * Allocation will be performed with 'mem_ctx' as ralloc owner. 312 static ir_rvalue *error_value(void *mem_ctx); 422 virtual ir_variable *clone(void *mem_ctx, struct hash_table *ht) const; 1188 virtual ir_function_signature *clone(void *mem_ctx, 1190 ir_function_signature *clone_prototype(void *mem_ctx, 1205 ir_constant *constant_expression_value(void *mem_ctx, 1317 bool constant_expression_evaluate_expression_list(void *mem_ctx, 2390 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 2423 clone(void *mem_ctx, struct hash_table *ht) const clone() argument 2453 clone(void *mem_ctx, struct hash_table *) const clone() argument [all...] |
H A D | lower_subroutine.cpp | 65 void *mem_ctx = ralloc_parent(call); in call_clone() local 68 new_return_ref = call->return_deref->clone(mem_ctx, NULL); in call_clone() 73 new_parameters.push_tail(ir->clone(mem_ctx, NULL)); in call_clone() 76 return new(mem_ctx) ir_call(callee, new_return_ref, &new_parameters); in call_clone() 85 void *mem_ctx = ralloc_parent(ir); in visit_leave() local 91 ir_constant *lc = new(mem_ctx)ir_constant(fn->subroutine_index); in visit_leave() 105 var = ir->array_idx->clone(mem_ctx, NULL); in visit_leave() 107 var = new(mem_ctx) ir_dereference_variable(ir->sub_var); in visit_leave()
|
/third_party/mesa3d/src/intel/compiler/ |
H A D | brw_cfg.cpp | 50 link(void *mem_ctx, bblock_t *block, enum bblock_link_kind kind) in link() argument 52 bblock_link *l = new(mem_ctx) bblock_link(block, kind); in link() 57 push_stack(exec_list *list, void *mem_ctx, bblock_t *block) in push_stack() argument 62 list->push_tail(link(mem_ctx, block, bblock_link_logical)); in push_stack() 74 bblock_t::add_successor(void *mem_ctx, bblock_t *successor, in add_successor() argument 77 successor->parents.push_tail(::link(mem_ctx, this, kind)); in add_successor() 78 children.push_tail(::link(mem_ctx, successor, kind)); in add_successor() 172 mem_ctx = ralloc_context(NULL); in cfg_t() 204 push_stack(&if_stack, mem_ctx, cur_if); in cfg_t() 205 push_stack(&else_stack, mem_ctx, cur_els in cfg_t() [all...] |
H A D | brw_simd_selection.c | 50 brw_simd_should_compile(void *mem_ctx, in brw_simd_should_compile() argument 71 mem_ctx, "SIMD%u skipped because would spill", width); in brw_simd_should_compile() 83 mem_ctx, "SIMD%u skipped because required dispatch width is %u", in brw_simd_should_compile() 91 mem_ctx, "SIMD%u skipped because workgroup size %u already fits in SIMD%u", in brw_simd_should_compile() 98 mem_ctx, "SIMD%u can't fit all %u invocations in %u threads", in brw_simd_should_compile() 110 mem_ctx, "SIMD32 skipped because not required"); in brw_simd_should_compile() 124 mem_ctx, "SIMD%u skipped because INTEL_DEBUG=no%u", in brw_simd_should_compile() 175 void *mem_ctx = ralloc_context(NULL); in brw_simd_select_for_workgroup_size() local 190 if (brw_simd_should_compile(mem_ctx, simd, devinfo, &cloned, in brw_simd_select_for_workgroup_size() 197 ralloc_free(mem_ctx); in brw_simd_select_for_workgroup_size() [all...] |
/third_party/mesa3d/src/compiler/glsl/tests/ |
H A D | lower_int64_test.cpp | 53 void *mem_ctx; member in expand_source 61 mem_ctx = ralloc_context(NULL); in SetUp() 65 body = new ir_factory(&instructions, mem_ctx); in SetUp() 74 ralloc_free(mem_ctx); in TearDown() 75 mem_ctx = NULL; in TearDown() 81 create_variable(void *mem_ctx, const glsl_type *type) in create_variable() argument 83 ir_variable *var = new(mem_ctx) ir_variable(type, in create_variable() 87 return new(mem_ctx) ir_dereference_variable(var); in create_variable() 91 create_expression(void *mem_ctx, const glsl_type *type) in create_expression() argument 93 return new(mem_ctx) ir_expressio in create_expression() 383 void *mem_ctx; global() member in compact_destination [all...] |
H A D | array_refcount_test.cpp | 38 void *mem_ctx; member in array_refcount_test 98 mem_ctx = ralloc_context(NULL); in SetUp() 101 body = new ir_factory(&instructions, mem_ctx); in SetUp() 120 ralloc_free(mem_ctx); in TearDown() 121 mem_ctx = NULL; in TearDown() 129 void *mem_ctx = ralloc_parent(array.val); in deref_array() local 131 ir_rvalue *val = new(mem_ctx) ir_dereference_array(array.val, index.val); in deref_array() 139 void *mem_ctx = ralloc_parent(s.val); in deref_struct() local 141 ir_rvalue *val = new(mem_ctx) ir_dereference_record(s.val, field); in deref_struct() 213 new(mem_ctx) ir_variabl in TEST_F() [all...] |
H A D | list_iterators.cpp | 40 void *mem_ctx; member in list_iterators_node_inherite 48 mem_ctx = ralloc_context(NULL); in SetUp() 53 test_node_inherite *node = new(mem_ctx) test_node_inherite(); in SetUp() 64 ralloc_free(mem_ctx); in TearDown() 65 mem_ctx = NULL; in TearDown() 158 void *mem_ctx; member in list_iterators_node_embed 166 mem_ctx = ralloc_context(NULL); in SetUp() 171 test_node_embed *node = new(mem_ctx) test_node_embed(); in SetUp() 183 ralloc_free(mem_ctx); in TearDown() 184 mem_ctx in TearDown() [all...] |
/third_party/mesa3d/src/compiler/nir/ |
H A D | nir_lower_goto_ifs.c | 113 sorted_block_arr_for_set(const struct set *block_set, void *mem_ctx) in sorted_block_arr_for_set() argument 116 nir_block **block_arr = ralloc_array(mem_ctx, nir_block *, num_blocks); in sorted_block_arr_for_set() 294 void *mem_ctx) in loop_routing_start() 311 struct routes *routing_backup = rzalloc(mem_ctx, struct routes); in loop_routing_start() 335 struct path_fork *fork = rzalloc(mem_ctx, struct path_fork); in loop_routing_start() 345 struct path_fork *fork = rzalloc(mem_ctx, struct path_fork); in loop_routing_start() 431 struct set *reach, struct set *brk_reachable, void *mem_ctx) in inside_outside() 434 struct set *remaining = _mesa_pointer_set_create(mem_ctx); in inside_outside() 490 brk_reachable, mem_ctx); in inside_outside() 510 nir_function_impl *impl, bool need_var, void *mem_ctx) in select_fork_recur() 292 loop_routing_start(struct routes *routing, nir_builder *b, struct path loop_path, struct set *reach, void *mem_ctx) loop_routing_start() argument 430 inside_outside(nir_block *block, struct set *loop_heads, struct set *outside, struct set *reach, struct set *brk_reachable, void *mem_ctx) inside_outside() argument 509 select_fork_recur(struct nir_block **blocks, unsigned start, unsigned end, nir_function_impl *impl, bool need_var, void *mem_ctx) select_fork_recur() argument 546 select_fork(struct set *reachable, nir_function_impl *impl, bool need_var, void *mem_ctx) select_fork() argument 583 handle_irreducible(struct set *remaining, struct strct_lvl *curr_level, struct set *brk_reachable, void *mem_ctx) handle_irreducible() argument 660 organize_levels(struct list_head *levels, struct set *remaining, struct set *reach, struct routes *routing, nir_function_impl *impl, bool is_domminated, void *mem_ctx) organize_levels() argument 802 select_blocks(struct routes *routing, nir_builder *b, struct path in_path, void *mem_ctx) select_blocks() argument 823 plant_levels(struct list_head *levels, struct routes *routing, nir_builder *b, void *mem_ctx) plant_levels() argument 853 nir_structurize(struct routes *routing, nir_builder *b, nir_block *block, void *mem_ctx) nir_structurize() argument 951 void *mem_ctx = ralloc_context(b.shader); nir_lower_goto_ifs_impl() local [all...] |
H A D | nir_split_vars.c | 33 get_complex_used_vars(nir_shader *shader, void *mem_ctx) in get_complex_used_vars() argument 35 struct set *complex_vars = _mesa_pointer_set_create(mem_ctx); in get_complex_used_vars() 62 void *mem_ctx; member 112 field->fields = ralloc_array(state->mem_ctx, struct field, in init_field_for_type() 117 field_name = ralloc_asprintf(state->mem_ctx, "%s_%s", name, in init_field_for_type() 120 field_name = ralloc_asprintf(state->mem_ctx, "{unnamed %s}_%s", in init_field_for_type() 150 void *mem_ctx) in split_var_list_structs() 153 .mem_ctx = mem_ctx, in split_var_list_structs() 172 *complex_vars = get_complex_used_vars(shader, mem_ctx); in split_var_list_structs() 144 split_var_list_structs(nir_shader *shader, nir_function_impl *impl, struct exec_list *vars, nir_variable_mode mode, struct hash_table *var_field_map, struct set **complex_vars, void *mem_ctx) split_var_list_structs() argument 196 split_struct_derefs_impl(nir_function_impl *impl, struct hash_table *var_field_map, nir_variable_mode modes, void *mem_ctx) split_struct_derefs_impl() argument 297 void *mem_ctx = ralloc_context(NULL); nir_split_struct_vars() local 372 init_var_list_array_infos(nir_shader *shader, struct exec_list *vars, nir_variable_mode mode, struct hash_table *var_info_map, struct set **complex_vars, void *mem_ctx) init_var_list_array_infos() argument 446 mark_array_deref_used(nir_deref_instr *deref, struct hash_table *var_info_map, nir_variable_mode modes, void *mem_ctx) mark_array_deref_used() argument 471 mark_array_usage_impl(nir_function_impl *impl, struct hash_table *var_info_map, nir_variable_mode modes, void *mem_ctx) mark_array_usage_impl() argument 502 create_split_array_vars(struct array_var_info *var_info, unsigned level, struct array_split *split, const char *name, nir_shader *shader, nir_function_impl *impl, void *mem_ctx) create_split_array_vars() argument 544 split_var_list_arrays(nir_shader *shader, nir_function_impl *impl, struct exec_list *vars, nir_variable_mode mode, struct hash_table *var_info_map, void *mem_ctx) split_var_list_arrays() argument 705 split_array_copies_impl(nir_function_impl *impl, struct hash_table *var_info_map, nir_variable_mode modes, void *mem_ctx) split_array_copies_impl() argument 750 split_array_access_impl(nir_function_impl *impl, struct hash_table *var_info_map, nir_variable_mode modes, void *mem_ctx) split_array_access_impl() argument 863 void *mem_ctx = ralloc_context(NULL); nir_split_array_vars() local 976 get_vec_var_usage(nir_variable *var, struct hash_table *var_usage_map, bool add_usage_entry, void *mem_ctx) get_vec_var_usage() argument 1016 get_vec_deref_usage(nir_deref_instr *deref, struct hash_table *var_usage_map, nir_variable_mode modes, bool add_usage_entry, void *mem_ctx) get_vec_deref_usage() argument 1033 mark_deref_if_complex(nir_deref_instr *deref, struct hash_table *var_usage_map, nir_variable_mode modes, void *mem_ctx) mark_deref_if_complex() argument 1059 mark_deref_used(nir_deref_instr *deref, nir_component_mask_t comps_read, nir_component_mask_t comps_written, nir_deref_instr *copy_deref, struct hash_table *var_usage_map, nir_variable_mode modes, void *mem_ctx) mark_deref_used() argument 1208 find_used_components_impl(nir_function_impl *impl, struct hash_table *var_usage_map, nir_variable_mode modes, void *mem_ctx) find_used_components_impl() argument 1217 var_usage_map, modes, mem_ctx); find_used_components_impl() local 1234 NULL, var_usage_map, modes, mem_ctx); find_used_components_impl() local 1648 void *mem_ctx = ralloc_context(NULL); nir_shrink_vec_array_vars() local [all...] |
/third_party/mesa3d/src/mesa/main/ |
H A D | ff_fragment_shader.cpp | 362 return new(p->mem_ctx) ir_dereference_variable(current); in get_current_attrib() 371 return new(p->mem_ctx) ir_dereference_variable(var); in get_gl_Color() 386 return new(p->mem_ctx) ir_dereference_variable(p->src_texture[unit]); in get_source() 396 return new(p->mem_ctx) in get_source() 402 deref = new(p->mem_ctx) ir_dereference_variable(var); in get_source() 404 return new(p->mem_ctx) ir_dereference_array(deref, in get_source() 405 new(p->mem_ctx) ir_constant(unit)); in get_source() 410 return new(p->mem_ctx) ir_dereference_variable(var); in get_source() 413 return new(p->mem_ctx) ir_constant(0.0f); in get_source() 416 return new(p->mem_ctx) ir_constan in get_source() [all...] |
/third_party/mesa3d/src/gallium/drivers/zink/nir_to_spirv/ |
H A D | spirv_builder.c | 41 spirv_buffer_grow(struct spirv_buffer *b, void *mem_ctx, size_t needed) in spirv_buffer_grow() argument 45 uint32_t *new_words = reralloc_size(mem_ctx, b->words, in spirv_buffer_grow() 56 spirv_buffer_prepare(struct spirv_buffer *b, void *mem_ctx, size_t needed) in spirv_buffer_prepare() argument 62 return spirv_buffer_grow(b, mem_ctx, needed); in spirv_buffer_prepare() 74 spirv_buffer_emit_string(struct spirv_buffer *b, void *mem_ctx, in spirv_buffer_emit_string() argument 82 spirv_buffer_prepare(b, mem_ctx, 1); in spirv_buffer_emit_string() 88 spirv_buffer_prepare(b, mem_ctx, 1); in spirv_buffer_emit_string() 98 b->caps = _mesa_set_create_u32_keys(b->mem_ctx); in spirv_builder_emit_cap() 108 spirv_buffer_prepare(&b->extensions, b->mem_ctx, 1); in spirv_builder_emit_extension() 110 int len = spirv_buffer_emit_string(&b->extensions, b->mem_ctx, nam in spirv_builder_emit_extension() [all...] |
/third_party/mesa3d/src/util/ |
H A D | u_dynarray.h | 47 void *mem_ctx; member 54 util_dynarray_init(struct util_dynarray *buf, void *mem_ctx) in util_dynarray_init() argument 57 buf->mem_ctx = mem_ctx; in util_dynarray_init() 64 if (buf->mem_ctx) { in util_dynarray_fini() 69 util_dynarray_init(buf, buf->mem_ctx); in util_dynarray_fini() 88 if (buf->mem_ctx) { in util_dynarray_ensure_cap() 89 data = reralloc_size(buf->mem_ctx, buf->data, capacity); in util_dynarray_ensure_cap() 121 util_dynarray_clone(struct util_dynarray *buf, void *mem_ctx, in util_dynarray_clone() argument 124 util_dynarray_init(buf, mem_ctx); in util_dynarray_clone() [all...] |