Home
last modified time | relevance | path

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

12345678910>>...40

/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/dev/iwlwififw/
H A DWHENCE156 File: iwlwifi-cc-a0-46.ucode
159 File: iwlwifi-cc-a0-48.ucode
174 File: iwlwifi-QuZ-a0-hr-b0-48.ucode
177 File: iwlwifi-QuZ-a0-jf-b0-48.ucode
180 File: iwlwifi-cc-a0-50.ucode
195 File: iwlwifi-QuZ-a0-hr-b0-50.ucode
198 File: iwlwifi-QuZ-a0-jf-b0-50.ucode
201 File: iwlwifi-cc-a0-53.ucode
216 File: iwlwifi-QuZ-a0-hr-b0-53.ucode
219 File: iwlwifi-QuZ-a0-jf-b0-53.ucode
[all …]
/freebsd/sys/contrib/openzfs/module/lua/setjmp/
H A Dsetjmp_rv64g.S42 sd sp, (0 * 8)(a0)
43 addi a0, a0, (1 * 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)
53 sd s7, (7 * 8)(a0)
[all …]
H A Dsetjmp_loongarch64.S40 st.d $ra, $a0, 0*8
41 st.d $sp, $a0, 1*8
42 st.d $r21, $a0, 2*8
43 st.d $fp, $a0, 3*8
44 st.d $s0, $a0, 4*8
45 st.d $s1, $a0, 5*8
46 st.d $s2, $a0, 6*8
47 st.d $s3, $a0, 7*8
48 st.d $s4, $a0, 8*8
49 st.d $s5, $a0, 9*8
[all …]
H A Dsetjmp_mips.S51 * jmp_buf is in a0. We need to save s0-s8, sp, gp, and ra in it.
55 REG_S sp, 0(a0) /* save registers */
56 REG_S ra, 1*SZREG(a0)
57 REG_S gp, 2*SZREG(a0)
58 REG_S s0, 3*SZREG(a0)
59 REG_S s1, 4*SZREG(a0)
60 REG_S s2, 5*SZREG(a0)
61 REG_S s3, 6*SZREG(a0)
62 REG_S s4, 7*SZREG(a0)
63 REG_S s5, 8*SZREG(a0)
[all …]
/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/modules/iwlwififw/
H A DMakefile15 iwlwifi-QuZ-a0-hr-b0-fw \
16 iwlwifi-QuZ-a0-jf-b0-fw \
17 iwlwifi-cc-a0-fw \
20 iwlwifi-so-a0-gf-a0-fw \
21 iwlwifi-so-a0-gf4-a0-fw \
22 iwlwifi-so-a0-hr-b0-fw \
23 iwlwifi-so-a0-jf-b0-fw \
24 iwlwifi-ty-a0-gf-a0-fw \
25 iwlwifi-so-a0-gf-a0-pnvm \
26 iwlwifi-so-a0-gf4-a0-pnvm \
[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.c302 u64 *a0, u64 *a1, int wait) in vnic_dev_cmd() argument
307 args[0] = *a0; in vnic_dev_cmd()
327 *a0 = args[0]; in vnic_dev_cmd()
361 u64 a0 = CMD_ADD_ADV_FILTER, a1 = 0; in vnic_dev_capable_adv_filters() local
365 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable_adv_filters()
428 u64 a0 = CMD_NIC_CFG, a1 = 0; in vnic_dev_capable_udp_rss_weak() local
434 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable_udp_rss_weak()
435 if (err == 0 && a0 != 0 && a1 != 0) { in vnic_dev_capable_udp_rss_weak()
443 u64 a0 = (u32)cmd, a1 = 0; in vnic_dev_capable() local
447 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable()
[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/share/man/man4/
H A Diwlwififw.4975 .It 0x8086 Ta 0x51f0 Ta any Ta 0x1691 Ta iwlwifi-so-a0-gf4-a0
978 .It 0x8086 Ta 0x51f0 Ta any Ta 0x1692 Ta iwlwifi-so-a0-gf4-a0
981 .It 0x8086 Ta 0x51f1 Ta any Ta 0x1692 Ta iwlwifi-so-a0-gf4-a0
984 .It 0x8086 Ta 0x54f0 Ta any Ta 0x1691 Ta iwlwifi-so-a0-gf4-a0
987 .It 0x8086 Ta 0x54f0 Ta any Ta 0x1692 Ta iwlwifi-so-a0-gf4-a0
[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/contrib/jemalloc/include/jemalloc/internal/
H A Dprof_inlines_a.h12 uint64_t a0, a1; in prof_accum_add() local
21 a0 = atomic_load_u64(&prof_accum->accumbytes, ATOMIC_RELAXED); in prof_accum_add()
23 a1 = a0 + accumbytes; in prof_accum_add()
24 assert(a1 >= a0); in prof_accum_add()
29 } while (!atomic_compare_exchange_weak_u64(&prof_accum->accumbytes, &a0, in prof_accum_add()
33 a0 = prof_accum->accumbytes; in prof_accum_add()
34 a1 = a0 + accumbytes; in prof_accum_add()
56 uint64_t a0, a1; in prof_accum_cancel() local
58 a0 = atomic_load_u64(&prof_accum->accumbytes, ATOMIC_RELAXED); in prof_accum_cancel()
60 a1 = (a0 >= SC_LARGE_MINCLASS - usize) in prof_accum_cancel()
[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/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 …]
/freebsd/lib/libc/softfloat/bits64/
H A Dsoftfloat-macros89 Shifts the 128-bit value formed by concatenating `a0' and `a1' right by 64
97 (This routine makes more sense if `a0' and `a1' are considered to form a
98 fixed-point value with binary point between `a0' and `a1'. This fixed-point
107 bits64 a0, bits64 a1, int16 count, bits64 *z0Ptr, bits64 *z1Ptr )
114 z0 = a0;
117 z1 = ( a0<<negCount ) | ( a1 != 0 );
118 z0 = a0>>count;
122 z1 = a0 | ( a1 != 0 );
125 z1 = ( ( a0 | a1 ) != 0 );
136 Shifts the 128-bit value formed by concatenating `a0' and `a1' right by the
[all …]

12345678910>>...40