Home
last modified time | relevance | path

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

123456789

/freebsd/sys/powerpc/fpu/
H A Dfpu_subr.c64 u_int m0, m1, m2, m3, s; in fpu_shr() local
72 m0 = fp->fp_mant[0]; in fpu_shr()
80 if ((m0 | m1 | m2 | m3) == 0) in fpu_shr()
88 if ((m0 | m1 | m2 | m3) == 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()
115 m1 = (m1 >> rsh) | (m0 << lsh); in fpu_shr()
116 m0 >>= rsh; in fpu_shr()
118 fp->fp_mant[0] = m0; in fpu_shr()
[all …]
/freebsd/sys/net/altq/
H A Daltq_classq.h98 struct mbuf *m0; in _addq() local
100 if ((m0 = qtail(q)) != NULL) in _addq()
101 m->m_nextpkt = m0->m_nextpkt; in _addq()
103 m0 = m; in _addq()
104 m0->m_nextpkt = m; in _addq()
113 struct mbuf *m, *m0; in _getq() local
117 if ((m0 = m->m_nextpkt) != m) in _getq()
118 m->m_nextpkt = m0->m_nextpkt; in _getq()
122 qsize(q) -= m_pktlen(m0); in _getq()
123 m0->m_nextpkt = NULL; in _getq()
[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()
752 if ((pktattr->pattr_hdr >= m0->m_data) && in read_dsfield()
753 (pktattr->pattr_hdr < m0->m_data + m0->m_len)) in read_dsfield()
755 if (m0 == NULL) { in read_dsfield()
788 struct mbuf *m0; in write_dsfield() local
795 for (m0 = m; m0 != NULL; m0 = m0->m_next) in write_dsfield()
796 if ((pktattr->pattr_hdr >= m0->m_data) && in write_dsfield()
797 (pktattr->pattr_hdr < m0->m_data + m0->m_len)) in write_dsfield()
799 if (m0 == NULL) { in write_dsfield()
[all …]
/freebsd/sys/contrib/libb2/
H A Dblake2s-load-sse41.h18 buf = TOI(_mm_shuffle_ps(TOF(m0), TOF(m1), _MM_SHUFFLE(2,0,2,0)));
21 buf = TOI(_mm_shuffle_ps(TOF(m0), TOF(m1), _MM_SHUFFLE(3,1,3,1)));
44 t2 = _mm_blend_epi16(m0, t1, 0xF0); \
48 t0 = _mm_unpackhi_epi32(m0,m1); \
60 t0 = _mm_unpacklo_epi32(m2,m0); \
61 t1 = _mm_blend_epi16(t0, m0, 0xF0); \
66 t0 = _mm_blend_epi16(m0, m2, 0x3C); \
73 t1 = _mm_blend_epi16(m0, m1, 0x33); \
78 t0 = _mm_unpackhi_epi32(m0,m1); \
85 t1 = _mm_blend_epi16(m3,m0,0x0C); \
[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); \
68 b0 = _mm_shuffle_epi32(m0, _MM_SHUFFLE(1,0,3,2)); \
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); \
156 b0 = _mm_blend_epi16(m0, m3, 0xF0); \
172 b0 = _mm_alignr_epi8(m6, m0, 8); \
181 b1 = _mm_unpacklo_epi64(m0, m4); \
[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)
56 #define LOAD_MSG_9_4(b0, b1) b0 = _mm_set_epi64x(m14, m11); b1 = _mm_set_epi64x(m0, m12)
[all …]
/freebsd/sys/dev/clk/allwinner/
H A Daw_clk_nmm.c50 struct aw_clk_factor m0; member
105 uint32_t n, m0, m1; in aw_clk_nmm_find_best() local
113 max_m0 = aw_clk_factor_get_max(&sc->m0); in aw_clk_nmm_find_best()
114 min_m0 = aw_clk_factor_get_min(&sc->m0); in aw_clk_nmm_find_best()
118 for (m0 = min_m0; m0 <= max_m0; ) { in aw_clk_nmm_find_best()
121 cur = fparent * n / m0 / m1; in aw_clk_nmm_find_best()
125 *factor_m0 = m0; in aw_clk_nmm_find_best()
132 m0++; in aw_clk_nmm_find_best()
144 uint32_t val, n, m0, m1, best_n, best_m0, best_m1; in aw_clk_nmm_set_freq() local
175 m0 = aw_clk_factor_get_value(&sc->m0, best_m0); in aw_clk_nmm_set_freq()
[all …]
/freebsd/sys/netipsec/
H A Dipsec_mbuf.c54 m_makespace(struct mbuf *m0, int skip, int hlen, int *off) in m_makespace() argument
59 IPSEC_ASSERT(m0 != NULL, ("null mbuf")); in m_makespace()
62 for (m = m0; m && skip > m->m_len; m = m->m_next) in m_makespace()
158 m0->m_pkthdr.len += hlen; /* adjust packet length */ in m_makespace()
170 struct mbuf *m0, *m1; in m_pad() local
182 m0 = m; in m_pad()
184 while (m0->m_len < len) { in m_pad()
185 len -= m0->m_len; in m_pad()
186 m0 = m0->m_next; in m_pad()
189 if (m0->m_len != len) { in m_pad()
[all …]
/freebsd/sys/netpfil/ipfw/
H A Dip_fw_pfil.c121 ipfw_check_packet(struct mbuf **m0, struct ifnet *ifp, int flags, in ipfw_check_packet() argument
136 tag = m_tag_locate(*m0, MTAG_IPFW_RULE, 0, NULL); in ipfw_check_packet()
139 m_tag_delete(*m0, tag); in ipfw_check_packet()
145 args.m = *m0; in ipfw_check_packet()
150 *m0 = args.m; in ipfw_check_packet()
152 KASSERT(*m0 != NULL || ipfw == IP_FW_DENY || in ipfw_check_packet()
179 (*m0)->m_flags |= M_FASTFWD_OURS; in ipfw_check_packet()
180 (*m0)->m_flags |= M_IP_NEXTHOP; in ipfw_check_packet()
192 (*m0)->m_flags |= M_IP6_NEXTHOP; in ipfw_check_packet()
201 m_tag_find(*m0, PACKET_TAG_IPFORWARD, NULL); in ipfw_check_packet()
[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.pl47 ($n0,$m0,$m1,$lo0,$hi0, $lo1,$hi1,$aj,$alo,$nj,$nlo,$tj)=
107 sllx $t3, 32, $m0
109 or $t2, $m0, $m0
118 mulx $aj, $m0, $lo0 ! ap[0]*bp[0]
119 umulxhi $aj, $m0, $hi0
136 mulx $aj, $m0, $alo ! ap[1]*bp[0]
137 umulxhi $aj, $m0, $aj ! ahi=aj
175 mulx $aj, $m0, $alo ! ap[j]*bp[0]
177 umulxhi $aj, $m0, $aj ! ahi=aj
219 sllx $t3, 32, $m0
[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); \
57 b0 = _mm_shuffle_epi32(m0, _MM_SHUFFLE(1, 0, 3, 2)); \
75 b0 = _mm_unpacklo_epi64(m4, m0); \
88 b1 = _mm_alignr_epi8(m2, m0, 8); \
99 b0 = _mm_unpackhi_epi64(m4, m0); \
112 b1 = _mm_unpacklo_epi64(m0, m4); \
123 b0 = _mm_blend_epi16(m0, m3, 0xF0); \
135 b0 = _mm_alignr_epi8(m6, m0, 8); \
142 b1 = _mm_unpacklo_epi64(m0, m4); \
[all …]
H A Dblake2b-load-avx2.h6 t0 = _mm256_unpacklo_epi64(m0, m1); \
13 t0 = _mm256_unpackhi_epi64(m0, m1); \
48 t0 = _mm256_shuffle_epi32(m0, _MM_SHUFFLE(1, 0, 3, 2)); \
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); \
[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
169 m0 = mnemonic_list_find(&m->child, ch); in mnemonic_append_child()
170 if (m0 == NULL) { in mnemonic_append_child()
171 m0 = mnemonic_create(m, ch, (wchar_t)ch); in mnemonic_append_child()
172 if (m0 == NULL) in mnemonic_append_child()
174 TAILQ_INSERT_TAIL(&m->child, m0, entry); in mnemonic_append_child()
176 m = m0; in mnemonic_append_child()
177 for (m0 = NULL; (ch = (unsigned char)*s) != '\0'; ++s) { in mnemonic_append_child()
178 m0 = mnemonic_list_find(&m->child, ch); in mnemonic_append_child()
179 if (m0 == NULL) { in mnemonic_append_child()
[all …]
/freebsd/contrib/smbfs/lib/smb/
H A Dmbuf.c74 m_freem(struct mbuf *m0) in m_freem() argument
78 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()
86 m_totlen(struct mbuf *m0) in m_totlen() argument
88 struct mbuf *m = m0; in m_totlen()
99 m_lineup(struct mbuf *m0, struct mbuf **mpp) in m_lineup() argument
106 if (m0->m_next == NULL) { in m_lineup()
107 *mpp = m0; in m_lineup()
[all …]
/freebsd/sys/dev/cxgbe/
H A Dt4_sge.c1620 struct mbuf *m0; in service_iq_fl() local
1654 m0 = NULL; in service_iq_fl()
1677 m0 = get_fl_payload(sc, fl, lq); in service_iq_fl()
1678 if (__predict_false(m0 == NULL)) in service_iq_fl()
1686 t4_cpl_handler[d->rss.opcode](iq, &d->rss, m0); in service_iq_fl()
1866 struct mbuf *m0, *m, **pnext; in get_fl_payload() local
1870 M_ASSERTPKTHDR(fl->m0); in get_fl_payload()
1871 MPASS(fl->m0->m_pkthdr.len == plen); in get_fl_payload()
1874 m0 = fl->m0; in get_fl_payload()
1886 m0 = get_scatter_segment(sc, fl, 0, plen); in get_fl_payload()
[all …]
/freebsd/sys/netgraph/bluetooth/socket/
H A Dng_btsocket_rfcomm.c133 (ng_btsocket_rfcomm_session_p s, struct mbuf *m0);
143 (ng_btsocket_rfcomm_session_p s, int dlci, int pf, struct mbuf *m0);
145 (ng_btsocket_rfcomm_session_p s, struct mbuf *m0);
147 (ng_btsocket_rfcomm_session_p s, struct mbuf *m0);
149 (ng_btsocket_rfcomm_session_p s, struct mbuf *m0);
151 (ng_btsocket_rfcomm_session_p s, struct mbuf *m0);
153 (ng_btsocket_rfcomm_session_p s, struct mbuf *m0);
155 (ng_btsocket_rfcomm_session_p s, struct mbuf *m0);
157 (ng_btsocket_rfcomm_session_p s, struct mbuf *m0);
1814 struct mbuf *m0) in ng_btsocket_rfcomm_receive_frame() argument
[all …]
/freebsd/sys/kern/
H A Duipc_sockbuf.c107 sbready_compress(struct sockbuf *sb, struct mbuf *m0, struct mbuf *end) in sbready_compress() argument
117 for (m = m0; m != end; m = m->m_next) { in sbready_compress()
195 sbready(struct sockbuf *sb, struct mbuf *m0, int count) in sbready() argument
204 m = m0; in sbready()
231 if (m0 == m) { in sbready()
237 sbready_compress(sb, m0, m); in sbready()
246 sbready_compress(sb, m0, m); in sbready()
912 #define SBLINKRECORD(sb, m0) do { \ argument
915 (sb)->sb_lastrecord->m_nextpkt = (m0); \
917 (sb)->sb_mb = (m0); \
[all …]
H A Duipc_mbuf.c304 m_demote(struct mbuf *m0, int all, int flags) in m_demote() argument
310 for (m = all ? m0 : m0->m_next; m != NULL; m = m->m_next) { in m_demote()
312 __func__, m, m0)); in m_demote()
327 m_sanity(struct mbuf *m0, int sanitize) in m_sanity() argument
339 for (m = m0; m != NULL; m = m->m_next) { in m_sanity()
355 if (m != m0 && m->m_nextpkt != NULL) { in m_sanity()
364 if (m0->m_flags & M_PKTHDR) in m_sanity()
368 if (m != m0 && m->m_flags & M_PKTHDR && in m_sanity()
378 if (m != m0 && m->m_flags & M_PKTHDR) { in m_sanity()
387 m = m0; in m_sanity()
[all …]
H A Dkern_sendfile.c781 struct mbuf *m0, *mtail; in vn_sendfile() local
963 m0 = mb_alloc_ext_pgs(M_WAITOK, in vn_sendfile()
967 m0->m_ext.ext_flags |= in vn_sendfile()
978 m0->m_ext.ext_flags |= in vn_sendfile()
985 mtail->m_next = m0; in vn_sendfile()
987 m = m0; in vn_sendfile()
988 mtail = m0; in vn_sendfile()
989 m0->m_epg_1st_off = in vn_sendfile()
994 m0->m_epg_nrdy++; in vn_sendfile()
997 m0->m_epg_pa[ext_pgs_idx] = VM_PAGE_TO_PHYS(pga); in vn_sendfile()
[all …]
/freebsd/sys/xdr/
H A Dxdr_mbuf.c109 struct mbuf *m0, *m; in xdrmbuf_getall() local
114 m0 = (struct mbuf *) xdrs->x_base; in xdrmbuf_getall()
116 if (m0 != m) { in xdrmbuf_getall()
117 while (m0->m_next != m) in xdrmbuf_getall()
118 m0 = m0->m_next; in xdrmbuf_getall()
119 m0->m_next = NULL; in xdrmbuf_getall()
250 struct mbuf *m0 = (struct mbuf *) xdrs->x_base; in xdrmbuf_getpos() local
254 while (m0 && m0 != m) { in xdrmbuf_getpos()
255 pos += m0->m_len; in xdrmbuf_getpos()
256 m0 = m0->m_next; in xdrmbuf_getpos()
[all …]
/freebsd/lib/libmd/aarch64/
H A Dmd5block.S69 .macro rounds f, m0, m1, m2, m3, s0, s1, s2, s3, k0, k1, k2, k3
70 round a, b, c, d, \f, \k0, \m0, \s0
77 .macro rounds0 m0, m1, m2, m3, k0, k1, k2, k3
78 rounds f0, \m0, \m1, \m2, \m3, 7, 12, 17, 22, \k0, \k1, \k2, \k3
81 .macro rounds1 m0, m1, m2, m3, k0, k1, k2, k3
82 round1 a, b, c, d, \k0, \m0, 5
88 .macro rounds2 m0, m1, m2, m3, k0, k1, k2, k3
89 rounds f2, \m0, \m1, \m2, \m3, 4, 11, 16, 23, \k0, \k1, \k2, \k3
92 .macro rounds3 m0, m1, m2, m3, k0, k1, k2, k3
93 rounds f3, \m0, \m
109 m0 .req w10 global() label
[all...]

123456789