/freebsd-12-stable/lib/libc/mips/gen/ |
H A D | _ctx_start.S | 45 jalr t9 51 PTR_LA t9, _ctx_done 52 jalr t9
|
H A D | ldexp.S | 89 * Find out how many leading zero bits are in t2,t3 and put in t9. 92 move t9, zero 95 addu t9, 32 99 addu t9, 16 104 addu t9, 8 109 addu t9, 4 114 addu t9, 2 119 addu t9, 1 124 subu t9, t9, DLEAD_ZERO [all...] |
H A D | _setjmp.S | 195 PTR_LA t9, _C_LABEL(longjmperror) 196 jalr t9
|
H A D | setjmp.S | 77 PTR_LA t9, _C_LABEL(sigprocmask) # get current signal mask 78 jalr t9 164 PTR_LA t9,_C_LABEL(sigprocmask) # set current signal mask 165 jal t9 232 PTR_LA t9, _C_LABEL(longjmperror) 233 jalr t9
|
/freebsd-12-stable/contrib/llvm-project/compiler-rt/lib/xray/ |
H A D | xray_trampoline_mips.S | 23 .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) [all...] |
H A D | xray_trampoline_mips64.S | 46 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) [all...] |
/freebsd-12-stable/contrib/llvm-project/compiler-rt/lib/tsan/rtl/ |
H A D | tsan_rtl_mips64.S | 19 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, [all...] |
/freebsd-12-stable/stand/mips/uboot/ |
H A D | start.S | 49 PTR_L t9, syscall_ptr 50 jalr t9
|
/freebsd-12-stable/sys/contrib/octeon-sdk/ |
H A D | cvmx-compactflash.c | 263 int t9; local 280 t9 = 10; 291 t9 = 10; 300 t9 = 10; 309 t9 = 10; 318 t9 = 10; 327 t9 = 15; 336 t9 = 20; 362 t9 = FLASH_RoundUP(t9 * clocks_u [all...] |
/freebsd-12-stable/libexec/rtld-elf/mips/ |
H A D | rtld_start.S | 67 PTR_ADDU t9, a1, t0 68 jalr t9 /* _rtld_relocate_nonplt_self(dynp, relocabase) */ 75 PTR_LA t9, _C_LABEL(_rtld) 76 jalr t9 /* v0 = _rtld(sp, cleanup, objp) */ 84 move t9, v0 86 move ra,t9 /* RA == PC signals backtrace routine to stop */ 87 j t9 /* _start(sp, cleanup, obj); */ 118 PTR_ADDU t9, 8 /* modify T9 to point at .cpload */ 164 PTR_LA t9, _C_LABEL(_mips_rtld_bind) 165 jalr t9 [all...] |
/freebsd-12-stable/lib/libc/mips/sys/ |
H A D | cerror.S | 58 PTR_LA t9, _C_LABEL(__error) # locate address of errno 59 jalr t9
|
/freebsd-12-stable/sys/mips/mips/ |
H A D | fp.S | 710 li t9, 32 # compute 32 - abs(exp diff) 711 subu t9, t9, v1 714 sll t8, t2, t9 # save bits shifted out 718 sll t8, ta2, t9 # save bits shifted out 737 sltu t9, zero, t8 # compute t2:zero - ta2:t8 740 subu t2, t2, t9 # subtract barrow 744 sltu t9, zero, t8 # compute ta2:zero - t2:t8 747 subu t2, t2, t9 # subtract barrow 837 li t9, 3 [all...] |
H A D | pm_machdep.c | 175 regs->t9 = (register_t)(intptr_t)catcher; 409 * point given by the exec_package passed in, as is $t9 (used for PIC 443 td->td_frame->t9 = imgp->entry_addr & ~3; /* abicall req */
|
/freebsd-12-stable/lib/libc/mips/ |
H A D | SYS.h | 79 * ii) Do interprocedure jumps indirectly via t9, with the side-effect of 80 * preserving the callee's entry address in t9. 86 # define PIC_TAILCALL(l) PTR_LA t9, _C_LABEL(l); jr t9 90 # define PIC_TAILCALL(l) PTR_LA t9, _C_LABEL(l); RESTORE_GP64; jr t9
|
/freebsd-12-stable/sys/mips/include/ |
H A D | regdef.h | 82 #define t9 $25 macro
|
H A D | asm.h | 76 * Final addiu to t9 must always equal the size of this _KERN_MCOUNT 83 sw t9,12(sp); \ 85 lui t9,%hi(_mcount); \ 86 addiu t9,t9,%lo(_mcount); \ 87 jalr t9; \ 89 lw t9,4(sp); \ 91 addiu t9,t9,40; \ 523 .cpload t9; \ [all...] |
H A D | frame.h | 81 register_t t9; member in struct:trapframe
|
/freebsd-12-stable/crypto/openssh/regress/ |
H A D | Makefile | 3 REGRESS_TARGETS= unit t1 t2 t3 t4 t5 t6 t7 t8 t9 t10 t11 t12 t-exec 122 t8.out t8.out.pub t9.out t9.out.pub testdata \ 178 $(OBJ)/t9.out: 182 t9: $(OBJ)/t9.out 184 ${TEST_SSH_SSHKEYGEN} -lf $(OBJ)/t9.out > /dev/null 186 ${TEST_SSH_SSHKEYGEN} -Bf $(OBJ)/t9.out > /dev/null
|
/freebsd-12-stable/crypto/openssl/crypto/aes/asm/ |
H A D | aes-mips.pl | 60 # ($t0,$t1,$t2,$t3,$t8,$t9)=map("\$$_",(12..15,24,25)); 121 my ($t0,$t1,$t2,$t3,$t4,$t5,$t6,$t7,$t8,$t9,$t10,$t11) = map("\$$_",(12..23)); 171 lwxs $t9,$i1($Tbl) # Te3[s0] 199 rotr $t9,$t9,24 207 xor $t1,$t9 297 lw $t9,0($i1) # Te3[s0] 315 lw $t9,0($i1) # Te3[s0] 337 rotr $t9,$t9,2 [all...] |
/freebsd-12-stable/contrib/bearssl/src/symcipher/ |
H A D | aes_ct.c | 47 uint32_t t0, t1, t2, t3, t4, t5, t6, t7, t8, t9; local 102 t9 = t8 ^ t7; 112 t19 = t9 ^ t14;
|
H A D | aes_ct64.c | 47 uint64_t t0, t1, t2, t3, t4, t5, t6, t7, t8, t9; local 102 t9 = t8 ^ t7; 112 t19 = t9 ^ t14;
|
/freebsd-12-stable/lib/msun/src/ |
H A D | e_lgamma_r.c | 120 t9 = -1.40346469989232843813e-03, /* 0xBF56FE8E, 0xBF2D1AF1 */ variable 260 p1 = t0+w*(t3+w*(t6+w*(t9 +w*t12))); /* parallel comp */
|
/freebsd-12-stable/sys/contrib/libsodium/src/libsodium/crypto_stream/salsa20/xmm6int/ |
H A D | u4.h | 55 __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);
|
H A D | u8.h | 51 __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);
|
/freebsd-12-stable/crypto/openssl/crypto/bn/asm/ |
H A D | mips.pl | 99 ($t0,$t1,$t2,$t3,$t8,$t9)=map("\$$_",(12..15,24,25)); 594 sltu $t9,$ta1,$t1 598 $ADDU $v0,$t9 608 sltu $t9,$ta3,$t3 615 $ADDU $v0,$t9 637 sltu $t9,$ta1,$t1 641 $ADDU $v0,$t9 724 sltu $t9,$t1,$ta1 729 $ADDU $v0,$t9 739 sltu $t9, [all...] |