Home
last modified time | relevance | path

Searched refs:q6 (Results 1 – 25 of 62) sorted by relevance

123

/freebsd/sys/netinet6/
H A Dfrag6.c299 mac_ip6q_destroy(q6); in frag6_rmqueue()
301 free(q6, M_FRAG6); in frag6_rmqueue()
353 struct ip6q *q6; in frag6_cleanup() local
427 struct ip6q *q6; in frag6_input() local
580 if (q6 == NULL) { in frag6_input()
600 if (q6 == NULL) in frag6_input()
604 free(q6, M_FRAG6); in frag6_input()
803 q6->ip6q_nfrag++; in frag6_input()
863 nxt = q6->ip6q_nxt; in frag6_input()
987 if (q6 != NULL) { in frag6_slowtimo()
[all …]
/freebsd/sys/security/mac/
H A Dmac_inet6.c84 mac_ip6q_init(struct ip6q *q6, int flag) in mac_ip6q_init() argument
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()
124 MAC_POLICY_PERFORM_NOSLEEP(ip6q_reassemble, q6, q6->ip6q_label, m, in mac_ip6q_reassemble()
139 q6->ip6q_label); in mac_ip6q_create()
155 q6->ip6q_label); in mac_ip6q_match()
[all …]
H A Dmac_framework.h209 void mac_ip6q_create(struct mbuf *m, struct ip6q *q6);
210 void mac_ip6q_destroy(struct ip6q *q6);
211 int mac_ip6q_init(struct ip6q *q6, int);
212 int mac_ip6q_match(struct mbuf *m, struct ip6q *q6);
213 void mac_ip6q_reassemble(struct ip6q *q6, struct mbuf *m);
214 void mac_ip6q_update(struct mbuf *m, struct ip6q *q6);
/freebsd/contrib/bearssl/src/symcipher/
H A Daes_ct64_dec.c43 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()
121 q6 = q[6]; in inv_mix_columns()
129 r6 = (q6 >> 16) | (q6 << 48); in inv_mix_columns()
[all …]
H A Daes_ct_dec.c57 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()
132 q6 = q[6]; in inv_mix_columns()
140 r6 = (q6 >> 8) | (q6 << 24); in inv_mix_columns()
[all …]
H A Daes_ct64_enc.c68 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 Daes_ct_enc.c65 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 Dbsaes-armv7.S137 veor q6, q6, q10
160 veor q6, q6, q11
184 veor q6, q6, q11
240 veor q6, q6, q4
325 vand q6, q6, q13
331 veor q6, q6, q10
335 veor q6, q6, q8
367 veor q6, q6, q5
376 veor q6, q6, q1
403 veor q6, q6, q8
[all …]
H A Dpoly1305-armv4.S878 vadd.i64 q6,q6,q4 @ h0 -> h1
884 vshr.u64 q4,q6,#26
885 vmovn.i64 d12,q6
945 vmull.u32 q6,d23,d0
953 vmlal.u32 q6,d21,d1
962 vmlal.u32 q6,d29,d4
972 vmlal.u32 q6,d27,d6
1045 vadd.i64 q6,q6,q4 @ h0 -> h1
1049 vshr.u64 q4,q6,#26
1050 vand.i64 q6,q6,q0
[all …]
H A Darmv4-mont.S636 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 Dchacha-armv4.S854 vmov q6,q2
887 vadd.i32 q6,q6,q7
935 vadd.i32 q6,q6,q7
959 vext.8 q6,q6,q6,#8
995 vadd.i32 q6,q6,q7
1043 vadd.i32 q6,q6,q7
1067 vext.8 q6,q6,q6,#8
1114 vadd.i32 q6,q6,q14
1140 veor q6,q6,q14
1360 veor q6,q6,q14
[all …]
H A Dsha1-armv4-large.S1382 vld1.8 {q6,q7},[r1]!
1387 vrev32.8 q6,q6
1395 vadd.i32 q12,q8,q6
1410 INST(0x8a,0xc3,0xba,0xf3) @ sha1su1 q6,q5
1414 vadd.i32 q12,q9,q6
1415 INST(0x8c,0xe3,0xba,0xf3) @ sha1su1 q7,q6
1430 INST(0x8a,0xc3,0xba,0xf3) @ sha1su1 q6,q5
1434 vadd.i32 q12,q10,q6
1435 INST(0x8c,0xe3,0xba,0xf3) @ sha1su1 q7,q6
1454 vadd.i32 q12,q10,q6
[all …]
H A Dghashv8-armx.S149 INST(0x8f,0xce,0xa9,0xf2) @ pmull2 q6,q12,q7
167 veor q2,q2,q6
198 INST(0x8f,0xce,0xa9,0xf2) @ pmull2 q6,q12,q7
/freebsd/sys/contrib/openzfs/module/icp/algs/edonr/
H A Dedonr.c120 uint64_t q0, q1, q2, q3, q4, q5, q6, q7; in Q512() local
158 QEF_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
166 LS2_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
167 QEF_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
174 LS1_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
176 QEF_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
184 LS2_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
185 QEF_512(q0, q1, q2, q3, q4, q5, q6, q7); in Q512()
202 p[14] ^= d(6) ^ q6; in Q512()
/freebsd/share/msgdef/
H A Dzh_CN.GB2312.src10 ^((7q6()|(7q)|([nN]([oO])?)|([nN]))
16 7q6(:7q:no:n:NO:N
/freebsd/tools/test/xregs_sig/
H A Dc2x2c_aarch64.S23 stp q6, q7, [x0, #( 6 * 16)]
47 ldp q6, q7, [x0, #( 6 * 16)]
/freebsd/contrib/arm-optimized-routines/pl/math/
H A Dsv_erfc_1u8.c19 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 DRegisterInfos_arm.h619 FPU_REG(s24, 4, 24, q6),
620 FPU_REG(s25, 4, 25, q6),
621 FPU_REG(s26, 4, 26, q6),
622 FPU_REG(s27, 4, 27, q6),
654 FPU_REG(d12, 8, 24, q6),
655 FPU_REG(d13, 8, 26, q6),
681 FPU_QREG(q6, 24),
/freebsd/contrib/llvm-project/compiler-rt/lib/orc/
H A Dmacho_tlv.arm64.S51 stp q6, q7, [sp, #32 * 20]
61 ldp q6, q7, [sp, #32 * 20]
H A Delfnix_tls.aarch64.S52 stp q6, q7, [sp, #32 * 20]
63 ldp q6, q7, [sp, #32 * 20]
/freebsd/contrib/llvm-project/compiler-rt/lib/xray/
H A Dxray_trampoline_AArch64.S12 stp q6, q7, [sp, #-32]!
19 ldp q6, q7, [sp], #32
/freebsd/sys/contrib/device-tree/src/arm64/qcom/
H A Dqru1000.dtsi22 tenx_q6_buffer_mem: tenx-q6-buffer@b4e00000 {
/freebsd/libexec/rtld-elf/aarch64/
H A Drtld_start.S78 stp q6, q7, [sp, #-32]!
98 ldp q6, q7, [sp], #32
/freebsd/sys/contrib/openzfs/module/icp/asm-arm/sha2/
H A Dsha512-armv7.S1209 vext.8 q14,q5,q6,#8 @ X[i+9]
1297 vext.8 q14,q6,q7,#8 @ X[i+9]
1551 vext.8 q14,q5,q6,#8 @ X[i+1]
1645 vadd.i64 q6,q15
1652 vadd.i64 q6,q14
1656 vadd.i64 q6,q15
1722 vshr.u64 q12,q6,#19
1723 vshr.u64 q13,q6,#61
1725 vshr.u64 q15,q6,#6
1726 vsli.64 q12,q6,#45
[all …]
/freebsd/sys/security/mac_stub/
H A Dmac_stub.c439 stub_ip6q_create(struct mbuf *m, struct label *mlabel, struct ip6q *q6, in stub_ip6q_create() argument
446 stub_ip6q_match(struct mbuf *m, struct label *mlabel, struct ip6q *q6, in stub_ip6q_match() argument
454 stub_ip6q_reassemble(struct ip6q *q6, struct label *q6label, struct mbuf *m, in stub_ip6q_reassemble() argument
461 stub_ip6q_update(struct mbuf *m, struct label *mlabel, struct ip6q *q6, in stub_ip6q_update() argument

123