Home
last modified time | relevance | path

Searched refs:r6 (Results 1 – 25 of 29) sorted by relevance

12

/f-stack/freebsd/crypto/openssl/arm/
H A Dsha1-armv4-large.S39 mov r6,r6,ror#30
545 add r6,r6,r9
555 add r6,r6,r11
605 add r6,r6,r9
663 add r6,r6,r9
720 add r6,r6,r9
771 add r6,r6,r9
819 add r6,r6,r9
862 add r6,r6,r9
907 add r6,r6,r9
[all …]
H A Decp_nistz256-armv4.S2435 adcs r6,r6,r6
2572 adcs r6,r6,r6
3062 eor r6,r6,r6
3369 and r6,r6,r3
3388 and r6,r6,r3
3407 and r6,r6,r3
3588 adcs r6,r6,r6
3821 orr r6,r6,r7
3823 orr r6,r6,r8
3844 orr r6,r6,r7
[all …]
H A Daes-armv4.S286 eor r2,r2,r6
313 eor r6,r6,r9,ror#8
326 eor r6,r6,r9,ror#16
350 eor r3,r3,r6
375 eor r6,r9,r6,lsl#8
388 eor r6,r9,r6,lsl#8
409 eor r3,r3,r6
1084 eor r6,r9,r6,ror#8
1097 eor r6,r9,r6,ror#8
1157 eor r6,r6,r9,lsl#8
[all …]
H A Dpoly1305-armv4.S101 orr r6,r6,r7,lsl#8
107 and r6,r6,r3
191 adcs r6,r6,r3
218 adcs r6,r6,r2
271 adcs r6,r6,#0
331 adc r6,r6,r11
338 rev r6,r6
352 mov r6,r6,lsr#8
361 mov r6,r6,lsr#8
370 mov r6,r6,lsr#8
[all …]
H A Dkeccak1600-armv4.S69 eor r6,r6,r12
85 eor r6,r6,r10
99 eor r6,r6,r12
125 eor r6,r6,r12
140 eor r6,r6,r10
155 eor r6,r6,r12
173 eor r6,r6,r10
246 eor r6,r6,r5
401 eor r6,r6,r4
1907 orr r6,r6,r6,lsl#8
[all …]
H A Dghash-armv4.S75 eor r6,r10,r6,lsr#4
76 eor r6,r6,r7,lsl#28
94 eor r6,r10,r6,lsr#4
99 eor r6,r6,r7,lsl#28
116 eor r6,r10,r6,lsr#4
117 eor r6,r6,r7,lsl#28
169 rev r6,r6
235 eor r6,r10,r6,lsr#4
236 eor r6,r6,r7,lsl#28
253 eor r6,r10,r6,lsr#4
[all …]
H A Darmv4-gf2m.S20 eor r7,r5,r6 @ a1^a2
26 eor r4,r6,r8 @ a2^a4
44 eor r5,r5,r6,lsl#6
45 eor r4,r4,r6,lsr#26
54 eor r5,r5,r6,lsl#12
55 eor r4,r4,r6,lsr#20
64 eor r5,r5,r6,lsl#18
65 eor r4,r4,r6,lsr#14
76 eor r4,r4,r6,lsr#8
93 eor r4,r4,r6,lsr#2
[all …]
H A Dchacha-armv4.S128 mov r6,r6,ror#20
140 mov r6,r6,ror#25
154 mov r6,r6,ror#20
281 add r6,r6,r10
291 rev r6,r6
368 add r6,r6,r10
378 rev r6,r6
1192 rev r6,r6
1256 rev r6,r6
1421 rev r6,r6
[all …]
H A Darmv4-mont.S65 ldr r6,[r3],#4 @ np[0],np++
106 ldr r6,[r3,#-4] @ np[0]
161 ldr r6,[r3],#4
640 vld1.64 {q6},[r6,:128]
645 addne r6,r6,#16 @ don't advance in last iteration
684 vld1.64 {q8},[r6,:128]
689 addne r6,r6,#16 @ don't advance in last iteration
728 vld1.64 {q10},[r6,:128]
733 addne r6,r6,#16 @ don't advance in last iteration
772 vld1.64 {q12},[r6,:128]
[all …]
H A Darmv4cpuid.S27 stmdb sp!,{r4,r5,r6,lr}
32 add r6,r3,r2 @ &spinlock
36 swp r0,r0,[r6]
43 str r0,[r6] @ release spinlock
44 ldmia sp!,{r4,r5,r6,lr}
H A Dbsaes-armv7.S1373 add r8, r6, r8
1435 sub r6, r8, r6
1531 mov r6, r2
1560 subs r6, r6, #1
1599 mov r3, r6
2001 sub r6, r8, #0x10
2012 vld1.8 {q0}, [r6]
2024 vst1.8 {q0}, [r6]
2079 mov r3, r6
2514 mov r6, r8
[all …]
/f-stack/freebsd/arm/arm/
H A Dswtch-v6.S242 ldr r6, [r6, #(P_VMSPACE)] /* newtd->proc->vmspace */
263 1: ldrex r0, [r6]
265 strex r1, r0, [r6]
269 ldr r0, [r6]
271 str r0, [r6]
363 ldr r6, [r6, #P_VMSPACE] /* newtd->proc->vmspace */
401 1: ldrex r0, [r6]
403 strex r1, r0, [r6]
407 ldr r0, [r6]
409 str r0, [r6]
[all …]
H A Dbcopyinout_xscale.S310 mov r6, r6, lsr #8
311 orr r6, r6, r7, lsl #24
349 mov r6, r6, lsr #16
350 orr r6, r6, r7, lsl #16
388 mov r6, r6, lsr #24
389 orr r6, r6, r7, lsl #8
696 mov r6, r6, lsr #8
697 orr r6, r6, r7, lsl #24
735 mov r6, r6, lsr #16
774 mov r6, r6, lsr #24
[all …]
H A Din_cksum_arm.S133 movle r6, #0x00
162 mov r6, #0x00
165 adds r2, r2, r6
167 ldrd r6, [r0], #0x08
171 adcs r2, r2, r6
173 ldrd r6, [r0], #0x08
177 adcs r2, r2, r6
180 ldrd r6, [r0], #0x08
184 adcs r2, r2, r6
186 ldrd r6, [r0], #0x08
[all …]
H A Dcopystr.S55 #define SAVE_REGS stmfd sp!, {r4-r6}
56 #define RESTORE_REGS ldmfd sp!, {r4-r6}
70 mov r6, #0x00000000
91 add r6, r6, #0x00000001
94 teqne r6, r2
105 strne r6, [r3]
H A Dfusu.S54 stmfd sp!, {r4, r5, r6}
61 GET_PCB(r6)
62 ldr r6, [r6]
65 teq r6, #0x00000000
66 ldmfdeq sp!, {r4, r5, r6}
71 str r4, [r6, #PCB_ONFAULT]
79 str r0, [r6, #PCB_ONFAULT]
82 ldmfd sp!, {r4, r5, r6}
93 str r0, [r6, #PCB_ONFAULT]
95 ldmfd sp!, {r4, r5, r6}
H A Dblockio.S434 orr r4, r5, r6, lsl #16
438 orr r6, r9, ip, lsl #16
440 stmia r1!, {r3-r6}
450 ldmia r0, {r3-r6}
455 orr r4, r5, r6, lsl #16
529 eor r6, r5, r5, lsr #16 /* r6 = (A)(A^B) */
530 eor r5, r5, r6, lsl #16 /* r5 = (A^A^B)(B) = (B)(B) */
531 eor r6, r6, r5, lsr #16 /* r6 = (A)(B^A^B) = (A)(A) */
553 eor r6, r3, r3, lsr #16 /* r6 = (A)(A^B) */
554 eor r5, r3, r6, lsl #16 /* r5 = (A^A^B)(B) = (B)(B) */
[all …]
H A Dsupport.S900 ldr r6, [r1], #0x04
978 ldr r6, [r1], #0x04
984 mov r6, r6, lsr #8
985 orr r6, r6, r7, lsl #24
990 str r6, [r3], #0x04
1017 ldr r6, [r1], #0x04
1023 mov r6, r6, lsr #16
1024 orr r6, r6, r7, lsl #16
1029 str r6, [r3], #0x04
1062 mov r6, r6, lsr #24
[all …]
H A Dlocore-v6.S338 mov r6, r2
356 eor r8, r8, r6 /* Set bits */
/f-stack/freebsd/netinet6/
H A Din6_fib_algo.c297 struct radix6_data *r6; in radix6_init() local
299 r6 = malloc(sizeof(struct radix6_data), M_RTABLE, M_NOWAIT | M_ZERO); in radix6_init()
300 if (r6 == NULL) in radix6_init()
302 r6->fd = fd; in radix6_init()
303 r6->rh = fib_get_rh(fd); in radix6_init()
305 *_data = r6; in radix6_init()
327 struct radix6_data *r6 = (struct radix6_data *)_data; in radix6_end_dump() local
330 dp->arg = r6->rh; in radix6_end_dump()
/f-stack/freebsd/contrib/openzfs/module/lua/setjmp/
H A Dsetjmp_s390x.S27 stmg %r6, %r15, 0(%r2)
46 lmg %r6, %r15, 0(%r2)
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_stream/salsa20/xmm6int/
H A Du8.h102 __m256i r0, r1, r2, r3, r4, r5, r6, r7, r8, r9, r10, r11, r12, r13, variable
203 r6 = y6;
206 r6 = _mm256_srli_epi32(r6, 19);
207 z6 = _mm256_xor_si256(z6, r6);
243 r6 = y6;
246 r6 = _mm256_srli_epi32(r6, 25);
247 z6 = _mm256_xor_si256(z6, r6);
H A Du4.h102 __m128i r0, r1, r2, r3, r4, r5, r6, r7, r8, r9, r10, r11, r12, r13, variable
203 r6 = y6;
206 r6 = _mm_srli_epi32(r6, 19);
207 z6 = _mm_xor_si128(z6, r6);
243 r6 = y6;
246 r6 = _mm_srli_epi32(r6, 25);
247 z6 = _mm_xor_si128(z6, r6);
/f-stack/dpdk/drivers/event/dlb/pf/base/
H A Ddlb_resource.c1839 union dlb_chp_qed_fl_pop_ptr r6 = { {0} }; in dlb_configure_ldb_credit_pool() local
1863 r6.field.pop_ptr = r3.field.base; in dlb_configure_ldb_credit_pool()
1864 r6.field.generation = 0; in dlb_configure_ldb_credit_pool()
2001 union dlb_chp_dqed_fl_pop_ptr r6 = { {0} }; in dlb_configure_dir_credit_pool() local
2026 r6.field.pop_ptr = r3.field.base; in dlb_configure_dir_credit_pool()
2027 r6.field.generation = 0; in dlb_configure_dir_credit_pool()
4276 r6.field.pop_ptr = r4.field.base; in dlb_configure_ldb_queue()
4277 r6.field.generation = 0; in dlb_configure_ldb_queue()
5147 union dlb_lsp_cq_ldb_infl_lim r6 = { {0} }; in dlb_ldb_port_configure_cq() local
5723 r6.val); in dlb_dir_port_configure_pp()
[all …]
/f-stack/dpdk/lib/librte_bpf/
H A Dbpf_jit_arm64.c795 uint8_t r6, r7, r8, r9, fp; in emit_prologue_has_call() local
797 r6 = ebpf_to_a64_reg(ctx, EBPF_REG_6); in emit_prologue_has_call()
826 emit_stack_push(ctx, r6, r7); in emit_prologue_has_call()
842 uint8_t r6, r7, r8, r9, fp, r0; in emit_epilogue_has_call() local
844 r6 = ebpf_to_a64_reg(ctx, EBPF_REG_6); in emit_epilogue_has_call()
855 emit_stack_pop(ctx, r6, r7); in emit_epilogue_has_call()

12