Home
last modified time | relevance | path

Searched full:t9 (Results 1 – 25 of 89) sorted by relevance

1234

/freebsd/contrib/llvm-project/compiler-rt/lib/tsan/rtl/
H A Dtsan_rtl_mips64.S19 daddu $gp,$gp,$t9
39 // load pointer of libc setjmp to t9
40 dla $t9,(_ZN14__interception11real_setjmpE)
50 ld $t9,0($t9)
51 jr $t9
71 daddu $gp,$gp,$t9
91 // load pointer of libc _setjmp to t9
92 dla $t9,(_ZN14__interception12real__setjmpE)
102 ld $t9,0($t9)
103 jr $t9
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/xray/
H A Dxray_trampoline_mips.S23 .cpload $t9
37 la $t9, _ZN6__xray19XRayPatchedFunctionE
38 lw $t9, 0($t9)
40 beqz $t9, FunctionEntry_restore
46 jalr $t9
70 .cpload $t9
84 la $t9, _ZN6__xray19XRayPatchedFunctionE
85 lw $t9, 0($t9)
87 beqz $t9, FunctionExit_restore
93 jalr $t9
H A Dxray_mips64.cpp70 // sd t9, 0(sp) ;save register t9 in patchSled()
71 // lui t9, %highest(__xray_FunctionEntry/Exit) in patchSled()
72 // ori t9, t9, %higher(__xray_FunctionEntry/Exit) in patchSled()
73 // dsll t9, t9, 16 in patchSled()
74 // ori t9, t9, %hi(__xray_FunctionEntry/Exit) in patchSled()
75 // dsll t9, t9, 16 in patchSled()
76 // ori t9, t9, %lo(__xray_FunctionEntry/Exit) in patchSled()
78 // jalr t9 ;call Tracing hook in patchSled()
80 // ld t9, 0(sp) ;restore register t9 in patchSled()
H A Dxray_trampoline_mips64.S46 daddu $gp, $gp, $t9
49 dla $t9, _ZN6__xray19XRayPatchedFunctionE
50 ld $t9, 0($t9)
52 beqz $t9, FunctionEntry_restore
58 jalr $t9
106 daddu $gp, $gp, $t9
109 dla $t9, _ZN6__xray19XRayPatchedFunctionE
110 ld $t9, 0($t9)
112 beqz $t9, FunctionExit_restore
118 jalr $t9
H A Dxray_mips.cpp62 // ADDIU T9, T9, 44 in patchSled()
70 // sw t9, 0(sp) ;save register t9 in patchSled()
71 // lui t9, %hi(__xray_FunctionEntry/Exit) in patchSled()
72 // ori t9, t9, %lo(__xray_FunctionEntry/Exit) in patchSled()
74 // jalr t9 ;call Tracing hook in patchSled()
76 // lw t9, 0(sp) ;restore register t9 in patchSled()
80 // We add 44 bytes to t9 because we want to adjust the function pointer to in patchSled()
84 // global offset table address, t9 must hold the address of the instruction in patchSled()
/freebsd/contrib/llvm-project/llvm/lib/ExecutionEngine/Orc/
H A DOrcABISupport.cpp545 0xafb9005c, // 0x60: sw $t9,92($sp) in writeResolverCode()
557 0x00000000, // 0x7c: lui $t9,reentry in writeResolverCode()
558 0x00000000, // 0x80: addiu $t9,$t9,reentry in writeResolverCode()
560 0x0320f809, // 0x84: jalr $t9 in writeResolverCode()
564 0x8fb9005c, // 0x94: lw $t9,92($sp) in writeResolverCode()
588 0x03200008, // 0xf4: jr $t9 in writeResolverCode()
589 0x00000000, // 0xf8: move $t9, $v0/v1 in writeResolverCode()
632 // lui $t9,ResolverAddr in writeTrampolines()
633 // addiu $t9,$t9,ResolverAddr in writeTrampolines()
634 // jalr $t9 in writeTrampolines()
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/sanitizer_common/
H A Dsanitizer_asm.h67 // $t9 to get the address of current function, instead of PCREL, even
68 // on MIPSr6. To be compatiable with them, we have to set $t9 properly.
73 "daddu $t8, $t8, $t9\n" \
75 "ld $t9, %got_disp(" i_func ")($t8)\n" \
76 "jr $t9\n"
80 ".cpload $t9\n" \
82 "lw $t9, %got(" i_func ")($gp)\n" \
83 "jr $t9\n"
/freebsd/contrib/llvm-project/llvm/lib/Target/Mips/
H A DMipsMachineFunction.cpp92 // daddu $v1, $v0, $t9 in initGlobalBaseReg()
116 MF.getRegInfo().addLiveIn(Mips::T9); in initGlobalBaseReg()
117 MBB.addLiveIn(Mips::T9); in initGlobalBaseReg()
121 // addu $v1, $v0, $t9 in initGlobalBaseReg()
126 BuildMI(MBB, I, DL, TII.get(Mips::ADDu), V1).addReg(V0).addReg(Mips::T9); in initGlobalBaseReg()
139 // 2. addu $globalbasereg, $2, $t9 in initGlobalBaseReg()
154 .addReg(Mips::V0).addReg(Mips::T9); in initGlobalBaseReg()
H A DMipsAsmPrinter.cpp1114 // ADDIU T9, T9, 52 in EmitSled()
1124 // SW T9, 0(SP) in EmitSled()
1125 // LUI T9, %hi(__xray_FunctionEntry/Exit) in EmitSled()
1126 // ORI T9, T9, %lo(__xray_FunctionEntry/Exit) in EmitSled()
1128 // JALR T9 in EmitSled()
1130 // LW T9, 0(SP) in EmitSled()
1134 // We add 52 bytes to t9 because we want to adjust the function pointer to in EmitSled()
1138 // global offset table address, t9 must hold the address of the instruction in EmitSled()
1157 // SD T9, 0(SP) in EmitSled()
1158 // LUI T9, %highest(__xray_FunctionEntry/Exit) in EmitSled()
[all …]
H A DMipsOptimizePICCall.cpp147 /// copy $t9, $vreg
148 /// jalr $t9
154 unsigned DstReg = getRegTy(SrcReg, MF) == MVT::i32 ? Mips::T9 : Mips::T9_64; in setCallTargetReg()
/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 \
221 $(OBJ)/t9.out:
225 t9: $(OBJ)/t9.out target
227 ${TEST_SSH_SSHKEYGEN} -lf $(OBJ)/t9.out > /dev/null
229 ${TEST_SSH_SSHKEYGEN} -Bf $(OBJ)/t9.out > /dev/null
/freebsd/lib/msun/src/
H A Ds_tanhl.c50 T9 = 2.1869488531393817e-2, /* 0x1664f488172022.0p-58 */ variable
65 T9 = 2.18694885361552028218693591149061717e-2L, /* 0x1664f4882c10f9f32d6b1a12a25e5.0p-118L */ variable
139 ((T11*x2 + T9)*x4 + (T7*x2 + T5))*(x2*x*x2) + in tanhl()
146 T15)*x2 + T13)*x2 + T11)*x2 + T9)*x2 + T7)*x2 + T5)* in tanhl()
152 T15)*x2 + T13)*x2 + T11)*x2 + T9)*x2 + T7)*x2 + T5)* in tanhl()
/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));
175 lwxs $t9,$i1($Tbl) # Te3[s0]
203 rotr $t9,$t9,24
211 xor $t1,$t9
302 ext $t9,$s0,0,8
308 $PTR_INS $i1,$t9,2,8
314 lw $t9,0($i1) # Te3[s0]
332 lw $t9,0($i1) # Te3[s0]
354 rotr $t9,$t9,24
[all …]
/freebsd/crypto/openssl/crypto/modes/asm/
H A Daes-gcm-armv8_64.pl208 my $t9="v30";
602 eor $t9.8b, $t9.8b, $res3.8b @ GHASH block 4k+3 - mid
614 pmull $t9.1q, $t9.1d, $h12k.1d @ GHASH block 4k+3 - mid
647 eor $acc_mb, $acc_mb, $t9.16b @ GHASH block 4k+3 - mid
653 eor $t9.16b, $acc_lb, $acc_hb @ MODULO - karatsuba tidy up
667 eor $acc_mb, $acc_mb, $t9.16b @ MODULO - karatsuba tidy up
796 eor $t9.8b, $t9.8b, $res3.8b @ GHASH block 4k+3 - mid
815 pmull $t9.1q, $t9.1d, $h12k.1d @ GHASH block 4k+3 - mid
825 eor $acc_mb, $acc_mb, $t9.16b @ GHASH block 4k+3 - mid
1088 eor $t9.16b, $acc_lb, $acc_hb @ MODULO - karatsuba tidy up
[all …]
/freebsd/contrib/llvm-project/llvm/lib/ExecutionEngine/RuntimeDyld/
H A DRuntimeDyld.cpp991 // 0: 3c190000 lui t9,%hi(addr). in createStubFunction()
992 // 4: 27390000 addiu t9,t9,%lo(addr). in createStubFunction()
993 // 8: 03200008 jr t9. in createStubFunction()
1008 // 0: 3c190000 lui t9,%highest(addr). in createStubFunction()
1009 // 4: 67390000 daddiu t9,t9,%higher(addr). in createStubFunction()
1010 // 8: 0019CC38 dsll t9,t9,16. in createStubFunction()
1011 // c: 67390000 daddiu t9,t9,%hi(addr). in createStubFunction()
1012 // 10: 0019CC38 dsll t9,t9,16. in createStubFunction()
1013 // 14: 67390000 daddiu t9,t9,%lo(addr). in createStubFunction()
1014 // 18: 03200008 jr t9. in createStubFunction()
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_stream/salsa20/xmm6int/
H A Du8.h51 __m256i t8, t9; variable
61 t9 = _mm256_add_epi64(addv9, z9);
63 z8 = _mm256_unpacklo_epi32(t8, t9);
64 z9 = _mm256_unpackhi_epi32(t8, t9);
67 t9 = _mm256_unpackhi_epi32(z8, z9);
71 z9 = _mm256_permutevar8x32_epi32(t9, permute);
H A Du4.h55 __m128i t8, t9; variable
62 t9 = _mm_set1_epi64x(in89);
65 z9 = _mm_add_epi64(addv9, t9);
68 t9 = _mm_unpackhi_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));
596 sltu $t9,$ta1,$t1
600 $ADDU $v0,$t9
610 sltu $t9,$ta3,$t3
617 $ADDU $v0,$t9
639 sltu $t9,$ta1,$t1
643 $ADDU $v0,$t9
726 sltu $t9,$t1,$ta1
731 $ADDU $v0,$t9
741 sltu $t9,$t3,$ta3
[all …]
/freebsd/lib/msun/ld128/
H A Dk_tanl.c29 T9 = 0x1.664f4882c10f9f32d6bbe09d8bcdp-6L, variable
81 r = T5 + w * (T9 + w * (T13 + w * (T17 + w * (T21 + in __kernel_tanl()
/freebsd/lib/msun/ld80/
H A Dk_tanl.c53 T9 = 0.021869488536312216, /* 0x1664f4882cc1c2.0p-58 */ variable
89 r = T5 + w * (T9 + w * (T13 + w * (T17 + w * (T21 + in __kernel_tanl()
/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
102 t9 = t8 ^ t7; in br_aes_ct_bitslice_Sbox()
112 t19 = t9 ^ t14; 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
102 t9 = t8 ^ t7; in br_aes_ct64_bitslice_Sbox()
112 t19 = t9 ^ t14; in br_aes_ct64_bitslice_Sbox()
/freebsd/crypto/openssl/test/certs/
H A Dwrongkey.pem15 t9/+N+i/fF7c9yKICxefNcO/Q1i4hozTimQHEWpCDKgystBrWl+CopRrq/QMndGh
/freebsd/sys/contrib/device-tree/src/arm64/mediatek/
H A Dmt8186-corsola-tentacruel-sku262144.dts27 MATRIX_KEY(0x01, 0x09, 0) /* T9 */
H A Dmt8186-corsola-tentacool-sku327681.dts35 MATRIX_KEY(0x01, 0x09, 0) /* T9 */

1234