| /freebsd/sys/netinet6/ |
| H A D | frag6.c | 291 frag6_rmqueue(struct ip6q *q6, uint32_t bucket) in frag6_rmqueue() argument
295 TAILQ_REMOVE(IP6QB_HEAD(bucket), q6, ip6q_tq); in frag6_rmqueue()
298 mac_ip6q_destroy(q6); in frag6_rmqueue()
300 free(q6, M_FRAG6); in frag6_rmqueue()
308 frag6_freef(struct ip6q *q6, uint32_t bucket) in frag6_freef() argument
316 while ((af6 = TAILQ_FIRST(&q6->ip6q_frags)) != NULL) { in frag6_freef()
318 TAILQ_REMOVE(&q6->ip6q_frags, af6, ip6af_tq); in frag6_freef()
329 ip6->ip6_src = q6->ip6q_src; in frag6_freef()
330 ip6->ip6_dst = q6->ip6q_dst; in frag6_freef()
340 atomic_subtract_int(&frag6_nfrags, q6->ip6q_nfrag); in frag6_freef()
[all …]
|
| /freebsd/sys/security/mac/ |
| H A D | mac_inet6.c | 84 mac_ip6q_init(struct ip6q *q6, int flag) in mac_ip6q_init() argument
88 q6->ip6q_label = mac_ip6q_label_alloc(flag); in mac_ip6q_init()
89 if (q6->ip6q_label == NULL) in mac_ip6q_init()
92 q6->ip6q_label = NULL; in mac_ip6q_init()
105 mac_ip6q_destroy(struct ip6q *q6) in mac_ip6q_destroy() argument
108 if (q6->ip6q_label != NULL) { in mac_ip6q_destroy()
109 mac_ip6q_label_free(q6->ip6q_label); in mac_ip6q_destroy()
110 q6->ip6q_label = NULL; in mac_ip6q_destroy()
115 mac_ip6q_reassemble(struct ip6q *q6, struct mbuf *m) in mac_ip6q_reassemble() argument
124 MAC_POLICY_PERFORM_NOSLEEP(ip6q_reassemble, q6, q6->ip6q_label, m, in mac_ip6q_reassemble()
[all …]
|
| H A D | mac_framework.h | 216 void mac_ip6q_create(struct mbuf *m, struct ip6q *q6);
217 void mac_ip6q_destroy(struct ip6q *q6);
218 int mac_ip6q_init(struct ip6q *q6, int);
219 int mac_ip6q_match(struct mbuf *m, struct ip6q *q6);
220 void mac_ip6q_reassemble(struct ip6q *q6, struct mbuf *m);
221 void mac_ip6q_update(struct mbuf *m, struct ip6q *q6);
|
| /freebsd/contrib/bearssl/src/symcipher/ |
| H A D | aes_ct64_dec.c | 35 uint64_t q0, q1, q2, q3, q4, q5, q6, q7; in br_aes_ct64_bitslice_invSbox() local
43 q6 = ~q[6]; in br_aes_ct64_bitslice_invSbox()
45 q[7] = q1 ^ q4 ^ q6; in br_aes_ct64_bitslice_invSbox()
48 q[4] = q6 ^ q1 ^ q3; in br_aes_ct64_bitslice_invSbox()
51 q[1] = q3 ^ q6 ^ q0; in br_aes_ct64_bitslice_invSbox()
62 q6 = ~q[6]; in br_aes_ct64_bitslice_invSbox()
64 q[7] = q1 ^ q4 ^ q6; in br_aes_ct64_bitslice_invSbox()
67 q[4] = q6 ^ q1 ^ q3; in br_aes_ct64_bitslice_invSbox()
70 q[1] = q3 ^ q6 ^ q0; in br_aes_ct64_bitslice_invSbox()
112 uint64_t q0, q1, q2, q3, q4, q5, q6, q7; in inv_mix_columns() local
[all …]
|
| H A D | aes_ct_dec.c | 49 uint32_t q0, q1, q2, q3, q4, q5, q6, q7; in br_aes_ct_bitslice_invSbox() local
57 q6 = ~q[6]; in br_aes_ct_bitslice_invSbox()
59 q[7] = q1 ^ q4 ^ q6; in br_aes_ct_bitslice_invSbox()
62 q[4] = q6 ^ q1 ^ q3; in br_aes_ct_bitslice_invSbox()
65 q[1] = q3 ^ q6 ^ q0; in br_aes_ct_bitslice_invSbox()
76 q6 = ~q[6]; in br_aes_ct_bitslice_invSbox()
78 q[7] = q1 ^ q4 ^ q6; in br_aes_ct_bitslice_invSbox()
81 q[4] = q6 ^ q1 ^ q3; in br_aes_ct_bitslice_invSbox()
84 q[1] = q3 ^ q6 ^ q0; in br_aes_ct_bitslice_invSbox()
123 uint32_t q0, q1, q2, q3, q4, q5, q6, q7; in inv_mix_columns() local
[all …]
|
| H A D | aes_ct64_enc.c | 68 uint64_t q0, q1, q2, q3, q4, q5, q6, q7; in mix_columns() local
77 q6 = q[6]; in mix_columns()
85 r6 = (q6 >> 16) | (q6 << 48); in mix_columns()
94 q[6] = q5 ^ r5 ^ r6 ^ rotr32(q6 ^ r6); in mix_columns()
95 q[7] = q6 ^ r6 ^ r7 ^ rotr32(q7 ^ r7); in mix_columns()
|
| H A D | aes_ct_enc.c | 65 uint32_t q0, q1, q2, q3, q4, q5, q6, q7; in mix_columns() local
74 q6 = q[6]; in mix_columns()
82 r6 = (q6 >> 8) | (q6 << 24); in mix_columns()
91 q[6] = q5 ^ r5 ^ r6 ^ rotr16(q6 ^ r6); in mix_columns()
92 q[7] = q6 ^ r6 ^ r7 ^ rotr16(q7 ^ r7); in mix_columns()
|
| /freebsd/sys/crypto/openssl/arm/ |
| H A D | bsaes-armv7.S | 117 veor q10, q6, q9
127 vshr.u64 q10, q6, #1
137 veor q6, q6, q10
155 veor q11, q11, q6
160 veor q6, q6, q11
179 veor q11, q11, q6
184 veor q6, q6, q11
225 veor q10, q10, q6
238 veor q1, q1, q6
240 veor q6, q6, q4
[all …]
|
| H A D | poly1305-armv4.S | 426 vmull.u32 q6,d1,d0[1]
432 vmlal.u32 q6,d0,d1[1]
438 vmlal.u32 q6,d7,d4[1]
445 vmlal.u32 q6,d5,d6[1]
451 vmlal.u32 q6,d3,d8[1]
789 vmull.u32 q6,d23,d0[1]
799 vmlal.u32 q6,d21,d1[1]
805 vmlal.u32 q6,d29,d4[1]
811 vmlal.u32 q6,d27,d6[1]
817 vmlal.u32 q6,d25,d8[1]
[all …]
|
| H A D | armv4-mont.S | 636 vmlal.u32 q6,d29,d4[0]
644 vst1.64 {q6},[r7,:128]!
646 vld1.64 {q6},[r6,:128]
677 vmlal.u32 q6,d28,d3[0]
686 vmlal.u32 q6,d29,d7[0]
719 vmlal.u32 q6,d28,d2[0]
728 vmlal.u32 q6,d29,d6[0]
770 vmlal.u32 q6,d29,d5[0]
779 vmlal.u32 q6,d28,d0[1]
|
| H A D | chacha-armv4.S | 854 vmov q6,q2
887 vadd.i32 q6,q6,q7
893 veor q13,q5,q6
935 vadd.i32 q6,q6,q7
941 veor q13,q5,q6
959 vext.8 q6,q6,q6,#8
995 vadd.i32 q6,q6,q7
1001 veor q13,q5,q6
1043 vadd.i32 q6,q6,q7
1049 veor q13,q5,q6
[all …]
|
| H A D | sha1-armv4-large.S | 1382 vld1.8 {q6,q7},[r1]!
1387 vrev32.8 q6,q6
1395 vadd.i32 q12,q8,q6
1396 INST(0x4c,0x8c,0x3a,0xe2) @ sha1su0 q4,q5,q6
1401 INST(0x4e,0xac,0x3c,0xe2) @ sha1su0 q5,q6,q7
1406 INST(0x48,0xcc,0x3e,0xe2) @ sha1su0 q6,q7,q4
1410 INST(0x8a,0xc3,0xba,0xf3) @ sha1su1 q6,q5
1414 vadd.i32 q12,q9,q6
1415 INST(0x8c,0xe3,0xba,0xf3) @ sha1su1 q7,q6
1416 INST(0x4c,0x8c,0x3a,0xe2) @ sha1su0 q4,q5,q6
[all …]
|
| /freebsd/sys/contrib/openzfs/module/icp/algs/edonr/ |
| H A D | edonr.c | 121 uint64_t q0, q1, q2, q3, q4, q5, q6, q7; in Q512() local
159 QEF_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
167 LS2_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
168 QEF_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
175 LS1_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
177 QEF_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
185 LS2_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
186 QEF_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
203 p[14] ^= d(6) ^ q6; in Q512()
|
| /freebsd/share/msgdef/ |
| H A D | zh_CN.GB2312.src | 10 ^((7q6()|(7q)|([nN]([oO])?)|([nN]))
16 7q6(:7q:no:n:NO:N
|
| /freebsd/tools/test/xregs_sig/ |
| H A D | c2x2c_aarch64.S | 23 stp q6, q7, [x0, #( 6 * 16)]
47 ldp q6, q7, [x0, #( 6 * 16)]
|
| /freebsd/contrib/arm-optimized-routines/math/aarch64/sve/ |
| H A D | erfc.c | 19 double q6, r6; member
41 .q6 = 0x1.2aaaaaaaaaaabp0,
122 svfloat64_t qr6 = svld1rq (svptrue_b64 (), &dat->q6); in SV_NAME_D1()
|
| /freebsd/contrib/llvm-project/lldb/source/Plugins/Process/Utility/ |
| H A D | RegisterInfos_arm.h | 612 FPU_REG(s24, 4, 24, q6),
613 FPU_REG(s25, 4, 25, q6),
614 FPU_REG(s26, 4, 26, q6),
615 FPU_REG(s27, 4, 27, q6),
647 FPU_REG(d12, 8, 24, q6),
648 FPU_REG(d13, 8, 26, q6),
674 FPU_QREG(q6, 24),
|
| /freebsd/crypto/openssl/crypto/aes/asm/ |
| H A D | bsaes-armv8.pl | 1054 ldr q6, [sp]
1057 str q6, [sp]
1075 ldr q6, [x0], #16
1128 ldr q6, [x0], #-6*16
1147 str q6, [x1], #16
1363 ldr q6, [x0], #16
1365 ldr q6, [x0], #16
1395 str q6, [x1], #16
1545 ldr q6, .Lxts_magic+16
1624 str q6, [x21], #16
[all …]
|
| /freebsd/sys/contrib/device-tree/src/arm64/qcom/ |
| H A D | qcs8550.dtsi | 92 q6_mpss_dtb_mem: q6-mpss-dtb-region@9b000000 {
142 q6_cdsp_dtb_mem: q6-cdsp-dtb-region@9e900000 {
147 q6_adsp_dtb_mem: q6-adsp-dtb-region@9e980000 {
|
| H A D | qru1000.dtsi | 22 tenx_q6_buffer_mem: tenx-q6-buffer@b4e00000 {
|
| /freebsd/contrib/llvm-project/compiler-rt/lib/orc/ |
| H A D | sysv_reenter.arm64.S | 47 stp q6, q7, [sp, #-32]!
71 ldp q6, q7, [sp], #32
|
| H A D | elfnix_tls.aarch64.S | 52 stp q6, q7, [sp, #32 * 20]
63 ldp q6, q7, [sp, #32 * 20]
|
| H A D | macho_tlv.arm64.S | 51 stp q6, q7, [sp, #32 * 20]
61 ldp q6, q7, [sp, #32 * 20]
|
| /freebsd/contrib/llvm-project/compiler-rt/lib/xray/ |
| H A D | xray_trampoline_AArch64.S | 12 stp q6, q7, [sp, #-32]!
19 ldp q6, q7, [sp], #32
|
| /freebsd/libexec/rtld-elf/aarch64/ |
| H A D | rtld_start.S | 77 stp q6, q7, [sp, #-32]!
97 ldp q6, q7, [sp], #32
|