Home
last modified time | relevance | path

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

12345678910>>...15

/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/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, \m1, \m2, \m3, 6, 10, 15, 21, \k0, \k1, \k2, \k3
[all …]
/freebsd/sys/dev/cxgbe/
H A Dt4_sge.c1618 struct mbuf *m0; in service_iq_fl() local
1652 m0 = NULL; in service_iq_fl()
1675 m0 = get_fl_payload(sc, fl, lq); in service_iq_fl()
1676 if (__predict_false(m0 == NULL)) in service_iq_fl()
1684 t4_cpl_handler[d->rss.opcode](iq, &d->rss, m0); in service_iq_fl()
1864 struct mbuf *m0, *m, **pnext; in get_fl_payload() local
1868 M_ASSERTPKTHDR(fl->m0); in get_fl_payload()
1869 MPASS(fl->m0->m_pkthdr.len == plen); in get_fl_payload()
1872 m0 = fl->m0; in get_fl_payload()
1884 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.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/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()
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); \
[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/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/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/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>>...15