Home
last modified time | relevance | path

Searched refs:instr2 (Results 1 – 25 of 29) sorted by relevance

12

/external/tensorflow/tensorflow/compiler/xla/service/
Dmulti_output_fusion.cc133 HloInstruction* instr2) { in Fuse() argument
135 HloInstruction* fused = instr2; in Fuse()
194 HloInstruction* instr2) { in GetNewFusibles() argument
196 HloInstruction* fused = instr2; in GetNewFusibles()
198 fusion = instr2; in GetNewFusibles()
241 HloInstruction* instr2) { in UpdateBeforeFuse() argument
243 HloInstruction* fused = instr2; in UpdateBeforeFuse()
245 fusion = instr2; in UpdateBeforeFuse()
293 HloInstruction* instr2) { in LegalToFuse() argument
297 return LegalToFuseMainConstraints(instr1, instr2); in LegalToFuse()
[all …]
Dmulti_output_fusion.h66 HloInstruction* instr2) = 0;
74 virtual int64 GetProfit(HloInstruction* instr1, HloInstruction* instr2) = 0;
80 virtual bool LegalToFuse(HloInstruction* instr1, HloInstruction* instr2);
85 HloInstruction* instr2);
89 virtual HloInstruction* Fuse(HloInstruction* instr1, HloInstruction* instr2);
102 HloInstruction* instr1, HloInstruction* instr2,
118 HloInstruction* instr1, HloInstruction* instr2);
137 HloInstruction* instr2; member
139 ToBeFused(HloInstruction* instr1, HloInstruction* instr2, int64 score) in ToBeFused()
140 : instr1(instr1), instr2(instr2), score(score) {} in ToBeFused()
[all …]
Dhlo_verifier.cc1273 const HloInstruction* instr2) { in CheckSameChannel() argument
1274 if (instr1->channel_id() != instr2->channel_id()) { in CheckSameChannel()
1278 instr1->ToString(), *instr1->channel_id(), instr2->ToString(), in CheckSameChannel()
1279 *instr2->channel_id()); in CheckSameChannel()
1288 const HloInstruction* instr2) { in CheckSameIsHostTransfer() argument
1292 DynCast<const HloSendRecvInstruction>(instr2); in CheckSameIsHostTransfer()
1300 instr1->ToString(), instr2->ToString()); in CheckSameIsHostTransfer()
Dhlo_instruction_test.cc1774 auto instr2 = instr1->Clone(); in TEST_F() local
1775 EXPECT_TRUE(instr1->Identical(*instr2)); in TEST_F()
1779 EXPECT_FALSE(instr1->Identical(*instr2)); in TEST_F()
1786 auto instr2 = instr1->Clone(); in TEST_F() local
1787 EXPECT_TRUE(instr1->Identical(*instr2)); in TEST_F()
1792 EXPECT_FALSE(instr1->Identical(*instr2)); in TEST_F()
1799 auto instr2 = instr1->Clone(); in TEST_F() local
1800 EXPECT_TRUE(instr1->Identical(*instr2)); in TEST_F()
1804 EXPECT_FALSE(instr1->Identical(*instr2)); in TEST_F()
/external/compiler-rt/test/profile/
Dinstrprof-shared.test6 3. libt-no-instr2.so is built with profile rt linked in (via -u<hook>), but the object file is built
19 RUN: %clang -c -o %t.d/instrprof-shared-lib-no-instr2.o -fPIC %S/Inputs/instrprof-shared-lib.c
20 RUN: %clang_profgen -o %t.d/libt-no-instr2.so -fPIC -shared %t.d/instrprof-shared-lib-no-instr2.o
24 RUN: %clang_profgen -o %t-instr-no-instr2 -L%t.d -rpath %t.d -lt-no-instr2 %S/Inputs/instrprof-sha…
27 RUN: %clang -o %t-no-instr1-no-instr2 -L%t.d -rpath %t.d -lt-no-instr2 %S/Inputs/instrprof-shared-…
28 RUN: %clang -c -o %t.d/instrprof-shared-main-no-instr2.o %S/Inputs/instrprof-shared-main.c
29 RUN: %clang -o %t-no-instr2-instr -L%t.d -rpath %t.d -lt-instr %t.d/instrprof-shared-main-no-instr…
30 RUN: %clang -o %t-no-instr2-no-instr1 -L%t.d -rpath %t.d -lt-no-instr1 %t.d/instrprof-shared-main-…
31 RUN: %clang -o %t-no-instr2-no-instr2 -L%t.d -rpath %t.d -lt-no-instr2 %t.d/instrprof-shared-main-…
35 RUN: env LLVM_PROFILE_FILE=%t-instr-no-instr2.profraw %run %t-instr-no-instr2
[all …]
/external/v8/src/codegen/mips/
Dassembler-mips-inl.h126 Instr instr2 = Assembler::instr_at(pc + 1 * kInstrSize); in set_target_internal_reference_encoded_at() local
128 DCHECK(Assembler::IsOri(instr2) || Assembler::IsJicOrJialc(instr2)); in set_target_internal_reference_encoded_at()
130 instr2 &= ~kImm16Mask; in set_target_internal_reference_encoded_at()
133 if (Assembler::IsJicOrJialc(instr2)) { in set_target_internal_reference_encoded_at()
139 Assembler::instr_at_put(pc + 1 * kInstrSize, instr2 | jic_offset_u); in set_target_internal_reference_encoded_at()
142 PatchLuiOriImmediate(pc, imm, instr1, 0 * kInstrSize, instr2, in set_target_internal_reference_encoded_at()
212 Instr instr2 = Assembler::instr_at(pc_ + 1 * kInstrSize); in target_internal_reference() local
214 DCHECK(Assembler::IsOri(instr2) || Assembler::IsJicOrJialc(instr2)); in target_internal_reference()
215 if (Assembler::IsJicOrJialc(instr2)) { in target_internal_reference()
217 Assembler::CreateTargetAddress(instr1, instr2)); in target_internal_reference()
[all …]
Dassembler-mips.cc855 Instr instr2 = instr_at(pos + 1 * kInstrSize); in target_at() local
856 DCHECK(IsOri(instr2) || IsJicOrJialc(instr2)); in target_at()
858 if (IsJicOrJialc(instr2)) { in target_at()
859 imm = CreateTargetAddress(instr1, instr2); in target_at()
861 imm = GetLuiOriImmediate(instr1, instr2); in target_at()
979 Instr instr2 = instr_at(pos + 1 * kInstrSize); in target_at_put() local
980 DCHECK(IsOri(instr2) || IsJicOrJialc(instr2)); in target_at_put()
983 DCHECK(IsLui(instr1) && (IsJicOrJialc(instr2) || IsOri(instr2))); in target_at_put()
985 instr2 &= ~kImm16Mask; in target_at_put()
987 if (IsJicOrJialc(instr2)) { in target_at_put()
[all …]
Dassembler-mips.h185 Instr instr2 = instr_at( in pc_offset_for_safepoint() local
192 DCHECK(GetOpcodeField(instr2) == SPECIAL && in pc_offset_for_safepoint()
193 GetFunctionField(instr2) == JALR); in pc_offset_for_safepoint()
1565 static int32_t GetLuiOriImmediate(Instr instr1, Instr instr2);
1812 Address offset_lui, Instr instr2,
1815 Address offset_lui, Instr instr2,
/external/tensorflow/tensorflow/compiler/xla/service/gpu/
Dmulti_output_fusion.cc41 HloInstruction* instr2) { in ShapesCompatibleForFusion() argument
42 return ShapesCompatibleForMultiOutputFusion(*instr1, *instr2); in ShapesCompatibleForFusion()
50 HloInstruction* instr2) { in GetProfit() argument
58 for (auto instr : instr2->operands()) { in GetProfit()
63 VLOG(2) << "Fusing instr1=" << instr1->name() << " instr2=" << instr2->name() in GetProfit()
69 HloInstruction* instr2) { in LegalToFuse() argument
70 if (!MultiOutputFusion::LegalToFuse(instr1, instr2)) { in LegalToFuse()
80 if ((instr2->opcode() == HloOpcode::kFusion && in LegalToFuse()
81 instr1->fusion_kind() != instr2->fusion_kind()) || in LegalToFuse()
82 (IsReductionFromOrToContiguousDimensions(*instr2) && in LegalToFuse()
[all …]
Dmulti_output_fusion.h34 HloInstruction* instr2) override;
44 int64 GetProfit(HloInstruction* instr1, HloInstruction* instr2) override;
47 bool LegalToFuse(HloInstruction* instr1, HloInstruction* instr2) override;
Dgpu_fusible.cc118 const HloInstruction& instr2) { in ShapesCompatibleForMultiOutputFusion() argument
156 auto* instr_2 = get_real_hero(&instr2); in ShapesCompatibleForMultiOutputFusion()
299 const HloInstruction& instr2) { in FusionWouldBeTooLarge() argument
316 ShapeUtil::SubshapeCount(instr2.shape()); in FusionWouldBeTooLarge()
325 if (instr1.operand_count() + instr2.operand_count() - 1 + in FusionWouldBeTooLarge()
334 operands.insert(instr2.operands().begin(), instr2.operands().end()); in FusionWouldBeTooLarge()
338 operands.erase(&instr2); in FusionWouldBeTooLarge()
Dgpu_fusible.h68 const HloInstruction& instr2);
83 const HloInstruction& instr2);
/external/v8/src/codegen/ppc/
Dassembler-ppc-inl.h284 Instr instr2 = instr_at(pc + kInstrSize); in target_address_at() local
286 if (IsLis(instr1) && IsOri(instr2)) { in target_address_at()
292 static_cast<uint32_t>(instr2 & kImm16Mask)); in target_address_at()
299 (instr2 & kImm16Mask)); in target_address_at()
398 Instr instr2 = instr_at(pc + kInstrSize); in PatchConstantPoolAccessInstruction() local
401 instr2 &= ~kImm16Mask; in PatchConstantPoolAccessInstruction()
402 instr2 |= (lo_word & kImm16Mask); in PatchConstantPoolAccessInstruction()
404 instr_at_put(pc + kInstrSize, instr2); in PatchConstantPoolAccessInstruction()
461 Instr instr2 = instr_at(pc + kInstrSize); in set_target_address_at() local
463 if (IsLis(instr1) && IsOri(instr2)) { in set_target_address_at()
[all …]
Dassembler-ppc.cc336 bool Assembler::Is64BitLoadIntoR12(Instr instr1, Instr instr2, Instr instr3, in Is64BitLoadIntoR12() argument
344 return (((instr1 >> 16) == 0x3D80) && ((instr2 >> 16) == 0x618C) && in Is64BitLoadIntoR12()
350 bool Assembler::Is32BitLoadIntoR12(Instr instr1, Instr instr2) { in Is32BitLoadIntoR12() argument
354 return (((instr1 >> 16) == 0x3D80) && ((instr2 >> 16) == 0x618C)); in Is32BitLoadIntoR12()
Dassembler-ppc.h1143 static bool Is64BitLoadIntoR12(Instr instr1, Instr instr2, Instr instr3,
1146 static bool Is32BitLoadIntoR12(Instr instr1, Instr instr2);
/external/mesa3d/src/compiler/nir/
Dnir_opt_vectorize.c99 instrs_equal(const nir_instr *instr1, const nir_instr *instr2) in instrs_equal() argument
104 nir_alu_instr *alu2 = nir_instr_as_alu(instr2); in instrs_equal()
165 instr_try_combine(struct nir_shader *nir, nir_instr *instr1, nir_instr *instr2, in instr_try_combine() argument
169 assert(instr2->type == nir_instr_type_alu); in instr_try_combine()
171 nir_alu_instr *alu2 = nir_instr_as_alu(instr2); in instr_try_combine()
313 nir_instr_remove(instr2); in instr_try_combine()
373 const nir_instr *instr2 = *(nir_instr **)util_dynarray_begin(arr2); in cmp_func() local
375 return instrs_equal(instr1, instr2); in cmp_func()
Dnir_opt_sink.c195 nir_foreach_instr(instr2, block) { in insert_after_phi()
196 if (instr2->type == nir_instr_type_phi) in insert_after_phi()
199 exec_node_insert_node_before(&instr2->node, in insert_after_phi()
Dnir_instr_set.c549 nir_instrs_equal(const nir_instr *instr1, const nir_instr *instr2) in nir_instrs_equal() argument
551 assert(instr_can_rewrite(instr1) && instr_can_rewrite(instr2)); in nir_instrs_equal()
553 if (instr1->type != instr2->type) in nir_instrs_equal()
559 nir_alu_instr *alu2 = nir_instr_as_alu(instr2); in nir_instrs_equal()
602 nir_deref_instr *deref2 = nir_instr_as_deref(instr2); in nir_instrs_equal()
646 nir_tex_instr *tex2 = nir_instr_as_tex(instr2); in nir_instrs_equal()
679 nir_load_const_instr *load2 = nir_instr_as_load_const(instr2); in nir_instrs_equal()
701 nir_phi_instr *phi2 = nir_instr_as_phi(instr2); in nir_instrs_equal()
721 nir_intrinsic_instr *intrinsic2 = nir_instr_as_intrinsic(instr2); in nir_instrs_equal()
/external/mesa3d/src/gallium/drivers/r600/sfn/
Dsfn_nir_vectorize_vs_inputs.c97 r600_io_access_same_var(const nir_instr *instr1, const nir_instr *instr2) in r600_io_access_same_var() argument
100 instr2->type == nir_instr_type_intrinsic); in r600_io_access_same_var()
103 nir_intrinsic_instr *intr2 = nir_instr_as_intrinsic(instr2); in r600_io_access_same_var()
221 const nir_instr *instr2 = *(nir_instr **)util_dynarray_begin(arr2); in r600_cmp_func() local
223 return r600_io_access_same_var(instr1, instr2); in r600_cmp_func()
/external/v8/src/codegen/s390/
Dassembler-s390.cc433 bool Assembler::Is64BitLoadIntoIP(SixByteInstr instr1, SixByteInstr instr2) { in Is64BitLoadIntoIP() argument
435 return (((instr1 >> 32) == 0xC0C8) && ((instr2 >> 32) == 0xC0C9)); in Is64BitLoadIntoIP()
/external/tensorflow/tensorflow/compiler/tf2xla/
Dxla_compiler_test.cc762 auto instr2 = c2.instructions(j); in TEST_F() local
766 instr2.clear_name(); in TEST_F()
767 instr2.clear_id(); in TEST_F()
768 instr2.clear_operand_ids(); in TEST_F()
774 LOG(INFO) << "instr2 = " << instr2.DebugString(); in TEST_F()
776 instr2.AppendPartialToString(&str2); in TEST_F()
/external/swiftshader/third_party/llvm-7.0/llvm/docs/
DMergeFunctions.rst415 instr0 i32 %pf0 instr1 i32 %pf1 instr2 i32 123
421 instr0 i32 %pg0 instr1 i32 %pg0 instr2 i32 123
434 And instructions with opcode "*instr2*" are equal, because their opcodes and
/external/llvm/docs/
DMergeFunctions.rst415 instr0 i32 %pf0 instr1 i32 %pf1 instr2 i32 123
421 instr0 i32 %pg0 instr1 i32 %pg0 instr2 i32 123
434 And instructions with opcode "*instr2*" are equal, because their opcodes and
/external/icu/icu4c/source/test/intltest/
Dregextst.cpp782 UnicodeString instr2 = "not abc"; in API_Match() local
793 m1->reset(instr2); in API_Match()
795 REGEX_ASSERT(m1->input() == instr2); in API_Match()
837 m1->reset(instr2); in API_Match()
878 m1->reset(instr2); // "not abc" in API_Match()
/external/v8/src/compiler/backend/arm/
Dcode-generator-arm.cc406 #define ASSEMBLE_ATOMIC64_ARITH_BINOP(instr1, instr2) \ argument
414 __ instr2(i.TempRegister(2), r3, Operand(i.InputRegister(1))); \
3424 #define ATOMIC_ARITH_BINOP_CASE(op, instr1, instr2) \ in AssembleArchInstruction() argument
3427 ASSEMBLE_ATOMIC64_ARITH_BINOP(instr1, instr2); \ in AssembleArchInstruction()

12