| /external/vixl/src/aarch64/ |
| D | cpu-features-auditor-aarch64.cc | 80 void CPUFeaturesAuditor::LoadStoreHelper(const Instruction* instr) { in LoadStoreHelper()
103 void CPUFeaturesAuditor::LoadStorePairHelper(const Instruction* instr) { in LoadStorePairHelper()
123 void CPUFeaturesAuditor::VisitAddSubExtended(const Instruction* instr) { in VisitAddSubExtended()
128 void CPUFeaturesAuditor::VisitAddSubImmediate(const Instruction* instr) { in VisitAddSubImmediate()
133 void CPUFeaturesAuditor::VisitAddSubShifted(const Instruction* instr) { in VisitAddSubShifted()
138 void CPUFeaturesAuditor::VisitAddSubWithCarry(const Instruction* instr) { in VisitAddSubWithCarry()
143 void CPUFeaturesAuditor::VisitRotateRightIntoFlags(const Instruction* instr) { in VisitRotateRightIntoFlags()
152 void CPUFeaturesAuditor::VisitEvaluateIntoFlags(const Instruction* instr) { in VisitEvaluateIntoFlags()
162 void CPUFeaturesAuditor::VisitAtomicMemory(const Instruction* instr) { in VisitAtomicMemory()
178 void CPUFeaturesAuditor::VisitBitfield(const Instruction* instr) { in VisitBitfield()
[all …]
|
| D | disasm-aarch64.cc | 65 void Disassembler::VisitAddSubImmediate(const Instruction *instr) { in VisitAddSubImmediate()
114 void Disassembler::VisitAddSubShifted(const Instruction *instr) { in VisitAddSubShifted()
164 void Disassembler::VisitAddSubExtended(const Instruction *instr) { in VisitAddSubExtended()
207 void Disassembler::VisitAddSubWithCarry(const Instruction *instr) { in VisitAddSubWithCarry()
247 void Disassembler::VisitRotateRightIntoFlags(const Instruction *instr) { in VisitRotateRightIntoFlags()
264 void Disassembler::VisitEvaluateIntoFlags(const Instruction *instr) { in VisitEvaluateIntoFlags()
285 void Disassembler::VisitLogicalImmediate(const Instruction *instr) { in VisitLogicalImmediate()
361 void Disassembler::VisitLogicalShifted(const Instruction *instr) { in VisitLogicalShifted()
424 void Disassembler::VisitConditionalCompareRegister(const Instruction *instr) { in VisitConditionalCompareRegister()
444 void Disassembler::VisitConditionalCompareImmediate(const Instruction *instr) { in VisitConditionalCompareImmediate()
[all …]
|
| D | simulator-aarch64.cc | 1572 void Simulator::VisitReserved(const Instruction* instr) { in VisitReserved()
1583 void Simulator::VisitUnimplemented(const Instruction* instr) { in VisitUnimplemented()
1591 void Simulator::VisitUnallocated(const Instruction* instr) { in VisitUnallocated()
1599 void Simulator::VisitPCRelAddressing(const Instruction* instr) { in VisitPCRelAddressing()
1607 void Simulator::VisitUnconditionalBranch(const Instruction* instr) { in VisitUnconditionalBranch()
1621 void Simulator::VisitConditionalBranch(const Instruction* instr) { in VisitConditionalBranch()
1650 void Simulator::VisitUnconditionalBranchToRegister(const Instruction* instr) { in VisitUnconditionalBranchToRegister()
1712 void Simulator::VisitTestBranch(const Instruction* instr) { in VisitTestBranch()
1733 void Simulator::VisitCompareBranch(const Instruction* instr) { in VisitCompareBranch()
1758 void Simulator::AddSubHelper(const Instruction* instr, int64_t op2) { in AddSubHelper()
[all …]
|
| /external/llvm-project/lld/ELF/ |
| D | AArch64ErrataFix.cpp | 55 static bool isADRP(uint32_t instr) { in isADRP()
65 static bool isLoadStoreClass(uint32_t instr) { in isLoadStoreClass()
81 static bool isST1MultipleOpcode(uint32_t instr) { in isST1MultipleOpcode()
88 static bool isST1Multiple(uint32_t instr) { in isST1Multiple()
93 static bool isST1MultiplePost(uint32_t instr) { in isST1MultiplePost()
109 static bool isST1SingleOpcode(uint32_t instr) { in isST1SingleOpcode()
115 static bool isST1Single(uint32_t instr) { in isST1Single()
120 static bool isST1SinglePost(uint32_t instr) { in isST1SinglePost()
124 static bool isST1(uint32_t instr) { in isST1()
132 static bool isLoadStoreExclusive(uint32_t instr) { in isLoadStoreExclusive()
[all …]
|
| /external/mesa3d/src/gallium/drivers/etnaviv/ |
| D | etnaviv_disasm.c | 39 struct instr { struct
41 uint32_t opc : 6;
42 uint32_t cond : 5;
43 uint32_t sat : 1;
44 uint32_t dst_use : 1;
45 uint32_t dst_amode : 3;
46 uint32_t dst_reg : 7;
47 uint32_t dst_comps : 4;
48 uint32_t tex_id : 5;
51 uint32_t tex_amode : 3;
[all …]
|
| /external/mesa3d/src/gallium/drivers/lima/ir/gp/ |
| D | instr.c | 33 gpir_instr *instr = rzalloc(block, gpir_instr); in gpir_instr_create() local
52 static gpir_node *gpir_instr_get_the_other_acc_node(gpir_instr *instr, int slot) in gpir_instr_get_the_other_acc_node()
62 static bool gpir_instr_check_acc_same_op(gpir_instr *instr, gpir_node *node, int slot) in gpir_instr_check_acc_same_op()
75 static int gpir_instr_get_consume_slot(gpir_instr *instr, gpir_node *node) in gpir_instr_get_consume_slot()
90 static bool gpir_instr_insert_alu_check(gpir_instr *instr, gpir_node *node) in gpir_instr_insert_alu_check()
159 static void gpir_instr_remove_alu(gpir_instr *instr, gpir_node *node) in gpir_instr_remove_alu()
184 static bool gpir_instr_insert_reg0_check(gpir_instr *instr, gpir_node *node) in gpir_instr_insert_reg0_check()
208 static void gpir_instr_remove_reg0(gpir_instr *instr, gpir_node *node) in gpir_instr_remove_reg0()
215 static bool gpir_instr_insert_reg1_check(gpir_instr *instr, gpir_node *node) in gpir_instr_insert_reg1_check()
234 static void gpir_instr_remove_reg1(gpir_instr *instr, gpir_node *node) in gpir_instr_remove_reg1()
[all …]
|
| D | codegen.c | 86 static void gpir_codegen_mul0_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_mul0_slot()
146 static void gpir_codegen_mul1_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_mul1_slot()
198 static void gpir_codegen_add0_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_add0_slot()
283 static void gpir_codegen_add1_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_add1_slot()
368 static void gpir_codegen_complex_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_complex_slot()
413 static void gpir_codegen_pass_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_pass_slot()
458 static void gpir_codegen_reg0_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_reg0_slot()
467 static void gpir_codegen_reg1_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_reg1_slot()
475 static void gpir_codegen_mem_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_mem_slot()
502 static void gpir_codegen_store_slot(gpir_codegen_instr *code, gpir_instr *instr) in gpir_codegen_store_slot()
[all …]
|
| D | disasm.c | 50 print_dest(gpir_codegen_instr *instr, gp_unit unit, unsigned cur_dest_index) in print_dest()
119 gpir_codegen_instr *instr, gpir_codegen_instr *prev_instr, in print_src()
247 print_mul(gpir_codegen_instr *instr, gpir_codegen_instr *prev_instr, in print_mul()
395 print_acc(gpir_codegen_instr *instr, gpir_codegen_instr *prev_instr, in print_acc()
471 print_pass(gpir_codegen_instr *instr, gpir_codegen_instr *prev_instr, in print_pass()
516 print_complex(gpir_codegen_instr *instr, gpir_codegen_instr *prev_instr, in print_complex()
561 print_instr(gpir_codegen_instr *instr, gpir_codegen_instr *prev_instr, in print_instr()
594 for (gpir_codegen_instr *instr = code; cur_instr < num_instr; in gpir_disassemble_program() local
|
| /external/mesa3d/src/compiler/nir/ |
| D | nir_search_helpers.h | 36 is_pos_power_of_two(UNUSED struct hash_table *ht, nir_alu_instr *instr, in is_pos_power_of_two()
68 is_neg_power_of_two(UNUSED struct hash_table *ht, nir_alu_instr *instr, in is_neg_power_of_two()
120 is_zero_to_one(UNUSED struct hash_table *ht, nir_alu_instr *instr, unsigned src, in is_zero_to_one()
151 is_gt_0_and_lt_1(UNUSED struct hash_table *ht, nir_alu_instr *instr, in is_gt_0_and_lt_1()
176 is_not_const_zero(UNUSED struct hash_table *ht, nir_alu_instr *instr, in is_not_const_zero()
205 is_not_const(UNUSED struct hash_table *ht, nir_alu_instr *instr, unsigned src, in is_not_const()
213 is_not_fmul(struct hash_table *ht, nir_alu_instr *instr, unsigned src, in is_not_fmul()
229 is_fmul(struct hash_table *ht, nir_alu_instr *instr, unsigned src, in is_fmul()
245 is_fsign(nir_alu_instr *instr, unsigned src, in is_fsign()
261 is_not_const_and_not_fsign(struct hash_table *ht, nir_alu_instr *instr, unsigned src, in is_not_const_and_not_fsign()
[all …]
|
| D | nir_opt_shrink_vectors.c | 68 opt_shrink_vectors_alu(nir_builder *b, nir_alu_instr *instr) in opt_shrink_vectors_alu()
113 opt_shrink_vectors_image_store(nir_builder *b, nir_intrinsic_instr *instr) in opt_shrink_vectors_image_store()
137 opt_shrink_vectors_intrinsic(nir_builder *b, nir_intrinsic_instr *instr) in opt_shrink_vectors_intrinsic()
200 opt_shrink_vectors_load_const(nir_load_const_instr *instr) in opt_shrink_vectors_load_const()
206 opt_shrink_vectors_ssa_undef(nir_ssa_undef_instr *instr) in opt_shrink_vectors_ssa_undef()
212 opt_shrink_vectors_instr(nir_builder *b, nir_instr *instr) in opt_shrink_vectors_instr()
|
| D | nir.c | 300 void nir_dest_copy(nir_dest *dest, const nir_dest *src, nir_instr *instr) in nir_dest_copy()
319 nir_alu_instr *instr) in nir_alu_src_copy()
330 nir_alu_instr *instr) in nir_alu_dest_copy()
480 instr_init(nir_instr *instr, nir_instr_type type) in instr_init()
518 nir_alu_instr *instr = in nir_alu_instr_create() local
534 nir_deref_instr *instr = in nir_deref_instr_create() local
555 nir_jump_instr *instr = ralloc(shader, nir_jump_instr); in nir_jump_instr_create() local
568 nir_load_const_instr *instr = in nir_load_const_instr_create() local
582 nir_intrinsic_instr *instr = in nir_intrinsic_instr_create() local
602 nir_call_instr *instr = in nir_call_instr_create() local
[all …]
|
| /external/mesa3d/src/gallium/drivers/r600/sfn/ |
| D | sfn_emitaluinstruction.cpp | 45 const nir_alu_instr& instr = *nir_instr_as_alu(ir); in do_emit() local
204 void EmitAluInstruction::preload_src(const nir_alu_instr& instr) in preload_src()
227 unsigned EmitAluInstruction::num_src_comp(const nir_alu_instr& instr) in num_src_comp()
265 void EmitAluInstruction::split_constants(const nir_alu_instr& instr, unsigned nsrc_comp) in split_constants()
309 bool EmitAluInstruction::emit_alu_inot(const nir_alu_instr& instr) in emit_alu_inot()
328 bool EmitAluInstruction::emit_alu_op1(const nir_alu_instr& instr, EAluOp opcode, in emit_alu_op1()
354 bool EmitAluInstruction::emit_mov(const nir_alu_instr& instr) in emit_mov()
373 bool EmitAluInstruction::emit_alu_trig_op1(const nir_alu_instr& instr, EAluOp opcode) in emit_alu_trig_op1()
424 bool EmitAluInstruction::emit_alu_trans_op1(const nir_alu_instr& instr, EAluOp opcode, in emit_alu_trans_op1()
458 bool EmitAluInstruction::emit_alu_f2i32_or_u32(const nir_alu_instr& instr, EAluOp op) in emit_alu_f2i32_or_u32()
[all …]
|
| D | sfn_shader_compute.cpp | 42 bool ComputeShaderFromNir::scan_sysvalue_access(UNUSED nir_instr *instr) in scan_sysvalue_access()
67 bool ComputeShaderFromNir::emit_intrinsic_instruction_override(nir_intrinsic_instr* instr) in emit_intrinsic_instruction_override()
81 bool ComputeShaderFromNir::emit_load_3vec(nir_intrinsic_instr* instr, in emit_load_3vec()
89 bool ComputeShaderFromNir::emit_load_num_work_groups(nir_intrinsic_instr* instr) in emit_load_num_work_groups()
119 UNUSED nir_intrinsic_instr* instr) in do_emit_load_deref()
125 UNUSED nir_intrinsic_instr* instr) in do_emit_store_deref()
|
| D | sfn_emittexinstruction.cpp | 38 bool EmitTexInstruction::do_emit(nir_instr* instr) in do_emit()
109 bool EmitTexInstruction::emit_cube_txf(UNUSED nir_tex_instr* instr, UNUSED TexInputs &src) in emit_cube_txf()
114 bool EmitTexInstruction::emit_cube_txd(nir_tex_instr* instr, TexInputs& tex_src) in emit_cube_txd()
186 bool EmitTexInstruction::emit_cube_txl(nir_tex_instr* instr, TexInputs& tex_src) in emit_cube_txl()
234 bool EmitTexInstruction::emit_cube_lod(nir_tex_instr* instr, TexInputs& src) in emit_cube_lod()
259 bool EmitTexInstruction::emit_cube_txb(nir_tex_instr* instr, TexInputs& tex_src) in emit_cube_txb()
307 bool EmitTexInstruction::emit_cube_tex(nir_tex_instr* instr, TexInputs& tex_src) in emit_cube_tex()
393 bool EmitTexInstruction::emit_buf_txf(nir_tex_instr* instr, TexInputs &src) in emit_buf_txf()
405 bool EmitTexInstruction::emit_tex_tex(nir_tex_instr* instr, TexInputs& src) in emit_tex_tex()
436 bool EmitTexInstruction::emit_tex_txd(nir_tex_instr* instr, TexInputs& src) in emit_tex_txd()
[all …]
|
| D | sfn_shader_tess_eval.cpp | 46 bool TEvalShaderFromNir::scan_sysvalue_access(nir_instr *instr) in scan_sysvalue_access()
101 bool TEvalShaderFromNir::load_tess_z_coord(nir_intrinsic_instr* instr) in load_tess_z_coord()
112 bool TEvalShaderFromNir::emit_intrinsic_instruction_override(nir_intrinsic_instr* instr) in emit_intrinsic_instruction_override()
134 …ol TEvalShaderFromNir::do_emit_store_deref(const nir_variable *out_var, nir_intrinsic_instr* instr) in do_emit_store_deref()
145 bool TEvalShaderFromNir::emit_load_tess_coord(nir_intrinsic_instr* instr) in emit_load_tess_coord()
|
| /external/mesa3d/src/broadcom/qpu/ |
| D | qpu_disasm.c | 60 const struct v3d_qpu_instr *instr, uint8_t mux) in v3d_qpu_disasm_raddr()
102 const struct v3d_qpu_instr *instr) in v3d_qpu_disasm_add()
139 const struct v3d_qpu_instr *instr) in v3d_qpu_disasm_mul()
182 const struct v3d_qpu_instr *instr) in v3d_qpu_disasm_sig_addr()
200 const struct v3d_qpu_instr *instr) in v3d_qpu_disasm_sig()
258 const struct v3d_qpu_instr *instr) in v3d_qpu_disasm_alu()
267 const struct v3d_qpu_instr *instr) in v3d_qpu_disasm_branch()
316 const struct v3d_qpu_instr *instr) in v3d_qpu_decode()
345 struct v3d_qpu_instr instr; in v3d_qpu_disasm() local
354 const struct v3d_qpu_instr *instr) in v3d_qpu_dump()
|
| /external/tensorflow/tensorflow/compiler/xla/service/gpu/ |
| D | gpu_fusible.cc | 40 void AppendParams(const HloInstruction& instr, in AppendParams()
52 bool IfFusedReadsElementsMultipleTimes(const HloInstruction& instr) { in IfFusedReadsElementsMultipleTimes()
113 bool IsReduceInputFusion(const HloInstruction& instr) { in IsReduceInputFusion()
136 bool IsInputFusibleReduction(const HloInstruction& instr) { in IsInputFusibleReduction()
147 const HloInstruction& instr) { in GetRealHeroForMultiOutputFusion()
194 bool IsInputFusibleScatter(const HloInstruction& instr) { in IsInputFusibleScatter()
204 bool IsInputFusible(const HloInstruction& instr) { in IsInputFusible()
210 bool IsLoopFusible(const HloInstruction& instr) { in IsLoopFusible()
319 static int64 SharedMemoryUsage(const HloInstruction& instr) { in SharedMemoryUsage()
446 auto producer_has_loop_codegen = [&](const HloInstruction& instr) { in CreatesNestedLoop()
[all …]
|
| /external/tensorflow/tensorflow/compiler/mlir/xla/transforms/ |
| D | mhlo_to_lhlo_with_xla.cc | 211 const HloInstruction* instr, absl::optional<xla::int64> num_operands, in CreateOperands()
227 OpType LhloDialectEmitter::CreateOpWithoutAttrs(const HloInstruction* instr, in CreateOpWithoutAttrs()
236 const HloInstruction* instr, size_t& num_arguments, size_t& num_results, in CreateOpWithoutAttrs()
245 const HloInstruction* instr) { in EmitOp()
412 Status LhloDialectEmitter::DefaultAction(const HloInstruction* instr) { in DefaultAction()
417 const HloInstruction* instr) { in EmitSortOp()
475 const HloInstruction* instr) { in EmitFusionOp()
544 LhloDialectEmitter::GetScatterDimensionNumbers(const HloInstruction* instr) { in GetScatterDimensionNumbers()
559 const HloInstruction* instr) { in EmitScatterOp()
583 const HloInstruction* instr) { in EmitSelectAndScatterOp()
[all …]
|
| /external/strace/tests/ |
| D | print_quoted_string.c | 13 print_quoted_string_ex(const char *instr, bool quote, const char *escape_chars) in print_quoted_string_ex()
19 print_quoted_string(const char *instr) in print_quoted_string()
25 print_quoted_cstring(const char *instr, const size_t size) in print_quoted_cstring()
37 print_quoted_stringn(const char *instr, const size_t size) in print_quoted_stringn()
72 print_quoted_memory_ex(const void *const instr, const size_t len, in print_quoted_memory_ex()
123 print_quoted_memory(const void *const instr, const size_t len) in print_quoted_memory()
129 print_quoted_hex(const void *const instr, const size_t len) in print_quoted_hex()
|
| /external/strace/tests-m32/ |
| D | print_quoted_string.c | 13 print_quoted_string_ex(const char *instr, bool quote, const char *escape_chars) in print_quoted_string_ex()
19 print_quoted_string(const char *instr) in print_quoted_string()
25 print_quoted_cstring(const char *instr, const size_t size) in print_quoted_cstring()
37 print_quoted_stringn(const char *instr, const size_t size) in print_quoted_stringn()
72 print_quoted_memory_ex(const void *const instr, const size_t len, in print_quoted_memory_ex()
123 print_quoted_memory(const void *const instr, const size_t len) in print_quoted_memory()
129 print_quoted_hex(const void *const instr, const size_t len) in print_quoted_hex()
|
| /external/strace/tests-mx32/ |
| D | print_quoted_string.c | 13 print_quoted_string_ex(const char *instr, bool quote, const char *escape_chars) in print_quoted_string_ex()
19 print_quoted_string(const char *instr) in print_quoted_string()
25 print_quoted_cstring(const char *instr, const size_t size) in print_quoted_cstring()
37 print_quoted_stringn(const char *instr, const size_t size) in print_quoted_stringn()
72 print_quoted_memory_ex(const void *const instr, const size_t len, in print_quoted_memory_ex()
123 print_quoted_memory(const void *const instr, const size_t len) in print_quoted_memory()
129 print_quoted_hex(const void *const instr, const size_t len) in print_quoted_hex()
|
| /external/mesa3d/src/panfrost/util/ |
| D | pan_sysval.c | 31 panfrost_sysval_for_ssbo(nir_intrinsic_instr *instr) in panfrost_sysval_for_ssbo()
41 panfrost_sysval_for_sampler(nir_intrinsic_instr *instr) in panfrost_sysval_for_sampler()
52 panfrost_nir_sysval_for_intrinsic(nir_intrinsic_instr *instr) in panfrost_nir_sysval_for_intrinsic()
72 panfrost_sysval_for_instr(nir_instr *instr, nir_dest *dest) in panfrost_sysval_for_instr()
108 panfrost_nir_assign_sysval_body(struct panfrost_sysvals *ctx, nir_instr *instr) in panfrost_nir_assign_sysval_body()
|
| /external/mesa3d/src/broadcom/compiler/ |
| D | v3d_nir_lower_robust_buffer_access.c | 29 nir_intrinsic_instr *instr, in rewrite_offset()
57 nir_intrinsic_instr *instr) in lower_load()
76 nir_intrinsic_instr *instr) in lower_store()
85 nir_intrinsic_instr *instr) in lower_atomic()
94 nir_intrinsic_instr *instr) in lower_shared()
105 lower_instr(struct v3d_compile *c, nir_builder *b, struct nir_instr *instr) in lower_instr()
|
| /external/mesa3d/src/freedreno/ir3/ |
| D | ir3_sched.c | 43 #define di(instr, fmt, ...) do { if (SCHED_DEBUG) { \ argument
106 struct ir3_instruction *instr; member
151 static bool is_scheduled(struct ir3_instruction *instr) in is_scheduled()
157 schedule(struct ir3_sched_ctx *ctx, struct ir3_instruction *instr) in schedule()
248 could_sched(struct ir3_instruction *instr, struct ir3_instruction *src) in could_sched()
264 struct ir3_instruction *instr) in check_instr()
381 nearest_use(struct ir3_instruction *instr) in nearest_use()
400 use_count(struct ir3_instruction *instr) in use_count()
411 live_effect(struct ir3_instruction *instr) in live_effect()
443 would_sync(struct ir3_sched_ctx *ctx, struct ir3_instruction *instr) in would_sync()
[all …]
|
| /external/mesa3d/src/gallium/drivers/freedreno/a2xx/ |
| D | ir2_nir.c | 253 struct ir2_instr *instr) in set_index()
272 struct ir2_instr *instr; in ir2_instr_create() local
331 struct ir2_instr *instr = ir2_instr_create(ctx, IR2_ALU); in instr_create_alu() local
346 struct ir2_instr *instr; in instr_create_alu_reg() local
363 struct ir2_instr *instr; in instr_create_alu_dest() local
373 struct ir2_instr *instr = ir2_instr_create(ctx, IR2_FETCH); in ir2_instr_create_fetch() local
384 struct ir2_instr *instr; in make_src_noconst() local
401 struct ir2_instr *instr; in emit_alu() local
488 struct ir2_instr *instr; in load_input() local
556 struct ir2_instr *instr; in store_output() local
[all …]
|