/freebsd/sys/powerpc/fpu/ |
H A D | fpu_subr.c | 72 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 D | altq_classq.h | 103 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 D | altq_subr.c | 743 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 D | blake2s-load-sse41.h | 48 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 D | blake2s-load-xop.h | 31 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 D | blake2b-load-sse41.h | 20 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 D | blake2s-load-sse2.h | 17 #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 D | blake2b-load-sse2.h | 17 #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 D | aw_clk_nmm.c | 105 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 D | ipsec_mbuf.c | 170 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 D | ia64-mont.pl | 514 (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 D | vis3-mont.pl | 107 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 D | ip_fw_pfil.c | 144 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 D | blake2b-load-sse41.h | 21 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 D | blake2b-load-avx2.h | 6 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 D | blake2b-load-sse2.h | 20 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 D | citrus_viqr.c | 163 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 D | mbuf.c | 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() 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 D | ng_btsocket_rfcomm.c | 1827 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 D | uipc_sockbuf.c | 204 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 D | uipc_mbuf.c | 307 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 D | kern_sendfile.c | 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() 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 D | xdr_mbuf.c | 105 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 D | t4_sge.c | 1614 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 D | rtwn_pci_tx.c | 59 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()
|