| /src/common/lib/libc/arch/ia64/string/ |
| memcpy.S | 38 mov r8 = in0
39 mov in0 = in1
|
| memmove.S | 39 mov r8 = in0
40 mov in0 = in1
|
| bcopy.S | 46 sub r14=in1,in0 ;; // check for overlap
50 extr.u r14=in0,0,3 // src & 7
55 1: ld1 r14=[in0],1 ;; // copy bytewise
65 3: ld1 r14=[in0],1 ;; // copy bytewise
67 extr.u r15=in0,0,3 // src & 7
80 ld8 r15=[in0],8 ;; // copy word
90 5: add in0=in0,in2
92 add in0=-1,in0
[all...] |
| bzero.S | 49 2: st1 [in0]=r0,1 // zero one byte
58 3: tbit.nz p6,p0=in0,0 ;;
59 (p6) st1 [in0]=r0,1
62 tbit.nz p6,p0=in0,1 ;;
63 (p6) st2 [in0]=r0,2
66 tbit.nz p6,p0=in0,2 ;;
67 (p6) st4 [in0]=r0,4
79 4: st8 [in0]=r0,8
|
| ffs.S | 45 sxt4 r14=in0 ;;
|
| /src/sys/external/bsd/gnu-efi/dist/lib/ia64/ |
| setjmp.S | 25 add r10 = 0x10*20, in0
27 stf.spill.nta [in0] = f2, 0x10
31 stf.spill.nta [in0] = f3, 0x10
35 stf.spill.nta [in0] = f4, 0x10
39 stf.spill.nta [in0] = f5, 0x10
43 stf.spill.nta [in0] = f16, 0x10
47 stf.spill.nta [in0] = f17, 0x10
51 stf.spill.nta [in0] = f18, 0x10
55 stf.spill.nta [in0] = f19, 0x10
58 stf.spill.nta [in0] = f20, 0x10
[all...] |
| palproc.S | 89 mov b5 = in0;; // get the PalProcEntrypt from input
120 // in0: PAL_PROC entrypoint
148 mov b5 = in0;; // get the PalProcEntrypt from input
|
| /src/sys/lib/libkern/arch/ia64/ |
| byte_swap_8.S | 43 mux1 r8=in0,@rev
|
| byte_swap_2.S | 42 mux1 r16=in0,@rev
|
| byte_swap_4.S | 42 mux1 r16=in0,@rev
|
| /src/sys/arch/ia64/stand/ia64/ski/ |
| ssc.c | 47 ssc(u_int64_t in0, u_int64_t in1, u_int64_t in2, u_int64_t in3, int which)
56 : "r"(which), "r"(in0), "r"(in1), "r"(in2), "r"(in3));
|
| libski.h | 93 u_int64_t ssc(u_int64_t in0, u_int64_t in1, u_int64_t in2, u_int64_t in3,
|
| /src/lib/libc/arch/ia64/gen/ |
| sigsetjmp.S | 48 add r14=J_SIGMASK,in0 // place to save mask
57 add r14=J_SIGMASK,in0 // address of mask value
|
| setjmp.S | 54 add out2=J_SIGSET,in0 // oset = &jb[J_SIGSET]
71 add out1=J_SIGSET,in0 // set = &jb[J_SIGSET]
|
| /src/sys/arch/ia64/ia64/ |
| ssc.c | 51 ssc(uint64_t in0, uint64_t in1, uint64_t in2, uint64_t in3, int which)
58 : "r"(which), "r"(in0), "r"(in1), "r"(in2), "r"(in3));
|
| support.S | 142 * in0 Address of EFI procedure descriptor
163 ld8 r14=[in0],8 // function address
170 ld8 gp=[in0] // function gp value
209 cmp.geu p6,p0=in0,r14
228 cmpxchg8.rel ret0=[in0],in2,ar.ccv
265 cmp.geu p6,p0=in0,r14 ;\
284 load_insn r14=[in0] /* r14 = *uaddr */ ;;\
327 cmp.geu p6,p0=in0,r14 ;\
342 store_insn [in0]=in1 /* *uaddr = val */ ;\
387 1: ld1 r15=[in0],1 // read one byt
[all...] |
| pal.S | 60 mov r28=in0 // procedure number
106 mov r28=in0 // procedure number
156 mov r28=in0 // procedure number
157 mov out0=in0
198 mov r28=in0 // procedure number
199 mov out0=in0
|
| /src/sys/crypto/chacha/arch/arm/ |
| chacha_neon.c | 159 uint32x4_t in0, in1, in2, in3;
162 r0 = in0 = vreinterpretq_u32_u8(vld1q_u8(c));
169 vst1q_u8(out + 0, vreinterpretq_u8_u32(vaddq_u32(r0, in0)));
210 uint32x4_t in0, in1, in2, in3;
213 in0 = vreinterpretq_u32_u8(vld1q_u8(chacha_const32));
224 r0 = in0;
229 r0 = vaddq_u32(r0, in0);
271 uint32x4_t in0, in1, in2, in3;
274 in0 = vreinterpretq_u32_u8(vld1q_u8(chacha_const32));
285 r0 = in0;
156 uint32x4_t in0, in1, in2, in3; local in function:chacha_core_neon
206 uint32x4_t in0, in1, in2, in3; local in function:chacha_stream_neon
266 uint32x4_t in0, in1, in2, in3; local in function:chacha_stream_xor_neon
[all...] |
| /src/sys/arch/ia64/stand/ia64/efi/ |
| start.S | 94 mov out0=in0 // image_handle
120 // in0: image base
172 (p6) add r18=r17,in0
181 (p6) add r21=r17,in0
187 (p6) add r29=r17,in0
213 add r15=r29,in0 // relocate r_offset
240 add r24=r29,in0 // relocate symbol value
261 add r29=in0,r17
268 add r29=in0,r17 // BD + A
|
| /src/sys/external/bsd/gnu-efi/dist/gnuefi/ |
| crt0-efi-ia64.S | 59 mov out0=in0 // image handle
|
| reloc_ia64.S | 77 #define ldbase in0 /* load address (address of .text) */
|
| /src/sys/crypto/chacha/arch/x86/ |
| chacha_sse2.c | 92 __m128i in0, in1, in2, in3;
95 r0 = in0 = _mm_loadu_si128((const __m128i *)c);
102 _mm_storeu_si128((__m128i *)out + 0, _mm_add_epi32(r0, in0));
314 __m128i in0, in1, in2, in3;
317 in0 = _mm_loadu_si128((const __m128i *)chacha_const32);
324 r0 = in0;
329 r0 = _mm_add_epi32(r0, in0);
473 __m128i in0, in1, in2, in3;
476 in0 = _mm_loadu_si128((const __m128i *)chacha_const32);
483 r0 = in0;
90 __m128i in0, in1, in2, in3; local in function:chacha_core_sse2
307 __m128i in0, in1, in2, in3; local in function:chacha_stream_sse2
463 __m128i in0, in1, in2, in3; local in function:chacha_stream_xor_sse2
[all...] |
| /src/sys/external/gpl2/dts/dist/arch/riscv/boot/dts/canaan/ |
| k210.dtsi | 91 in0: oscillator { label
435 clocks = <&in0>;
|
| /src/sys/external/bsd/drm2/dist/drm/i915/display/ |
| intel_sdvo_regs.h | 193 u16 in0, in1; member in struct:intel_sdvo_in_out_map
|
| /src/sys/external/isc/libsodium/dist/src/libsodium/crypto_aead/aes256gcm/aesni/ |
| aead_aes256gcm_aesni.c | 461 MULREDUCE4(rev, hv, h2v, h3v, h4v, in3, in2, in1, in0, accv_); \
|
