Home
last modified time | relevance | path

Searched refs:m0 (Results 1 – 25 of 105) sorted by relevance

12345

/f-stack/freebsd/net/altq/
H A Daltq_classq.h104 m0 = m; in _addq()
105 m0->m_nextpkt = m; in _addq()
114 struct mbuf *m, *m0; in _getq() local
125 return (m0); in _getq()
137 prev = m0; in _getq_tail()
138 m0 = m0->m_nextpkt; in _getq_tail()
139 } while (m0 != m); in _getq_tail()
183 m0 = qtail(q); in _removeq()
185 prev = m0; in _removeq()
186 m0 = m0->m_nextpkt; in _removeq()
[all …]
H A Daltq_subr.c741 struct mbuf *m0; local
749 for (m0 = m; m0 != NULL; m0 = m0->m_next)
751 (pktattr->pattr_hdr < m0->m_data + m0->m_len))
793 for (m0 = m; m0 != NULL; m0 = m0->m_next) in write_dsfield()
795 (pktattr->pattr_hdr < m0->m_data + m0->m_len)) in write_dsfield()
1138 for (m0 = m; m0 != NULL; m0 = m0->m_next)
1140 ((caddr_t)ip < m0->m_data + m0->m_len))
1156 m0 = m0->m_next;
1228 for (m0 = m; m0 != NULL; m0 = m0->m_next)
1230 ((caddr_t)ip6 < m0->m_data + m0->m_len))
[all …]
/f-stack/freebsd/contrib/libb2/
H A Dblake2s-load-sse41.h48 t0 = _mm_unpackhi_epi32(m0,m1); \
60 t0 = _mm_unpacklo_epi32(m2,m0); \
78 t0 = _mm_unpackhi_epi32(m0,m1); \
95 t0 = _mm_unpacklo_epi32(m0,m2); \
101 t1 = _mm_unpackhi_epi64(m0,m2); \
107 t1 = _mm_unpacklo_epi64(m0,m1); \
112 t1 = _mm_unpackhi_epi64(m2,m0); \
122 t0 = _mm_unpackhi_epi32(m0,m1); \
123 t1 = _mm_unpacklo_epi32(m0,m2); \
170 t1 = _mm_srli_si128(m0,4); \
[all …]
H A Dblake2s-load-xop.h31 buf = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(6),TOB(4),TOB(2),TOB(0)) );
34 buf = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(7),TOB(5),TOB(3),TOB(1)) );
51 t0 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(5),TOB(0),TOB(0),TOB(1)) ); \
55 t1 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(3),TOB(7),TOB(2),TOB(0)) ); \
63 t1 = _mm_perm_epi8(m0, m2, _mm_set_epi32(TOB(0),TOB(2),TOB(0),TOB(4)) ); \
67 t0 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(0),TOB(7),TOB(3),TOB(0)) ); \
71 t1 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(4),TOB(1),TOB(6),TOB(0)) ); \
75 t0 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(0),TOB(0),TOB(3),TOB(7)) ); \
80 t1 = _mm_perm_epi8(m0, m2, _mm_set_epi32(TOB(0),TOB(0),TOB(1),TOB(5)) ); \
84 t0 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(0),TOB(4),TOB(5),TOB(2)) ); \
[all …]
H A Dblake2b-load-sse41.h20 b0 = _mm_unpacklo_epi64(m0, m1); \
28 b0 = _mm_unpackhi_epi64(m0, m1); \
92 b0 = _mm_unpacklo_epi64(m4, m0); \
109 b1 = _mm_alignr_epi8(m2, m0, 8); \
124 b0 = _mm_unpackhi_epi64(m4, m0); \
141 b1 = _mm_unpacklo_epi64(m0, m4); \
172 b0 = _mm_alignr_epi8(m6, m0, 8); \
181 b1 = _mm_unpacklo_epi64(m0, m4); \
197 b1 = _mm_unpackhi_epi64(m7, m0); \
228 b0 = _mm_unpacklo_epi64(m0, m3); \
[all …]
H A Dblake2s-load-sse2.h17 #define LOAD_MSG_0_1(buf) buf = _mm_set_epi32(m6,m4,m2,m0)
23 #define LOAD_MSG_1_3(buf) buf = _mm_set_epi32(m5,m11,m0,m1)
26 #define LOAD_MSG_2_2(buf) buf = _mm_set_epi32(m13,m2,m0,m8)
32 #define LOAD_MSG_3_4(buf) buf = _mm_set_epi32(m8,m0,m10,m6)
34 #define LOAD_MSG_4_2(buf) buf = _mm_set_epi32(m15,m4,m7,m0)
37 #define LOAD_MSG_5_1(buf) buf = _mm_set_epi32(m8,m0,m6,m2)
43 #define LOAD_MSG_6_3(buf) buf = _mm_set_epi32(m8,m9,m6,m0)
48 #define LOAD_MSG_7_4(buf) buf = _mm_set_epi32(m10,m6,m4,m0)
49 #define LOAD_MSG_8_1(buf) buf = _mm_set_epi32(m0,m11,m14,m6)
56 #define LOAD_MSG_9_4(buf) buf = _mm_set_epi32(m0,m12,m14,m11)
H A Dblake2b-load-sse2.h17 #define LOAD_MSG_0_1(b0, b1) b0 = _mm_set_epi64x(m2, m0); b1 = _mm_set_epi64x(m6, m4)
23 #define LOAD_MSG_1_3(b0, b1) b0 = _mm_set_epi64x(m0, m1); b1 = _mm_set_epi64x(m5, m11)
26 #define LOAD_MSG_2_2(b0, b1) b0 = _mm_set_epi64x(m0, m8); b1 = _mm_set_epi64x(m13, m2)
32 #define LOAD_MSG_3_4(b0, b1) b0 = _mm_set_epi64x(m10, m6); b1 = _mm_set_epi64x(m8, m0)
34 #define LOAD_MSG_4_2(b0, b1) b0 = _mm_set_epi64x(m7, m0); b1 = _mm_set_epi64x(m15, m4)
37 #define LOAD_MSG_5_1(b0, b1) b0 = _mm_set_epi64x(m6, m2); b1 = _mm_set_epi64x(m8, m0)
43 #define LOAD_MSG_6_3(b0, b1) b0 = _mm_set_epi64x(m6, m0); b1 = _mm_set_epi64x(m8, m9)
48 #define LOAD_MSG_7_4(b0, b1) b0 = _mm_set_epi64x(m4, m0); b1 = _mm_set_epi64x(m10, m6)
49 #define LOAD_MSG_8_1(b0, b1) b0 = _mm_set_epi64x(m14, m6); b1 = _mm_set_epi64x(m0, m11)
57 #define LOAD_MSG_10_1(b0, b1) b0 = _mm_set_epi64x(m2, m0); b1 = _mm_set_epi64x(m6, m4)
[all …]
/f-stack/freebsd/arm/allwinner/clkng/
H A Daw_clk_nmm.c113 uint32_t n, m0, m1; in aw_clk_nmm_find_best() local
126 for (m0 = min_m0; m0 <= max_m0; ) { in aw_clk_nmm_find_best()
140 m0++; in aw_clk_nmm_find_best()
183 m0 = aw_clk_factor_get_value(&sc->m0, best_m0); in aw_clk_nmm_set_freq()
189 val |= m0 << sc->m0.shift; in aw_clk_nmm_set_freq()
223 m0 = aw_clk_get_factor(val, &sc->m0); in aw_clk_nmm_recalc()
263 sc->m0.shift = clkdef->m0.shift; in aw_clk_nmm_register()
264 sc->m0.width = clkdef->m0.width; in aw_clk_nmm_register()
265 sc->m0.mask = ((1 << sc->m0.width) - 1) << sc->m0.shift; in aw_clk_nmm_register()
266 sc->m0.value = clkdef->m0.value; in aw_clk_nmm_register()
[all …]
/f-stack/freebsd/netipsec/
H A Dipsec_mbuf.c175 struct mbuf *m0, *m1; in m_pad() local
187 m0 = m; in m_pad()
190 len -= m0->m_len; in m_pad()
191 m0 = m0->m_next; in m_pad()
215 m0 = m1->m_next; in m_pad()
222 m_freem(m0); in m_pad()
227 m0->m_next = m1; in m_pad()
228 m0 = m1; in m_pad()
229 m0->m_len = 0; in m_pad()
232 retval = m0->m_data + m0->m_len; in m_pad()
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-load-sse41.h21 b0 = _mm_unpacklo_epi64(m0, m1); \
27 b0 = _mm_unpackhi_epi64(m0, m1); \
88 b1 = _mm_alignr_epi8(m2, m0, 8); \
99 b0 = _mm_unpackhi_epi64(m4, m0); \
112 b1 = _mm_unpacklo_epi64(m0, m4); \
142 b1 = _mm_unpacklo_epi64(m0, m4); \
196 b1 = _mm_unpackhi_epi64(m0, m4); \
207 b0 = _mm_unpacklo_epi64(m0, m2); \
214 b1 = _mm_alignr_epi8(m0, m5, 8); \
226 b1 = _mm_alignr_epi8(m5, m0, 8); \
[all …]
H A Dblake2b-load-avx2.h6 t0 = _mm256_unpacklo_epi64(m0, m1); \
13 t0 = _mm256_unpackhi_epi64(m0, m1); \
69 t0 = _mm256_unpacklo_epi64(m4, m0); \
84 t1 = _mm256_alignr_epi8(m2, m0, 8); \
97 t0 = _mm256_unpackhi_epi64(m4, m0); \
112 t1 = _mm256_unpacklo_epi64(m0, m4); \
125 t0 = _mm256_blend_epi32(m3, m0, 0x33); \
139 t0 = _mm256_alignr_epi8(m6, m0, 8); \
147 t1 = _mm256_unpacklo_epi64(m0, m4); \
161 t1 = _mm256_unpackhi_epi64(m7, m0); \
[all …]
H A Dblake2b-load-sse2.h20 b0 = _mm_set_epi64x(m2, m0); \
38 b0 = _mm_set_epi64x(m0, m1); \
47 b0 = _mm_set_epi64x(m0, m8); \
66 b1 = _mm_set_epi64x(m8, m0)
71 b0 = _mm_set_epi64x(m7, m0); \
81 b1 = _mm_set_epi64x(m8, m0)
98 b0 = _mm_set_epi64x(m6, m0); \
113 b0 = _mm_set_epi64x(m4, m0); \
117 b1 = _mm_set_epi64x(m0, m11)
138 b1 = _mm_set_epi64x(m0, m12)
[all …]
/f-stack/freebsd/netpfil/ipfw/
H A Dip_fw_pfil.c140 m_tag_delete(*m0, tag); in ipfw_check_packet()
146 args.m = *m0; in ipfw_check_packet()
151 *m0 = args.m; in ipfw_check_packet()
204 m_tag_unlink(*m0, tag); in ipfw_check_packet()
215 m_tag_prepend(*m0, tag); in ipfw_check_packet()
271 if (*m0 != NULL) in ipfw_check_packet()
285 if (*m0) in ipfw_check_packet()
321 if (*m0) in ipfw_check_packet()
322 FREE_PKT(*m0); in ipfw_check_packet()
323 *m0 = NULL; in ipfw_check_packet()
[all …]
/f-stack/dpdk/examples/l3fwd/
H A Dl3fwd_em_hlm_neon.h12 get_ipv4_5tuple(struct rte_mbuf *m0, int32x4_t mask0, in get_ipv4_5tuple() argument
15 int32x4_t tmpdata0 = vld1q_s32(rte_pktmbuf_mtod_offset(m0, int32_t *, in get_ipv4_5tuple()
23 get_ipv6_5tuple(struct rte_mbuf *m0, int32x4_t mask0, in get_ipv6_5tuple() argument
27 rte_pktmbuf_mtod_offset(m0, int *, in get_ipv6_5tuple()
32 rte_pktmbuf_mtod_offset(m0, int *, in get_ipv6_5tuple()
37 rte_pktmbuf_mtod_offset(m0, int *, in get_ipv6_5tuple()
H A Dl3fwd_em_hlm_sse.h11 get_ipv4_5tuple(struct rte_mbuf *m0, __m128i mask0, in get_ipv4_5tuple() argument
15 rte_pktmbuf_mtod_offset(m0, __m128i *, in get_ipv4_5tuple()
23 get_ipv6_5tuple(struct rte_mbuf *m0, __m128i mask0, in get_ipv6_5tuple() argument
27 rte_pktmbuf_mtod_offset(m0, __m128i *, in get_ipv6_5tuple()
32 rte_pktmbuf_mtod_offset(m0, __m128i *, in get_ipv6_5tuple()
38 rte_pktmbuf_mtod_offset(m0, __m128i *, in get_ipv6_5tuple()
/f-stack/freebsd/kern/
H A Duipc_mbuf.c271 for (m = all ? m0 : m0->m_next; m != NULL; m = m->m_next) { in m_demote()
349 m = m0; in m_sanity()
1366 return (m0); in m_defrag()
1416 m_freem(m0); in m_defrag()
1417 m0 = m_final; in m_defrag()
1422 return (m0); in m_defrag()
1492 m = m0; in m_collapse()
1622 m_freem(m0); in m_fragment()
1624 return (m0); in m_fragment()
1629 return (m0); in m_fragment()
[all …]
H A Duipc_sockbuf.c209 m = m0; in sbready()
237 if (m0 == m) { in sbready()
1109 if (m0 == NULL) in sbappendrecord_locked()
1116 sballoc(sb, m0); in sbappendrecord_locked()
1119 sb->sb_mbtail = m0; in sbappendrecord_locked()
1120 m = m0->m_next; in sbappendrecord_locked()
1121 m0->m_next = 0; in sbappendrecord_locked()
1157 if (m0) { in sbappendaddr_locked_internal()
1174 control = m0; in sbappendaddr_locked_internal()
1204 if (m0 && (m0->m_flags & M_PKTHDR) == 0) in sbappendaddr_locked()
[all …]
H A Dkern_sendfile.c1039 mtail->m_next = m0; in vn_sendfile()
1041 m = m0; in vn_sendfile()
1042 mtail = m0; in vn_sendfile()
1043 m0->m_epg_1st_off = in vn_sendfile()
1048 m0->m_epg_nrdy++; in vn_sendfile()
1052 m0->m_epg_npgs++; in vn_sendfile()
1122 mtail->m_next = m0; in vn_sendfile()
1124 m = m0; in vn_sendfile()
1125 mtail = m0; in vn_sendfile()
1145 m0 = m; in vn_sendfile()
[all …]
/f-stack/freebsd/netgraph/bluetooth/socket/
H A Dng_btsocket_rfcomm.c1838 if ((m0 = m_pullup(m0, length)) == NULL) { in ng_btsocket_rfcomm_receive_frame()
1885 NG_FREE_M(m0); in ng_btsocket_rfcomm_receive_frame()
1952 NG_FREE_M(m0); in ng_btsocket_rfcomm_receive_frame()
2332 m_adj(m0, 1); in ng_btsocket_rfcomm_receive_uih()
2377 m0 = NULL; in ng_btsocket_rfcomm_receive_uih()
2487 m0->m_pkthdr.len = m0->m_len = sizeof(*hdr); in ng_btsocket_rfcomm_receive_mcc()
2494 m0->m_data[m0->m_len] = RFCOMM_MKMCC_TYPE(cr, type); in ng_btsocket_rfcomm_receive_mcc()
2496 m0->m_len ++; in ng_btsocket_rfcomm_receive_mcc()
2738 m0->m_pkthdr.len = m0->m_len = sizeof(*hdr) + sizeof(*rpn); in ng_btsocket_rfcomm_receive_rpn()
2841 0, 0, m0); in ng_btsocket_rfcomm_receive_pn()
[all …]
/f-stack/freebsd/netgraph/atm/
H A Dngatmbase.c140 struct mbuf *m, *m0, *last; in uni_msg_pack_mbuf() local
144 if (m0 == NULL) in uni_msg_pack_mbuf()
151 m0->m_len = hdrlen; in uni_msg_pack_mbuf()
152 m0->m_pkthdr.len = hdrlen; in uni_msg_pack_mbuf()
156 if (!(MCLGET(m0, M_NOWAIT))) in uni_msg_pack_mbuf()
164 m0->m_len = n; in uni_msg_pack_mbuf()
165 m0->m_pkthdr.len = n; in uni_msg_pack_mbuf()
168 last = m0; in uni_msg_pack_mbuf()
186 m0->m_pkthdr.len += n; in uni_msg_pack_mbuf()
189 return (m0); in uni_msg_pack_mbuf()
[all …]
/f-stack/freebsd/netinet6/
H A Dmld6.c2338 m0 = NULL; in mld_v2_enqueue_group_record()
2468 m = m0; in mld_v2_enqueue_group_record()
2500 if (m != m0) in mld_v2_enqueue_group_record()
2524 if (m == m0) { in mld_v2_enqueue_group_record()
2554 if (m != m0) in mld_v2_enqueue_group_record()
2573 if (m != m0) in mld_v2_enqueue_group_record()
2581 if (m != m0) { in mld_v2_enqueue_group_record()
2615 if (m != m0) in mld_v2_enqueue_group_record()
2751 m = m0; in mld_v2_enqueue_filter_change()
2888 if (m != m0) in mld_v2_enqueue_filter_change()
[all …]
/f-stack/freebsd/netgraph/bluetooth/l2cap/
H A Dng_l2cap_llpi.c558 m0 = ng_l2cap_prepend(m0, sizeof(*l2cap_hdr)); in ng_l2cap_lp_send()
559 if (m0 == NULL) { in ng_l2cap_lp_send()
580 while (m0 != NULL) { in ng_l2cap_lp_send()
582 len = m0->m_pkthdr.len; in ng_l2cap_lp_send()
596 m0 = ng_l2cap_prepend(m0, sizeof(*acl_hdr)); in ng_l2cap_lp_send()
597 if (m0 == NULL) { in ng_l2cap_lp_send()
612 m0->m_nextpkt = NULL; in ng_l2cap_lp_send()
617 m_last->m_nextpkt = m0; in ng_l2cap_lp_send()
618 m_last = m0; in ng_l2cap_lp_send()
626 m0 = m; in ng_l2cap_lp_send()
[all …]
/f-stack/freebsd/netinet/
H A Dip_output.c325 struct mbuf *m0; in ip_output() local
832 for (; m; m = m0) { in ip_output()
833 m0 = m->m_nextpkt; in ip_output()
906 m0 = mb_unmapped_to_ext(m0); in ip_fragment()
907 if (m0 == NULL) { in ip_fragment()
912 in_delayed_cksum(m0); in ip_fragment()
917 m0 = mb_unmapped_to_ext(m0); in ip_fragment()
918 if (m0 == NULL) { in ip_fragment()
923 sctp_delayed_cksum(m0, hlen); in ip_fragment()
1026 mac_netinet_fragment(m0, m); in ip_fragment()
[all …]
/f-stack/tools/compat/include/sys/
H A Dsockbuf.h148 struct mbuf *m0, struct mbuf *control);
150 struct mbuf *m0, struct mbuf *control);
152 const struct sockaddr *asa, struct mbuf *m0, struct mbuf *control);
153 void sbappendcontrol(struct sockbuf *sb, struct mbuf *m0,
155 void sbappendcontrol_locked(struct sockbuf *sb, struct mbuf *m0,
157 void sbappendrecord(struct sockbuf *sb, struct mbuf *m0);
158 void sbappendrecord_locked(struct sockbuf *sb, struct mbuf *m0);
/f-stack/freebsd/sys/
H A Dsockbuf.h148 struct mbuf *m0, struct mbuf *control);
150 struct mbuf *m0, struct mbuf *control);
152 const struct sockaddr *asa, struct mbuf *m0, struct mbuf *control);
153 void sbappendcontrol(struct sockbuf *sb, struct mbuf *m0,
155 void sbappendcontrol_locked(struct sockbuf *sb, struct mbuf *m0,
157 void sbappendrecord(struct sockbuf *sb, struct mbuf *m0);
158 void sbappendrecord_locked(struct sockbuf *sb, struct mbuf *m0);

12345