Searched refs:t9 (Results 1 - 25 of 41) sorted by relevance

12

/freebsd-12-stable/lib/libc/mips/gen/
H A D_ctx_start.S45 jalr t9
51 PTR_LA t9, _ctx_done
52 jalr t9
H A Dldexp.S89 * 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.S195 PTR_LA t9, _C_LABEL(longjmperror)
196 jalr t9
H A Dsetjmp.S77 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 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)
[all...]
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)
[all...]
/freebsd-12-stable/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,
[all...]
/freebsd-12-stable/stand/mips/uboot/
H A Dstart.S49 PTR_L t9, syscall_ptr
50 jalr t9
/freebsd-12-stable/sys/contrib/octeon-sdk/
H A Dcvmx-compactflash.c263 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 Drtld_start.S67 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 Dcerror.S58 PTR_LA t9, _C_LABEL(__error) # locate address of errno
59 jalr t9
/freebsd-12-stable/sys/mips/mips/
H A Dfp.S710 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 Dpm_machdep.c175 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 DSYS.h79 * 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 Dregdef.h82 #define t9 $25 macro
H A Dasm.h76 * 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 Dframe.h81 register_t t9; member in struct:trapframe
/freebsd-12-stable/crypto/openssh/regress/
H A DMakefile3 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 Daes-mips.pl60 # ($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 Daes_ct.c47 uint32_t t0, t1, t2, t3, t4, t5, t6, t7, t8, t9; local
102 t9 = t8 ^ t7;
112 t19 = t9 ^ t14;
H A Daes_ct64.c47 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 De_lgamma_r.c120 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 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);
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);
/freebsd-12-stable/crypto/openssl/crypto/bn/asm/
H A Dmips.pl99 ($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...]

Completed in 235 milliseconds

12