Home
last modified time | relevance | path

Searched full:t8 (Results 1 – 25 of 108) sorted by relevance

12345

/freebsd/contrib/llvm-project/llvm/lib/ExecutionEngine/JITLink/
H A Dloongarch.cpp25 0x14, 0x00, 0x00, 0x1a, // pcalau12i $t8, %page20(imm)
26 0x94, 0x02, 0xc0, 0x28, // ld.d $t8, $t8, %pageoff12(imm)
27 0x80, 0x02, 0x00, 0x4c // jr $t8
31 0x14, 0x00, 0x00, 0x1a, // pcalau12i $t8, %page20(imm)
32 0x94, 0x02, 0x80, 0x28, // ld.w $t8, $t8, %pageoff12(imm)
33 0x80, 0x02, 0x00, 0x4c // jr $t8
/freebsd/contrib/llvm-project/llvm/lib/Target/X86/
H A DX86InstrAMX.td24 T8, PS;
29 T8, PD;
34 T8, XD;
39 T8, PD;
44 T8, XS;
55 "tilerelease", [(int_x86_tilerelease)]>, VEX, T8, PS;
58 VEX, T8, XD;
104 VEX, VVVV, T8, XD;
108 VEX, VVVV, T8, XS;
112 VEX, VVVV, T8, PD;
[all …]
H A DX86InstrRAOINT.td36 defm AADD : RaoInt<"add">, T8;
37 defm AAND : RaoInt<"and">, T8, PD;
38 defm AOR : RaoInt<"or" >, T8, XD;
39 defm AXOR : RaoInt<"xor">, T8, XS;
H A DX86InstrKL.td48 [(int_x86_loadiwkey XMM0, VR128:$src1, VR128:$src2, EAX)]>, T8, XS;
53 def ENCODEKEY128 : Encodekey<0xFA, "encodekey128">, T8;
56 def ENCODEKEY256 : Encodekey<0xFB, "encodekey256">, T8;
59 defm "" : Aesencdec<"">, T8;
73 defm "" : Aesencdecwide<"">, T8;
H A DX86InstrVMX.td20 "invept\t{$src2, $src1|$src1, $src2}", []>, T8, PD,
23 "invept\t{$src2, $src1|$src1, $src2}", []>, T8, PD,
31 "invvpid\t{$src2, $src1|$src1, $src2}", []>, T8, PD,
34 "invvpid\t{$src2, $src1|$src1, $src2}", []>, T8, PD,
H A DX86InstrUtils.td28 class T8 { Map OpMap = T8; }
684 // SS38I - SSSE3 instructions with T8 prefix.
686 // MMXSS38I - SSSE3 instructions with T8 prefix and MMX operands.
695 : I<o, F, outs, ins, asm, pattern, SSEPackedInt>, T8, PD,
703 : I<o, F, outs, ins, asm, pattern, SSEPackedInt>, T8,
712 // SS48I - SSE 4.1 instructions with T8 prefix.
717 : I<o, F, outs, ins, asm, pattern, SSEPackedInt>, T8, PD,
726 // SS428I - SSE 4.2 instructions with T8 prefix.
729 : I<o, F, outs, ins, asm, pattern, SSEPackedInt>, T8, PD,
741 // AVX8I - AVX instructions with T8, PD prefix.
[all …]
H A DX86InstrMisc.td1106 defm MOVBE16 : Movbe<0xF0, Xi16>, OpSize16, T8;
1107 defm MOVBE32 : Movbe<0xF0, Xi32>, OpSize32, T8;
1108 defm MOVBE64 : Movbe<0xF0, Xi64>, T8;
1211 (outs t.RegClass:$dst), []>, T8, VVVV;
1216 (outs t.RegClass:$dst), []>, T8, VVVV;
1294 (node t.RegClass:$src1, t.RegClass:$src2))]>, T8;
1300 t.RegClass:$src2))]>, T8;
1392 T8, VVVV, Sched<[WriteALU]>;
1396 T8, VVVV, Sched<[WriteALU.Folded, WriteALU.ReadAfterFold]>;
1510 T8, Requires<[HasMOVDIRI, NoEGPR]>;
[all …]
H A DX86InstrAVX512.td1054 DestInfo.ExeDomain>, T8, PD, EVEX, Sched<[SchedRR]>;
1066 DestInfo.ExeDomain>, T8, PD, EVEX, EVEX_KZ, Sched<[SchedRR]>;
1080 DestInfo.ExeDomain>, T8, PD, EVEX, EVEX_K, Sched<[SchedRR]>;
1091 DestInfo.ExeDomain>, T8, PD, EVEX,
1105 DestInfo.ExeDomain>, T8, PD, EVEX, EVEX_KZ,
1122 DestInfo.ExeDomain>, T8, PD, EVEX, EVEX_K,
1188 T8, PD, EVEX, Sched<[SchedRR]>;
1200 "$src0 = $dst">, T8, PD, EVEX, Sched<[SchedRR]>;
2108 T8, REX_W, EVEX_CD8<64, CD8VF>;
2124 T8, REX_W, EVEX_CD8<64, CD8VF>;
[all …]
H A DX86InstrFMA3Info.cpp149 (TSFlags & X86II::OpMapMask) == X86II::T8) || in getFMA3Group()
151 ((TSFlags & X86II::OpMapMask) == X86II::T8 || in getFMA3Group()
H A DX86InstrArithmetic.td1364 binop_ndd_args, andn_rr_p>, VVVV, Sched<[WriteALU]>, T8;
1368 Sched<[WriteALU.Folded, WriteALU.ReadAfterFold]>, T8;
1411 (ins t.RegClass:$src), "mulx", mulx_args, []>, T8, XD, VEX,
1415 (ins t.MemOperand:$src), "mulx", mulx_args, []>, T8, XD, VEX,
1421 (ins t.RegClass:$src), "mulx", mulx_args, []>, T8, XD,
1426 (ins t.MemOperand:$src), "mulx", mulx_args, []>, T8, XD,
1450 def ADCX32rr : BinOpRRF_RF<0xF6, "adcx", Xi32>, T8, PD;
1451 def ADCX64rr : BinOpRRF_RF<0xF6, "adcx", Xi64>, T8, PD;
1452 def ADOX32rr : BinOpRRF_RF<0xF6, "adox", Xi32>, T8, XS;
1453 def ADOX64rr : BinOpRRF_RF<0xF6, "adox", Xi64>, T8, XS;
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/sanitizer_common/
H A Dsanitizer_asm.h72 "lui $t8, %hi(%neg(%gp_rel(" t_func ")))\n" \
73 "daddu $t8, $t8, $t9\n" \
74 "daddiu $t8, $t8, %lo(%neg(%gp_rel(" t_func ")))\n" \
75 "ld $t9, %got_disp(" i_func ")($t8)\n" \
H A Dsanitizer_syscall_linux_loongarch64.inc23 // t0-t8 should be considered clobbered
28 "memory", "$t0", "$t1", "$t2", "$t3", "$t4", "$t5", "$t6", "$t7", "$t8"
/freebsd/crypto/openssh/regress/
H A DMakefile5 REGRESS_TARGETS= t1 t2 t3 t4 t5 t6 t7 t8 t9 t10 t11 t12
148 t8.out t8.out.pub t9.out t9.out.pub \
210 $(OBJ)/t8.out:
215 t8: $(OBJ)/t8.out target
217 ${TEST_SSH_SSHKEYGEN} -lf $(OBJ)/t8.out > /dev/null ; \
218 ${TEST_SSH_SSHKEYGEN} -Bf $(OBJ)/t8.out > /dev/null ; \
/freebsd/contrib/llvm-project/llvm/lib/Target/LoongArch/
H A DLoongArchExpandPseudoInsts.cpp504 // Part0: addi.d $t8, $zero, %MO0(sym) in expandLargeAddressLoad()
505 // Part2: lu32i.d $t8, %MO2(sym) in expandLargeAddressLoad()
506 // Part3: lu52i.d $t8, $t8, %MO3(sym) in expandLargeAddressLoad()
507 // Fin: LastOpcode $dst, $t8, $dst in expandLargeAddressLoad()
538 Register ScratchReg = LoongArch::R20; // $t8 in expandLargeAddressLoad()
625 // addi.d $t8, $zero, %desc_pc_lo12(sym) in expandLoadAddressTLSDescPcLarge()
626 // lu32i.d $t8, %desc64_pc_lo20(sym) in expandLoadAddressTLSDescPcLarge()
627 // lu52i.d $t8, $t8, %desc64_pc_hi12(sym) in expandLoadAddressTLSDescPcLarge()
628 // add.d $a0, $a0, $t8 in expandLoadAddressTLSDescPcLarge()
637 Register ScratchReg = LoongArch::R20; // $t8 in expandLoadAddressTLSDescPcLarge()
[all …]
H A DLoongArchRegisterInfo.td80 def R20 : LoongArchReg<20, "r20", ["t8"]>, DwarfRegNum<[20]>;
105 // Temporary registers (t0...t8)
121 // a0...a7, t0...t8
/freebsd/crypto/openssl/crypto/aes/asm/
H A Daes-mips.pl65 # ($t0,$t1,$t2,$t3,$t8,$t9)=map("\$$_",(12..15,24,25));
125 my ($t0,$t1,$t2,$t3,$t4,$t5,$t6,$t7,$t8,$t9,$t10,$t11) = map("\$$_",(12..23));
173 lwxs $t8,$i0($Tbl) # Te3[s3]
201 rotr $t8,$t8,24
210 xor $t0,$t8
300 ext $t8,$s3,0,8
307 $PTR_INS $i0,$t8,2,8
312 lw $t8,0($i0) # Te3[s3]
330 lw $t8,0($i0) # Te3[s3]
353 rotr $t8,$t8,24
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/Mips/
H A DMips16InstrInfo.td116 // Implicit use of T8
122 !strconcat(asmstr, "\t$rx, $imm\n\tmove\t$cc, $$t8"), []> {
176 // Implicit use of T8
182 !strconcat(asmstr, "\t$rx, $ry\n\tmove\t$cc, $$t8"), []> {
341 !strconcat(asmstr, "\t$rx, $ry\n\tmove\t$rz, $$t8"), []> ;
435 // two operands and returns a value in register T8 and
436 //then does a conditional branch based on the value of T8
642 let Uses = [T8];
646 let Uses = [T8];
670 let Uses = [T8];
[all …]
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_stream/salsa20/xmm6int/
H A Du8.h51 __m256i t8, t9; variable
60 t8 = _mm256_add_epi64(addv8, z8);
63 z8 = _mm256_unpacklo_epi32(t8, t9);
64 z9 = _mm256_unpackhi_epi32(t8, t9);
66 t8 = _mm256_unpacklo_epi32(z8, z9);
70 z8 = _mm256_permutevar8x32_epi32(t8, permute);
H A Du4.h55 __m128i t8, t9; variable
61 t8 = _mm_set1_epi64x(in89);
64 z8 = _mm_add_epi64(addv8, t8);
67 t8 = _mm_unpacklo_epi32(z8, z9);
70 z8 = _mm_unpacklo_epi32(t8, t9);
71 z9 = _mm_unpackhi_epi32(t8, t9);
/freebsd/crypto/openssl/crypto/bn/asm/
H A Dmips.pl101 ($t0,$t1,$t2,$t3,$t8,$t9)=map("\$$_",(12..15,24,25));
589 sltu $t8,$ta0,$t0
593 $ADDU $v0,$t8
603 sltu $t8,$ta2,$t2
607 $ADDU $v0,$t8
628 sltu $t8,$ta0,$t0
632 $ADDU $v0,$t8
649 sltu $t8,$ta2,$t2
653 $ADDU $v0,$t8
719 sltu $t8,$t0,$ta0
[all …]
/freebsd/contrib/bearssl/src/symcipher/
H A Daes_ct.c47 uint32_t t0, t1, t2, t3, t4, t5, t6, t7, t8, t9; in br_aes_ct_bitslice_Sbox() local
101 t8 = y5 & y1; in br_aes_ct_bitslice_Sbox()
102 t9 = t8 ^ t7; in br_aes_ct_bitslice_Sbox()
H A Daes_ct64.c47 uint64_t t0, t1, t2, t3, t4, t5, t6, t7, t8, t9; in br_aes_ct64_bitslice_Sbox() local
101 t8 = y5 & y1; in br_aes_ct64_bitslice_Sbox()
102 t9 = t8 ^ t7; in br_aes_ct64_bitslice_Sbox()
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_onetimeauth/poly1305/sse2/
H A Dpoly1305_sse2.c207 xmmi T0, T1, T2, T3, T4, T5, T6, T7, T8; in poly1305_blocks() local
402 T8 = _mm_unpackhi_epi32(T5, T6); in poly1305_blocks()
405 M7 = _mm_unpacklo_epi32(T8, _mm_setzero_si128()); in poly1305_blocks()
406 M8 = _mm_unpackhi_epi32(T8, _mm_setzero_si128()); in poly1305_blocks()
627 T8 = _mm_unpackhi_epi32(T5, T6); in poly1305_blocks()
630 M2 = _mm_unpacklo_epi32(T8, _mm_setzero_si128()); in poly1305_blocks()
631 M3 = _mm_unpackhi_epi32(T8, _mm_setzero_si128()); in poly1305_blocks()
/freebsd/sys/powerpc/powerpc/
H A Dsupport.S204 #define t8 %r0 macro
302 LOAD t8, WORD*7(rs)
311 STORE t8, WORD*7(rd)
/freebsd/contrib/llvm-project/llvm/include/llvm/ExecutionEngine/JITLink/
H A Dloongarch.h270 /// pcalau12i $t8, %page20(ptr)
271 /// ld.[w/d] $t8, %pageoff12(ptr)
272 /// jr $t8

12345