Home
last modified time | relevance | path

Searched full:a0 (Results 1 – 25 of 1052) sorted by relevance

12345678910>>...43

/freebsd/sys/riscv/vmm/
H A Dvmm_switch.S39 * a0 == hypctx *
42 sd ra, (HYP_H_RA)(a0)
43 sd sp, (HYP_H_SP)(a0)
44 sd tp, (HYP_H_TP)(a0)
45 sd gp, (HYP_H_GP)(a0)
46 sd s0, (HYP_H_S + 0 * 8)(a0)
47 sd s1, (HYP_H_S + 1 * 8)(a0)
48 sd s2, (HYP_H_S + 2 * 8)(a0)
49 sd s3, (HYP_H_S + 3 * 8)(a0)
50 sd s4, (HYP_H_S + 4 * 8)(a0)
[all …]
/freebsd/lib/libc/riscv/gen/
H A Dsetjmp.S40 sd a0, 0(sp)
44 addi a2, a0, (_JB_SIGMASK * 8) /* oset */
46 li a0, 1 /* SIG_BLOCK */
49 ld a0, 0(sp)
55 sd t0, (0 * 8)(a0)
56 sd sp, (1 * 8)(a0)
57 addi a0, a0, (2 * 8)
60 sd s0, (0 * 8)(a0)
61 sd s1, (1 * 8)(a0)
62 sd s2, (2 * 8)(a0)
[all …]
H A D_setjmp.S41 sd t0, (0 * 8)(a0)
42 sd sp, (1 * 8)(a0)
43 addi a0, a0, (2 * 8)
46 sd s0, (0 * 8)(a0)
47 sd s1, (1 * 8)(a0)
48 sd s2, (2 * 8)(a0)
49 sd s3, (3 * 8)(a0)
50 sd s4, (4 * 8)(a0)
51 sd s5, (5 * 8)(a0)
52 sd s6, (6 * 8)(a0)
[all …]
/freebsd/sys/riscv/riscv/
H A Dsupport.S48 li a0, -1
57 bgeu a0, a4, fsu_fault_nopcb
61 lr.w a4, 0(a0) /* Load-exclusive the data */
63 sc.w a5, a3, 0(a0) /* Store the new data */
69 mv a0, a5 /* Success indicator */
78 bgeu a0, a4, fsu_fault_nopcb
82 lr.d a4, 0(a0) /* Load-exclusive the data */
84 sc.d a5, a3, 0(a0) /* Store the new data */
90 mv a0, a5 /* Success indicator */
99 bgeu a0, a1, fsu_fault_nopcb
[all …]
H A Dcopyinout.S49 li a0, EFAULT
56 * a0 - Source address
72 andi t0, a0, (XLEN_BYTES-1) /* Low bits of src */
78 1: lb a4, 0(a0) /* Load byte from src */
79 addi a0, a0, 1
83 andi t0, a0, (XLEN_BYTES-1)
88 2: ld a4, 0(a0) /* Load word from src */
89 addi a0, a0, XLEN_BYTES
99 4: lb a4, 0(a0) /* Load byte from src */
100 addi a0, a0, 1
[all …]
/freebsd/sys/contrib/openzfs/module/lua/setjmp/
H A Dsetjmp_rv64g.S43 sd sp, (0 * 8)(a0)
44 addi a0, a0, (1 * 8)
47 sd s0, (0 * 8)(a0)
48 sd s1, (1 * 8)(a0)
49 sd s2, (2 * 8)(a0)
50 sd s3, (3 * 8)(a0)
51 sd s4, (4 * 8)(a0)
52 sd s5, (5 * 8)(a0)
53 sd s6, (6 * 8)(a0)
54 sd s7, (7 * 8)(a0)
[all …]
H A Dsetjmp_loongarch64.S41 st.d $ra, $a0, 0*8
42 st.d $sp, $a0, 1*8
43 st.d $r21, $a0, 2*8
44 st.d $fp, $a0, 3*8
45 st.d $s0, $a0, 4*8
46 st.d $s1, $a0, 5*8
47 st.d $s2, $a0, 6*8
48 st.d $s3, $a0, 7*8
49 st.d $s4, $a0, 8*8
50 st.d $s5, $a0, 9*8
[all …]
H A Dsetjmp_mips.S52 * jmp_buf is in a0. We need to save s0-s8, sp, gp, and ra in it.
56 REG_S sp, 0(a0) /* save registers */
57 REG_S ra, 1*SZREG(a0)
58 REG_S gp, 2*SZREG(a0)
59 REG_S s0, 3*SZREG(a0)
60 REG_S s1, 4*SZREG(a0)
61 REG_S s2, 5*SZREG(a0)
62 REG_S s3, 6*SZREG(a0)
63 REG_S s4, 7*SZREG(a0)
64 REG_S s5, 8*SZREG(a0)
[all …]
/freebsd/lib/libc/riscv/string/
H A Dmemchr.S10 * a0 - const void *b
16 * a0 - const char *ptr
37 add a3, a0, a2
39 sltu t2, a0, a3
45 slli t2, a0, 3
46 and a0, a0, ~0b111
49 ld a2, (a0)
72 addi a0, a0, 8
77 beq a0, a4, .Lno_match
93 ld a2, (a0)
[all …]
H A Dstrrchr.S13 * a0 - const char *s
18 * a0 - const char *ptr_align
40 slli a2, a0, 3
46 andi a0, a0, ~0b111
51 ld a1, 0(a0) /* a1 -> data = *ptr_align */
63 addi a0, a0, 8 /* ptr_align = ptr_align + 8 */
70 addi a6, a0, -8 /* save_align = ptr_align - 8 */
87 and a0, a1, a2
89 beqz a0, .Lret
92 and a0, a1, a2
[all …]
H A Dstrchrnul.S13 * a0 - const char *str
18 * a0 - const char *ptr;
39 andi t2, a0, 0b111
42 andi a0, a0, ~0b111
47 ld a2, (a0)
73 addi a0, a0, 8
78 ld a2, (a0)
94 addi a0, a0, 8
98 addi a0, a0, -8
114 add a0, a0, a2
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/
H A Dblamka-round-avx512f.h17 #define G1_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
19 A0 = muladd(A0, B0); \
22 D0 = _mm512_xor_si512(D0, A0); \
38 #define G2_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
40 A0 = muladd(A0, B0); \
43 D0 = _mm512_xor_si512(D0, A0); \
59 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
71 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
83 #define BLAKE2_ROUND(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
85 G1_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1); \
[all …]
H A Dblamka-round-avx2.h12 #define G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
14 __m256i ml = _mm256_mul_epu32(A0, B0); \
16 A0 = _mm256_add_epi64(A0, _mm256_add_epi64(B0, ml)); \
17 D0 = _mm256_xor_si256(D0, A0); \
41 #define G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
43 __m256i ml = _mm256_mul_epu32(A0, B0); \
45 A0 = _mm256_add_epi64(A0, _mm256_add_epi64(B0, ml)); \
46 D0 = _mm256_xor_si256(D0, A0); \
68 #define DIAGONALIZE_1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
79 #define DIAGONALIZE_2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
[all …]
/freebsd/sys/dev/enic/
H A Dvnic_devcmd.h74 * (u64)a0=paddr to struct vnic_devcmd_fw_info
85 * (u64)a0=paddr to struct vnic_devcmd_fw_info
101 * in: (u16)a0=offset,(u8)a1=size
102 * out: a0=value
109 /* stats dump in mem: (u64)a0=paddr to stats area,
113 /* set Rx packet filter: (u32)a0=filters (see CMD_PFILTER_*) */
116 /* set Rx packet filter for all: (u32)a0=filters (see CMD_PFILTER_*) */
122 /* MAC address in (u48)a0 */
127 /* add addr from (u48)a0 */
131 /* del addr from (u48)a0 */
[all …]
H A Dvnic_dev.c373 u64 *a0, u64 *a1, int wait) in vnic_dev_cmd() argument
378 args[0] = *a0; in vnic_dev_cmd()
398 *a0 = args[0]; in vnic_dev_cmd()
432 u64 a0 = CMD_ADD_ADV_FILTER, a1 = 0; in vnic_dev_capable_adv_filters() local
436 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable_adv_filters()
499 u64 a0 = CMD_NIC_CFG, a1 = 0; in vnic_dev_capable_udp_rss_weak() local
505 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable_udp_rss_weak()
506 if (err == 0 && a0 != 0 && a1 != 0) { in vnic_dev_capable_udp_rss_weak()
514 u64 a0 = (u32)cmd, a1 = 0; in vnic_dev_capable() local
518 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable()
[all …]
/freebsd/sys/contrib/dev/iwlwifi/cfg/
H A Drf-gf.c14 #define IWL_SO_A_GF_A_FW_PRE "iwlwifi-so-a0-gf-a0"
15 #define IWL_TY_A_GF_A_FW_PRE "iwlwifi-ty-a0-gf-a0"
16 #define IWL_MA_A_GF_A_FW_PRE "iwlwifi-ma-a0-gf-a0"
17 #define IWL_MA_B_GF_A_FW_PRE "iwlwifi-ma-b0-gf-a0"
18 #define IWL_SO_A_GF4_A_FW_PRE "iwlwifi-so-a0-gf4-a0"
19 #define IWL_MA_A_GF4_A_FW_PRE "iwlwifi-ma-a0-gf4-a0"
20 #define IWL_MA_B_GF4_A_FW_PRE "iwlwifi-ma-b0-gf4-a0"
21 #define IWL_BZ_A_GF_A_FW_PRE "iwlwifi-bz-a0-gf-a0"
22 #define IWL_BZ_A_GF4_A_FW_PRE "iwlwifi-bz-a0-gf4-a0"
23 #define IWL_SC_A_GF_A_FW_PRE "iwlwifi-sc-a0-gf-a0"
[all …]
/freebsd/sys/cddl/dev/dtrace/riscv/
H A Ddtrace_asm.S58 csrrci a0, sstatus, (SSTATUS_SIE)
59 andi a0, a0, (SSTATUS_SIE)
67 csrs sstatus, a0
76 lb a0, 0(a0)
87 lh a0, 0(a0)
98 lw a0, 0(a0)
109 ld a0, 0(a0)
122 lb a4, 0(a0) /* Load from uaddr */
123 addi a0, a0, 1
143 lb a4, 0(a0) /* Load from uaddr */
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/sanitizer_common/
H A Dsanitizer_syscall_linux_loongarch64.inc20 // parameters, if present, are placed in a0-a6
22 // the return value is placed in a0
32 register u64 a0 asm("$a0");
34 : "=r"(a0)
37 return a0;
43 register u64 a0 asm("$a0") = arg1;
45 : "+r"(a0)
48 return a0;
54 register u64 a0 asm("$a0") = arg1;
57 : "+r"(a0)
[all …]
H A Dsanitizer_syscall_linux_riscv64.inc21 // a0 and a1 (http://man7.org/linux/man-pages/man2/syscall.2.html) arguments
22 // are passed in: a0-a7 (see below)
35 register u64 a0 asm("a0");
37 : "=r"(a0)
40 return a0;
46 register u64 a0 asm("a0") = arg1;
48 : "+r"(a0)
51 return a0;
57 register u64 a0 asm("a0") = arg1;
60 : "+r"(a0)
[all …]
H A Dsanitizer_common_interceptors_vfork_loongarch64.inc.S22 // store $ra by $a0
23 st.d $ra, $a0, 0
27 la.local $a0, _ZN14__interception10real_vforkE
28 ld.d $a0, $a0, 0
29 jirl $ra, $a0, 0
33 // store $a0 by adjusted stack
34 st.d $a0, $sp, 8
35 // jump to exit label if $a0 is 0
36 beqz $a0, .L_exit
38 // $a0 != 0 => parent process. Clear stack shadow.
[all …]
/freebsd/sys/dev/psci/
H A Dsmccc.h60 register_t a0; member
95 #define arm_smccc_invoke_1(func, a0, res) \ argument
96 func(a0, 0, 0, 0, 0, 0, 0, 0, res)
97 #define arm_smccc_invoke_2(func, a0, a1, res) \ argument
98 func(a0, a1, 0, 0, 0, 0, 0, 0, res)
99 #define arm_smccc_invoke_3(func, a0, a1, a2, res) \ argument
100 func(a0, a1, a2, 0, 0, 0, 0, 0, res)
101 #define arm_smccc_invoke_4(func, a0, a1, a2, a3, res) \ argument
102 func(a0, a1, a2, a3, 0, 0, 0, 0, res)
103 #define arm_smccc_invoke_5(func, a0, a1, a2, a3, a4, res) \ argument
[all …]
/freebsd/sys/sys/
H A Dktr.h143 #define KTR_EVENT1(m, egroup, ident, etype, edat, a0, v0) \ argument
144 CTR3(m, KTR_EFMT(egroup, ident, etype) a0, ident, edat, (v0))
145 #define KTR_EVENT2(m, egroup, ident, etype, edat, a0, v0, a1, v1) \ argument
146 CTR4(m, KTR_EFMT(egroup, ident, etype) a0 ", " a1, \
148 #define KTR_EVENT3(m, egroup, ident, etype, edat, a0, v0, a1, v1, a2, v2)\ argument
149 CTR5(m,KTR_EFMT(egroup, ident, etype) a0 ", " a1 ", " a2, \
152 a0, v0, a1, v1, a2, v2, a3, v3) \ argument
153 CTR6(m,KTR_EFMT(egroup, ident, etype) a0 ", " a1 ", " a2 ", " a3,\
161 #define KTR_STATE1(m, egroup, ident, state, a0, v0) \ argument
162 KTR_EVENT1(m, egroup, ident, "state:\"%s\"", state, a0, (v0))
[all …]
/freebsd/crypto/openssl/crypto/ec/asm/
H A Dx25519-ppc64.pl49 my ($bi,$a0,$a1,$a2,$a3,$t0,$t1, $t2,$t3,
75 ld $a0,0($ap)
81 mulld $acc0,$a0,$bi # a[0]*b[0]
82 mulhdu $t0,$a0,$bi
97 mulld $t0,$a0,$bi
105 mulhdu $t0,$a0,$bi
189 ld $a0,0($ap)
196 # | | | | | |a1*a0| |
197 # | | | | |a2*a0| | |
198 # | |a3*a2|a3*a0| | | |
[all …]
/freebsd/contrib/jemalloc/include/jemalloc/internal/
H A Dprof_inlines_a.h
/freebsd/crypto/openssl/crypto/chacha/asm/
H A Dchacha-c64xplus.pl61 MV $LEN,A0 ; reassign
62 [!A0] BNOP RA ; no data
63 || [A0] STW FP,*SP--(40+64) ; save frame pointer and alloca(40+64)
64 || [A0] MV SP,FP
65 [A0] STDW B13:B12,*SP[4+8] ; ABI says so
66 || [A0] MV $KEYB,$KEYA
67 || [A0] MV $COUNTERA,$COUNTERB
68 [A0] STDW B11:B10,*SP[3+8]
69 || [A0] STDW A13:A12,*FP[-3]
70 [A0] STDW A11:A10,*FP[-4]
[all …]

12345678910>>...43