Home
last modified time | relevance | path

Searched full:m0 (Results 1 – 25 of 334) sorted by relevance

12345678910>>...14

/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.c42 * clk = clkin * n / m0 / m1
50 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
[all …]
/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/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/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()
153 ipfw == IP_FW_NAT64, ("%s: m0 is NULL", __func__)); 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()
[all …]
/freebsd/sys/dev/cxgbe/
H A Dt4_sge.c1580 struct mbuf *m0; in service_iq_fl() local
1614 m0 = NULL; in service_iq_fl()
1637 m0 = get_fl_payload(sc, fl, lq); in service_iq_fl()
1638 if (__predict_false(m0 == NULL)) in service_iq_fl()
1646 t4_cpl_handler[d->rss.opcode](iq, &d->rss, m0); in service_iq_fl()
1826 struct mbuf *m0, *m, **pnext; in get_fl_payload() local
1830 M_ASSERTPKTHDR(fl->m0); in get_fl_payload()
1831 MPASS(fl->m0->m_pkthdr.len == plen); in get_fl_payload()
1834 m0 = fl->m0; in get_fl_payload()
1846 m0 = get_scatter_segment(sc, fl, 0, plen); in get_fl_payload()
[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/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/kern/
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()
311 KASSERT(m->m_nextpkt == NULL, ("%s: m_nextpkt in m %p, m0 %p", 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()
[all …]
H A Duipc_sockbuf.c102 * mbufs similar to sbcompress() once mbufs are ready. 'm0' is the first
107 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()
232 if (m0 == m) { in sbready()
238 sbready_compress(sb, m0, m); in sbready()
251 sbready_compress(sb, m0, m); in sbready()
915 #define SBLINKRECORD(sb, m0) do { \ argument
918 (sb)->sb_lastrecord->m_nextpkt = (m0); \
[all …]
H A Dkern_sendfile.c759 struct mbuf *m0, *mtail; in vn_sendfile() local
1005 m0 = mb_alloc_ext_pgs(M_WAITOK, in vn_sendfile()
1009 m0->m_ext.ext_flags |= in vn_sendfile()
1020 m0->m_ext.ext_flags |= in vn_sendfile()
1024 m0->m_ext.ext_flags |= in vn_sendfile()
1026 m0->m_ext.ext_arg1 = sfs; in vn_sendfile()
1035 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()
[all …]
/freebsd/crypto/openssl/crypto/bn/asm/
H A Dvis3-mont.pl47 ($n0,$m0,$m1,$lo0,$hi0, $lo1,$hi1,$aj,$alo,$nj,$nlo,$tj)=
100 ld [$bp+0], $t2 ! m0=bp[0]
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
[all …]
/freebsd/contrib/llvm-project/llvm/utils/TableGen/Common/
H A DInfoByHwMode.cpp149 unsigned M0 = Map.begin()->first; in operator <() local
150 return get(M0) < I.get(M0); in operator <()
154 unsigned M0 = Map.begin()->first; in operator ==() local
155 return get(M0) == I.get(M0); in operator ==()
159 unsigned M0 = Map.begin()->first; in isSubClassOf() local
160 return get(M0).isSubClassOf(I.get(M0)); in isSubClassOf()
165 unsigned M0 = Map.begin()->first; in hasStricterSpillThan() local
166 const RegSizeInfo &A0 = get(M0); in hasStricterSpillThan()
167 const RegSizeInfo &B0 = I.get(M0); in hasStricterSpillThan()
/freebsd/crypto/heimdal/lib/kadm5/
H A Dad.c129 LDAPMessage *m, *m0; in ldap_tsasl_bind_s() local
141 rc = ldap_search_s(ld, "", LDAP_SCOPE_BASE, NULL, attrs, 0, &m0); in ldap_tsasl_bind_s()
145 m = ldap_first_entry(ld, m0); in ldap_tsasl_bind_s()
147 ldap_msgfree(m0); in ldap_tsasl_bind_s()
153 ldap_msgfree(m0); in ldap_tsasl_bind_s()
159 ldap_msgfree(m0); in ldap_tsasl_bind_s()
163 ldap_msgfree(m0); in ldap_tsasl_bind_s()
356 LDAPMessage *m, *m0; in _kadm5_ad_connect() local
371 m0 = ldap_first_entry(CTX2LP(context), m); in _kadm5_ad_connect()
372 if (m0 == NULL) { in _kadm5_ad_connect()
[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 …]

12345678910>>...14