Home
last modified time | relevance | path

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

12345678

/freebsd/sys/powerpc/fpu/
H A Dfpu_subr.c72 m0 = fp->fp_mant[0]; in fpu_shr()
100 m3 = m0, m2 = 0, m1 = 0, m0 = 0; in fpu_shr()
103 m3 = m1, m2 = m0, m1 = 0, m0 = 0; in fpu_shr()
106 m3 = m2, m2 = m1, m1 = m0, m0 = 0; in fpu_shr()
116 m0 >>= rsh; in fpu_shr()
118 fp->fp_mant[0] = m0; in fpu_shr()
142 m0 = fp->fp_mant[0]; in fpu_norm()
148 if (m0 == 0) { in fpu_norm()
164 if (m0 >= sup) { in fpu_norm()
176 m0 = top; in fpu_norm()
[all …]
/freebsd/sys/net/altq/
H A Daltq_classq.h103 m0 = m; in _addq()
104 m0->m_nextpkt = m; in _addq()
113 struct mbuf *m, *m0; in _getq() local
124 return (m0); in _getq()
136 prev = m0; in _getq_tail()
137 m0 = m0->m_nextpkt; in _getq_tail()
138 } while (m0 != m); in _getq_tail()
182 m0 = qtail(q); in _removeq()
184 prev = m0; in _removeq()
185 m0 = m0->m_nextpkt; in _removeq()
[all …]
H A Daltq_subr.c743 struct mbuf *m0; in read_dsfield() local
751 for (m0 = m; m0 != NULL; m0 = m0->m_next) in read_dsfield()
753 (pktattr->pattr_hdr < m0->m_data + m0->m_len)) in read_dsfield()
795 for (m0 = m; m0 != NULL; m0 = m0->m_next) in write_dsfield()
797 (pktattr->pattr_hdr < m0->m_data + m0->m_len)) in write_dsfield()
1136 for (m0 = m; m0 != NULL; m0 = m0->m_next)
1138 ((caddr_t)ip < m0->m_data + m0->m_len))
1154 m0 = m0->m_next;
1226 for (m0 = m; m0 != NULL; m0 = m0->m_next)
1228 ((caddr_t)ip6 < m0->m_data + m0->m_len))
[all …]
/freebsd/sys/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 …]
/freebsd/sys/dev/clk/allwinner/
H A Daw_clk_nmm.c105 uint32_t n, m0, m1; in aw_clk_nmm_find_best() local
118 for (m0 = min_m0; m0 <= max_m0; ) { in aw_clk_nmm_find_best()
132 m0++; in aw_clk_nmm_find_best()
175 m0 = aw_clk_factor_get_value(&sc->m0, best_m0); in aw_clk_nmm_set_freq()
181 val |= m0 << sc->m0.shift; in aw_clk_nmm_set_freq()
215 m0 = aw_clk_get_factor(val, &sc->m0); in aw_clk_nmm_recalc()
255 sc->m0.shift = clkdef->m0.shift; in aw_clk_nmm_register()
256 sc->m0.width = clkdef->m0.width; in aw_clk_nmm_register()
257 sc->m0.mask = ((1 << sc->m0.width) - 1) << sc->m0.shift; in aw_clk_nmm_register()
258 sc->m0.value = clkdef->m0.value; in aw_clk_nmm_register()
[all …]
/freebsd/sys/netipsec/
H A Dipsec_mbuf.c170 struct mbuf *m0, *m1; in m_pad() local
182 m0 = m; in m_pad()
185 len -= m0->m_len; in m_pad()
186 m0 = m0->m_next; in m_pad()
210 m0 = m1->m_next; in m_pad()
217 m_freem(m0); in m_pad()
222 m0->m_next = m1; in m_pad()
223 m0 = m1; in m_pad()
224 m0->m_len = 0; in m_pad()
227 retval = m0->m_data + m0->m_len; in m_pad()
[all …]
/freebsd/crypto/openssl/crypto/bn/asm/
H A Dia64-mont.pl514 (p17) xma.hu nhi[7]=ni6,mj[1],nhi[6] // np[6]*m0
534 (p17) xma.hu nhi[8]=ni7,mj[1],nhi[7] // np[7]*m0
554 (p16) xma.hu nhi[0]=ni0,mj[0],alo[0] // np[0]*m0
574 (p16) xma.hu nhi[1]=ni1,mj[0],nhi[0] // np[1]*m0
594 (p16) xma.hu nhi[2]=ni2,mj[0],nhi[1] // np[2]*m0
614 (p16) xma.hu nhi[3]=ni3,mj[0],nhi[2] // np[3]*m0
632 (p16) xma.hu nhi[4]=ni4,mj[0],nhi[3] // np[4]*m0
652 (p16) xma.hu nhi[5]=ni5,mj[0],nhi[4] // np[5]*m0
676 (p17) xma.hu nhi[7]=ni6,mj[1],nhi[6] // np[6]*m0
693 (p17) xma.hu nhi[8]=ni7,mj[1],nhi[7] // np[7]*m0
H A Dvis3-mont.pl107 sllx $t3, 32, $m0
109 or $t2, $m0, $m0
118 mulx $aj, $m0, $lo0 ! ap[0]*bp[0]
119 umulxhi $aj, $m0, $hi0
137 umulxhi $aj, $m0, $aj ! ahi=aj
177 umulxhi $aj, $m0, $aj ! ahi=aj
219 sllx $t3, 32, $m0
221 or $t2, $m0, $m0
226 umulxhi $aj, $m0, $hi0
232 umulxhi $aj, $m0, $aj ! ahi=aj
[all …]
/freebsd/sys/netpfil/ipfw/
H A Dip_fw_pfil.c144 args.m = *m0; in ipfw_check_packet()
150 *m0 = args.m; in ipfw_check_packet()
284 if (*m0) in ipfw_check_packet()
320 if (*m0) in ipfw_check_packet()
321 FREE_PKT(*m0); in ipfw_check_packet()
322 *m0 = NULL; in ipfw_check_packet()
358 args.m = *m0; in ipfw_check_frame_mbuf()
361 *m0 = args.m; in ipfw_check_frame_mbuf()
399 if (*m0) in ipfw_check_frame_mbuf()
401 *m0 = NULL; in ipfw_check_frame_mbuf()
[all …]
/freebsd/sys/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 …]
/freebsd/lib/libiconv_modules/VIQR/
H A Dcitrus_viqr.c163 mnemonic_t *m0; in mnemonic_append_child() local
170 if (m0 == NULL) { in mnemonic_append_child()
172 if (m0 == NULL) in mnemonic_append_child()
176 m = m0; in mnemonic_append_child()
179 if (m0 == NULL) { in mnemonic_append_child()
181 if (m0 == NULL) in mnemonic_append_child()
185 m = m0; in mnemonic_append_child()
187 if (m0 == NULL) in mnemonic_append_child()
189 m0->value = value; in mnemonic_append_child()
293 if (m0 == NULL) in _citrus_VIQR_mbrtowc_priv()
[all …]
/freebsd/contrib/smbfs/lib/smb/
H A Dmbuf.c78 while (m0) { in m_freem()
79 m = m0->m_next; in m_freem()
80 m_free(m0); in m_freem()
81 m0 = m; in m_freem()
88 struct mbuf *m = m0; in m_totlen()
107 *mpp = m0; in m_lineup()
113 while (m0) { in m_lineup()
114 len = m0->m_len; in m_lineup()
117 m = m0->m_next; in m_lineup()
118 m_free(m0); in m_lineup()
[all …]
/freebsd/sys/netgraph/bluetooth/socket/
H A Dng_btsocket_rfcomm.c1827 if ((m0 = m_pullup(m0, length)) == NULL) { in ng_btsocket_rfcomm_receive_frame()
1874 NG_FREE_M(m0); in ng_btsocket_rfcomm_receive_frame()
1941 NG_FREE_M(m0); in ng_btsocket_rfcomm_receive_frame()
2321 m_adj(m0, 1); in ng_btsocket_rfcomm_receive_uih()
2366 m0 = NULL; in ng_btsocket_rfcomm_receive_uih()
2476 m0->m_pkthdr.len = m0->m_len = sizeof(*hdr); in ng_btsocket_rfcomm_receive_mcc()
2483 m0->m_data[m0->m_len] = RFCOMM_MKMCC_TYPE(cr, type); in ng_btsocket_rfcomm_receive_mcc()
2485 m0->m_len ++; in ng_btsocket_rfcomm_receive_mcc()
2727 m0->m_pkthdr.len = m0->m_len = sizeof(*hdr) + sizeof(*rpn); in ng_btsocket_rfcomm_receive_rpn()
2830 0, 0, m0); in ng_btsocket_rfcomm_receive_pn()
[all …]
/freebsd/sys/kern/
H A Duipc_sockbuf.c204 m = m0; in sbready()
232 if (m0 == m) { in sbready()
1171 if (m0 == NULL) in sbappendrecord_locked()
1185 m = m0->m_next; in sbappendrecord_locked()
1186 m0->m_next = 0; in sbappendrecord_locked()
1214 if (m0 != NULL) in sbappendaddr_locked_internal()
1228 if (m0) { in sbappendaddr_locked_internal()
1246 control = m0; in sbappendaddr_locked_internal()
1276 if (m0 && (m0->m_flags & M_PKTHDR) == 0) in sbappendaddr_locked()
1278 if (m0) in sbappendaddr_locked()
[all …]
H A Duipc_mbuf.c307 for (m = all ? m0 : m0->m_next; m != NULL; m = m->m_next) { in m_demote()
384 m = m0; in m_sanity()
1568 return (m0); in m_defrag()
1618 m_freem(m0); in m_defrag()
1619 m0 = m_final; in m_defrag()
1624 return (m0); in m_defrag()
1694 m = m0; in m_collapse()
1824 m_freem(m0); in m_fragment()
1826 return (m0); in m_fragment()
1831 return (m0); in m_fragment()
[all …]
H A Dkern_sendfile.c1035 mtail->m_next = m0; in vn_sendfile()
1037 m = m0; in vn_sendfile()
1038 mtail = m0; in vn_sendfile()
1039 m0->m_epg_1st_off = in vn_sendfile()
1044 m0->m_epg_nrdy++; in vn_sendfile()
1048 m0->m_epg_npgs++; in vn_sendfile()
1118 mtail->m_next = m0; in vn_sendfile()
1120 m = m0; in vn_sendfile()
1121 mtail = m0; in vn_sendfile()
1141 m0 = m; in vn_sendfile()
[all …]
/freebsd/sys/xdr/
H A Dxdr_mbuf.c105 struct mbuf *m0, *m; in xdrmbuf_getall() local
110 m0 = (struct mbuf *) xdrs->x_base; in xdrmbuf_getall()
112 if (m0 != m) { in xdrmbuf_getall()
113 while (m0->m_next != m) in xdrmbuf_getall()
114 m0 = m0->m_next; in xdrmbuf_getall()
115 m0->m_next = NULL; in xdrmbuf_getall()
246 struct mbuf *m0 = (struct mbuf *) xdrs->x_base; in xdrmbuf_getpos() local
250 while (m0 && m0 != m) { in xdrmbuf_getpos()
251 pos += m0->m_len; in xdrmbuf_getpos()
252 m0 = m0->m_next; in xdrmbuf_getpos()
[all …]
/freebsd/sys/dev/cxgbe/
H A Dt4_sge.c1614 m0 = NULL; in service_iq_fl()
1834 m0 = fl->m0; in get_fl_payload()
1856 fl->m0 = m0; in get_fl_payload()
1869 return (m0); in get_fl_payload()
2713 m0 = m_pullup(m0, m0->m_pkthdr.len); in parse_pkt()
2747 m = m0; in parse_pkt()
2883 immhdrs = m0->m_pkthdr.l2hlen + m0->m_pkthdr.l3hlen + in parse_pkt()
5391 m0->m_pkthdr.l3hlen + m0->m_pkthdr.l4hlen + in write_tnl_lso_cpl()
6632 immhdrs = m0->m_pkthdr.l2hlen + m0->m_pkthdr.l3hlen + m0->m_pkthdr.l4hlen; in write_ethofld_wr()
6722 for (; m0 != NULL; m0 = m0->m_next) { in write_ethofld_wr()
[all …]
/freebsd/sys/dev/rtwn/pci/
H A Drtwn_pci_tx.c59 rtwn_mbuf_defrag(struct mbuf *m0, int how) in rtwn_mbuf_defrag() argument
63 KASSERT(m0->m_flags & M_PKTHDR, in rtwn_mbuf_defrag()
64 ("M_PKTHDR flag is absent (m %p)!", m0)); in rtwn_mbuf_defrag()
67 if (m0->m_pkthdr.len > MJUMPAGESIZE) { in rtwn_mbuf_defrag()
70 } else if (m0->m_pkthdr.len > MCLBYTES) { in rtwn_mbuf_defrag()
75 if (m_dup_pkthdr(m, m0, how) == 0) { in rtwn_mbuf_defrag()
80 m_copydata(m0, 0, m0->m_pkthdr.len, mtod(m, caddr_t)); in rtwn_mbuf_defrag()
82 m_freem(m0); in rtwn_mbuf_defrag()
86 return (m_defrag(m0, how)); in rtwn_mbuf_defrag()

12345678