Home
last modified time | relevance | path

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

12345678910>>...40

/freebsd-src/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-src/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-src/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-src/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-src/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 …]
H A Dblamka-round-ssse3.h31 #define G1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
33 A0 = fBlaMka(A0, B0); \
36 D0 = _mm_xor_si128(D0, A0); \
52 #define G2(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
54 A0 = fBlaMka(A0, B0); \
57 D0 = _mm_xor_si128(D0, A0); \
73 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
90 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
107 #define BLAKE2_ROUND(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
109 G1(A0, B0, C0, D0, A1, B1, C1, D1); \
[all …]
/freebsd-src/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
[all...]
/freebsd-src/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.c378 u64 *a0, u64 *a1, int wait)
383 args[0] = *a0; in vnic_dev_capable_filter_mode()
403 *a0 = args[0]; in vnic_dev_capable_filter_mode()
437 u64 a0 = CMD_ADD_ADV_FILTER, a1 = 0; in vnic_dev_capable_udp_rss_weak()
441 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable()
504 u64 a0 = CMD_NIC_CFG, a1 = 0; in vnic_dev_stats_dump()
510 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_stats_dump()
511 if (err == 0 && a0 != 0 && a1 != 0) { in vnic_dev_stats_dump()
519 u64 a0 = (u32)cmd, a1 = 0; in vnic_dev_counter_dma_cfg()
523 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, in vnic_dev_counter_dma_cfg()
302 vnic_dev_cmd(struct vnic_dev * vdev,enum vnic_devcmd_cmd cmd,u64 * a0,u64 * a1,int wait) vnic_dev_cmd() argument
361 u64 a0 = CMD_ADD_ADV_FILTER, a1 = 0; vnic_dev_capable_adv_filters() local
428 u64 a0 = CMD_NIC_CFG, a1 = 0; vnic_dev_capable_udp_rss_weak() local
443 u64 a0 = (u32)cmd, a1 = 0; vnic_dev_capable() local
455 u64 a0, a1; vnic_dev_spec() local
487 u64 a0 = 0, a1 = 0; vnic_dev_stats_clear() local
495 u64 a0, a1; vnic_dev_stats_dump() local
553 u64 a0 = 0, a1 = 0; vnic_dev_close() local
561 u64 a0 = 0, a1 = 0; vnic_dev_enable_wait() local
572 u64 a0 = 0, a1 = 0; vnic_dev_disable() local
580 u64 a0 = (u32)arg, a1 = 0; vnic_dev_open() local
588 u64 a0 = 0, a1 = 0; vnic_dev_open_done() local
605 u64 a0 = 0, a1 = 0; vnic_dev_get_mac_addr() local
625 u64 a0, a1 = 0; vnic_dev_packet_filter() local
644 u64 a0 = 0, a1 = 0; vnic_dev_add_addr() local
663 u64 a0 = 0, a1 = 0; vnic_dev_del_addr() local
683 u64 a0 = ig_vlan_rewrite_mode, a1 = 0; vnic_dev_set_ig_vlan_rewrite_mode() local
706 u64 a0, a1; vnic_dev_notify_setcmd() local
759 u64 a0, a1; vnic_dev_notify_unsetcmd() local
815 u64 a0 = (u32)arg, a1 = 0; vnic_dev_init() local
963 u64 a0 = overlay; vnic_dev_overlay_offload_ctrl() local
974 u64 a0 = overlay; vnic_dev_overlay_offload_cfg() local
982 u64 a0 = VIC_FEATURE_VXLAN; vnic_dev_capable_vxlan() local
996 u64 a0 = 0; vnic_dev_counter_alloc() local
1008 u64 a0 = idx; vnic_dev_counter_free() local
1019 u64 a0 = idx; vnic_dev_counter_query() local
[all...]
/freebsd-src/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-src/contrib/llvm-project/compiler-rt/lib/sanitizer_common/
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_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_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-src/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-src/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-src/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-src/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-src/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-src/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 …]
/freebsd-src/crypto/openssl/crypto/bn/asm/
H A Dbn-c64xplus.asm148 ADDU A1,A9:A8,A1:A0
150 || STW A0,*A3++ ; write result
172 SUBU B7,A7,A1:A0
173 [A2] SUB A1:A0,1,A1:A0
175 || STW A0,*A3++ ; write result
185 LMBD 1,A6,A0 ; leading zero bits in dv
188 CMPLTU A1,A0,A2
189 || ADD A0,B0,B0
195 [!A2] SHL A6,A0,A6 ; normalize dv
231 || MVK 8,A0 ; M, outer loop counter
[all …]

12345678910>>...40