Home
last modified time | relevance | path

Searched refs:parent_instr (Results 1 – 25 of 44) sorted by relevance

12

/external/mesa3d/src/compiler/nir/
Dnir_move_vec_src_uses_to_dest.c55 if (instr->index <= def->parent_instr->index) { in ssa_def_dominates_instr()
57 } else if (def->parent_instr->block == instr->block) { in ssa_def_dominates_instr()
58 return def->parent_instr->index < instr->index; in ssa_def_dominates_instr()
60 return nir_block_dominates(def->parent_instr->block, instr->block); in ssa_def_dominates_instr()
127 if (use->parent_instr == &vec->instr) in move_vec_src_uses_to_dest_block()
131 if (!ssa_def_dominates_instr(&vec->dest.dest.ssa, use->parent_instr)) in move_vec_src_uses_to_dest_block()
135 if (use->parent_instr->type != nir_instr_type_alu) in move_vec_src_uses_to_dest_block()
140 nir_alu_instr *use_alu = nir_instr_as_alu(use->parent_instr); in move_vec_src_uses_to_dest_block()
165 nir_instr_rewrite_src(use->parent_instr, use, in move_vec_src_uses_to_dest_block()
Dnir_repair_ssa.c60 if (src->parent_instr->type == nir_instr_type_phi) { in get_src_block()
63 return src->parent_instr->block; in get_src_block()
74 if (!nir_block_dominates(def->parent_instr->block, get_src_block(src))) { in repair_ssa_def()
85 BITSET_SET(state->def_set, def->parent_instr->block->index); in repair_ssa_def()
91 nir_phi_builder_value_set_block_def(val, def->parent_instr->block, def); in repair_ssa_def()
95 if (!nir_block_dominates(def->parent_instr->block, src_block)) { in repair_ssa_def()
96 nir_instr_rewrite_src(src->parent_instr, src, nir_src_for_ssa( in repair_ssa_def()
Dnir_to_lcssa.c76 if (use->parent_instr->block->index <= block_before_loop->index || in is_use_inside_loop()
77 use->parent_instr->block->index >= block_after_loop->index) { in is_use_inside_loop()
94 if (use->parent_instr->type == nir_instr_type_phi && in convert_loop_exit_for_ssa()
95 use->parent_instr->block == block_after_loop) { in convert_loop_exit_for_ssa()
137 if (use->parent_instr->type == nir_instr_type_phi && in convert_loop_exit_for_ssa()
138 block_after_loop == use->parent_instr->block) { in convert_loop_exit_for_ssa()
143 nir_instr_rewrite_src(use->parent_instr, use, in convert_loop_exit_for_ssa()
Dnir_loop_analyze.c134 return var->def->parent_instr->type == nir_instr_type_alu; in is_var_alu()
140 return var->def->parent_instr->type == nir_instr_type_load_const; in is_var_constant()
146 return var->def->parent_instr->type == nir_instr_type_phi; in is_var_phi()
166 nir_alu_instr *alu = nir_instr_as_alu(def->parent_instr); in mark_invariant()
228 nir_phi_instr *phi = nir_instr_as_phi(var->def->parent_instr); in compute_induction_information()
243 nir_alu_instr *alu = nir_instr_as_alu(src_var->def->parent_instr); in compute_induction_information()
251 if (alu->src[i].src.ssa->parent_instr->type == nir_instr_type_load_const && in compute_induction_information()
284 if (def->parent_instr->type == nir_instr_type_load_const) { in initialize_ssa_def()
338 if (nif->condition.ssa->parent_instr->type == nir_instr_type_phi) in find_loop_terminators()
351 terminator->conditional_instr = nif->condition.ssa->parent_instr; in find_loop_terminators()
[all …]
Dnir_liveness.c57 if (def->parent_instr->type == nir_instr_type_ssa_undef) in index_ssa_def()
265 def->parent_instr->block == instr->block) { in nir_ssa_def_is_live_at()
280 if (a->parent_instr == b->parent_instr) { in nir_ssa_defs_interfere()
289 return nir_ssa_def_is_live_at(a, b->parent_instr); in nir_ssa_defs_interfere()
291 return nir_ssa_def_is_live_at(b, a->parent_instr); in nir_ssa_defs_interfere()
Dnir_from_ssa.c56 } else if (a->parent_instr->block == b->parent_instr->block) { in ssa_def_dominates()
59 return nir_block_dominates(a->parent_instr->block, in ssa_def_dominates()
60 b->parent_instr->block); in ssa_def_dominates()
406 if (entry->src.ssa->parent_instr->type == nir_instr_type_load_const) in aggressive_coalesce_parallel_copy()
491 if (def->parent_instr->type == nir_instr_type_load_const) in rewrite_ssa_def()
500 if (def->parent_instr->type == nir_instr_type_ssa_undef) { in rewrite_ssa_def()
504 nir_instr *parent_instr = def->parent_instr; in rewrite_ssa_def() local
505 nir_instr_remove(parent_instr); in rewrite_ssa_def()
506 ralloc_steal(state->dead_ctx, parent_instr); in rewrite_ssa_def()
511 assert(def->parent_instr->type != nir_instr_type_load_const); in rewrite_ssa_def()
[all …]
Dnir_opt_gcm.c211 gcm_schedule_early_instr(src->ssa->parent_instr, void_state); in gcm_schedule_early_src()
220 if (instr->block->index < src->ssa->parent_instr->block->index) in gcm_schedule_early_src()
221 instr->block = src->ssa->parent_instr->block; in gcm_schedule_early_src()
282 nir_instr *use_instr = use_src->parent_instr; in gcm_schedule_late_def()
334 if (block == def->parent_instr->block) in gcm_schedule_late_def()
337 def->parent_instr->block = best; in gcm_schedule_late_def()
380 gcm_place_instr(use_src->parent_instr, state); in gcm_place_instr_def()
Dnir_opt_dce.c59 if (src->is_ssa && !src->ssa->parent_instr->pass_flags) { in mark_live_cb()
60 worklist_push(worklist, src->ssa->parent_instr); in mark_live_cb()
124 !following_if->condition.ssa->parent_instr->pass_flags) in init_block()
125 worklist_push(worklist, following_if->condition.ssa->parent_instr); in init_block()
Dnir_opt_copy_propagate.c102 copy_prop_src(nir_src *src, nir_instr *parent_instr, nir_if *parent_if, in copy_prop_src() argument
107 return copy_prop_src(src->reg.indirect, parent_instr, parent_if, 1); in copy_prop_src()
111 nir_instr *src_instr = src->ssa->parent_instr; in copy_prop_src()
122 if (parent_instr) { in copy_prop_src()
123 nir_instr_rewrite_src(parent_instr, src, in copy_prop_src()
145 nir_instr *src_instr = src->src.ssa->parent_instr; in copy_prop_alu_src()
Dnir_lower_to_source_mods.c51 if (alu->src[i].src.ssa->parent_instr->type != nir_instr_type_alu) in nir_lower_to_source_mods_block()
54 nir_alu_instr *parent = nir_instr_as_alu(alu->src[i].src.ssa->parent_instr); in nir_lower_to_source_mods_block()
145 nir_instr *child = child_src->parent_instr; in nir_lower_to_source_mods_block()
172 nir_alu_instr *child_alu = nir_instr_as_alu(child_src->parent_instr); in nir_lower_to_source_mods_block()
Dnir_search.c62 if (src.ssa->parent_instr->type == nir_instr_type_alu) { in src_is_type()
63 nir_alu_instr *src_alu = nir_instr_as_alu(src.ssa->parent_instr); in src_is_type()
81 } else if (src.ssa->parent_instr->type == nir_instr_type_intrinsic) { in src_is_type()
82 nir_intrinsic_instr *intr = nir_instr_as_intrinsic(src.ssa->parent_instr); in src_is_type()
129 if (instr->src[src].src.ssa->parent_instr->type != nir_instr_type_alu) in match_value()
133 nir_instr_as_alu(instr->src[src].src.ssa->parent_instr), in match_value()
154 instr->src[src].src.ssa->parent_instr->type != nir_instr_type_load_const) in match_value()
186 if (instr->src[src].src.ssa->parent_instr->type != nir_instr_type_load_const) in match_value()
190 nir_instr_as_load_const(instr->src[src].src.ssa->parent_instr); in match_value()
Dnir.c967 src->parent_instr = instr; in add_use_cb()
995 dest->reg.parent_instr = instr; in add_reg_def_cb()
1415 if (src.ssa->parent_instr->type != nir_instr_type_load_const) in nir_src_as_const_value()
1418 nir_load_const_instr *load = nir_instr_as_load_const(src.ssa->parent_instr); in nir_src_as_const_value()
1435 if (src.ssa->parent_instr->type == nir_instr_type_load_const) in nir_src_is_dynamically_uniform()
1439 if (src.ssa->parent_instr->type == nir_instr_type_intrinsic) { in nir_src_is_dynamically_uniform()
1440 nir_intrinsic_instr *intr = nir_instr_as_intrinsic(src.ssa->parent_instr); in nir_src_is_dynamically_uniform()
1464 src_add_all_uses(nir_src *src, nir_instr *parent_instr, nir_if *parent_if) in src_add_all_uses() argument
1470 if (parent_instr) { in src_add_all_uses()
1471 src->parent_instr = parent_instr; in src_add_all_uses()
[all …]
Dnir_opt_undef.c50 nir_instr *parent = instr->src[i].src.ssa->parent_instr; in opt_undef_csel()
91 alu->src[i].src.ssa->parent_instr->type != nir_instr_type_ssa_undef) in opt_undef_vecN()
122 intrin->src[0].ssa->parent_instr->type != nir_instr_type_ssa_undef) in opt_undef_store()
Dnir_opt_if.c113 if (cond->parent_instr->type != nir_instr_type_phi) in opt_peel_loop_initial_if()
116 nir_phi_instr *cond_phi = nir_instr_as_phi(cond->parent_instr); in opt_peel_loop_initial_if()
117 if (cond->parent_instr->block != header_block) in opt_peel_loop_initial_if()
Dnir_opt_global_to_local.c38 nir_instr *instr = def_dest->reg.parent_instr; in global_to_local()
50 nir_instr *instr = use_src->parent_instr; in global_to_local()
Dnir_opt_constant_folding.c71 nir_instr *src_instr = instr->src[i].src.ssa->parent_instr; in constant_fold_alu_instr()
130 arr->indirect.ssa->parent_instr->type == nir_instr_type_load_const) { in constant_fold_deref()
132 nir_instr_as_load_const(arr->indirect.ssa->parent_instr); in constant_fold_deref()
Dnir_opt_move_comparisons.c83 nir_instr *src_instr = src->ssa->parent_instr; in move_comparison_source()
107 nir_instr *instr = src->parent_instr; in move_comparison_source_cb()
Dnir_opt_remove_phis.c34 if (ssa->parent_instr->type != nir_instr_type_alu) in get_parent_mov()
37 nir_alu_instr *alu = nir_instr_as_alu(ssa->parent_instr); in get_parent_mov()
Dnir_lower_regs_to_ssa.c47 nir_instr *instr = src->parent_instr; in rewrite_src()
91 nir_instr *instr = dest->reg.parent_instr; in rewrite_dest()
245 BITSET_SET(defs, dest->reg.parent_instr->block->index); in nir_lower_regs_to_ssa_impl()
Dnir_lower_vec_to_movs.c135 if (src->parent_instr != &vec->instr) in try_coalesce()
146 if (vec->src[start_idx].src.ssa->parent_instr->type != nir_instr_type_alu) in try_coalesce()
150 nir_instr_as_alu(vec->src[start_idx].src.ssa->parent_instr); in try_coalesce()
Dnir_search_helpers.h180 if (use->parent_instr->type == nir_instr_type_alu && in is_not_used_by_conditional()
181 nir_instr_as_alu(use->parent_instr)->op == nir_op_bcsel) in is_not_used_by_conditional()
Dnir_opt_peephole_select.c133 if (use->parent_instr->type != nir_instr_type_phi || in block_check_for_allowed_instrs()
134 use->parent_instr->block != block->successors[0]) in block_check_for_allowed_instrs()
/external/mesa3d/src/intel/compiler/
Dbrw_nir_opt_peephole_ffma.c43 nir_instr *use_instr = use_src->parent_instr; in are_all_uses_fadd()
77 nir_instr *instr = src->src.ssa->parent_instr; in get_mul_for_src()
150 if (srcs[i].src.ssa->parent_instr->type == nir_instr_type_load_const) { in any_alu_src_is_a_constant()
152 nir_instr_as_load_const (srcs[i].src.ssa->parent_instr); in any_alu_src_is_a_constant()
Dbrw_nir_analyze_boolean_resolves.c47 nir_instr *src_instr = src->ssa->parent_instr; in get_resolve_status_for_src()
70 nir_instr *src_instr = src->ssa->parent_instr; in src_mark_needs_resolve()
/external/tensorflow/tensorflow/compiler/xla/service/
Dhlo_graph_dumper.cc346 const HloInstruction* parent_instr);
581 const HloInstruction* parent_instr) { in DumpSubcomputation() argument
586 if (parent_instr->opcode() != HloOpcode::kFusion) { in DumpSubcomputation()
588 VLOG(2) << "Edge: from " << from->name() << " to " << parent_instr->name() in DumpSubcomputation()
590 edge_ids_.insert({{from, parent_instr}, next_edge_id_++}); in DumpSubcomputation()
594 edge_fmt, InstructionId(from), InstructionId(parent_instr), in DumpSubcomputation()
595 SubcomputationId(subcomp), subcomp->name(), parent_instr->name())); in DumpSubcomputation()
609 if (parent_instr->opcode() == HloOpcode::kFusion) { in DumpSubcomputation()
612 HtmlLikeStringSanitize(parent_instr->name()), in DumpSubcomputation()
613 HtmlLikeStringSanitize(parent_instr->ToCategory())); in DumpSubcomputation()
[all …]

12