Home
last modified time | relevance | path

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

123456

/freebsd/crypto/openssl/crypto/chacha/asm/
H A Dchacha-loongarch64.pl17 my ($t0,$t1,$t2,$t3,$t4,$t5,$t6,$t7,$t8,$x)=map("\$r$_",(12..21));
195 la.local $t8,.Lsigma
196 ld.w @x[0],$t8,0 # 'expa'
197 ld.w @x[1],$t8,4 # 'nd 3'
198 ld.w @x[2],$t8,8 # '2-by'
199 ld.w @x[3],$t8,12 # 'te k'
220 ori $t8,$zero,10
231 addi.w $t8,$t8,-1
232 bnez $t8,.Loop_1x
235 la.local $t8,.Lsigma
[all …]
/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/crypto/openssl/crypto/aes/asm/
H A Daes-riscv32-zkn.pl474 my ($T0,$T1,$T2,$T3,$T4,$T5,$T6,$T7,$T8) = use_regs(13..17,28..31);
652 li $T8,$rcon[$rnum]
653 xor $T0,$T0,$T8
658 @{[rori $T8,$T7,8]}
662 srli $T8,$T7,8
664 or $T8,$T8,$BITS
668 @{[fwdsbox4 $T0,$T8]}
969 # BITS and T8 are temp variables
971 @{[invm4 $T8,$BITS,$T4]}
972 sw $T8,16($KEYP)
[all …]
H A Daes-riscv64.pl85 my ($T4,$T5,$T6,$T7,$T8,$T9,$T10,$T11) = use_regs(17..24);
277 [$T8,$T9,$T10,$T11],
310 xor $T4,$T4,$T8
372 [$T8,$T9,$T10,$T11],
398 slli $T8,$T8,8
417 xor $T8,$T8,$T12
422 xor $T0,$T4,$T8
429 # T0 = [T1 T13 T9 T5 T0 T12 T8 T4]
509 [$T8,$T9,$T10,$T11],
540 xor $T4,$T4,$T8
[all …]
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/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 …]
/freebsd/crypto/openssl/crypto/md5/asm/
H A Dmd5-loongarch64.pl19 my ($t0,$t1,$t2,$t3,$t4,$t5,$t6,$t7,$t8,$x)=map("\$r$_",(12..21));
51 lu12i.w $t8,$T_i_h /* load bits [31:12] of constant */
53 ori $t8,$t8,$T_i_l /* load bits [11:0] of constant */
55 add.w $t7,$t2,$t8 /* dst + X[k] + Const */
84 lu12i.w $t8,$T_i_h /* load bits [31:12] of Constant */
86 ori $t8,$t8,$T_i_l /* load bits [11:0] of Constant */
88 add.w $t7,$t2,$t8 /* dst + X[k] + Const */
117 lu12i.w $t8,$T_i_h /* load bits [31:12] of Constant */
119 ori $t8,$t8,$T_i_l /* load bits [11:0] of Constant */
120 add.w $t7,$t2,$t8 /* dst + X[k] + Const */
[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" \
/freebsd/crypto/openssh/regress/
H A DMakefile5 REGRESS_TARGETS= t1 t2 t3 t4 t5 t6 t7 t8 t9 t10 t11 t12
151 t8.out t8.out.pub t9.out t9.out.pub \
213 $(OBJ)/t8.out:
218 t8: $(OBJ)/t8.out target
220 ${TEST_SSH_SSHKEYGEN} -lf $(OBJ)/t8.out > /dev/null ; \
221 ${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/ec/asm/
H A Decp_sm2p256-armv8.pl26 my ($t4,$t5,$t6,$t7,$t8)=map("x$_",(15..17,19,20));
641 adcs $t8,xzr,xzr
647 adcs $t8,$t8,xzr
653 adcs $t8,$t8,xzr
659 adcs $t8,$t8,$t1
665 adcs $t8,$t8,$t1
671 adds $s6,$t8,$t0
791 umulh $t8,$s7,$s7
799 adcs $t4,$t4,$t8
/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()

123456