| /src/sys/arch/powerpc/fpu/ |
| fpu_subr.c | 70 u_int m0, m1, m2, m3, s; local in function:fpu_shr
76 m0 = fp->fp_mant[0];
83 KASSERT((m0 | m1 | m2 | m3) != 0);
89 if ((m0 | m1 | m2 | m3) == 0)
101 m3 = m0, m2 = 0, m1 = 0, m0 = 0;
104 m3 = m1, m2 = m0, m1 = 0, m0 = 0;
107 m3 = m2, m2 = m1, m1 = m0, m0 = 0
139 u_int m0, m1, m2, m3, top, sup, nrm; local in function:fpu_norm
[all...] |
| /src/sys/arch/sparc/fpu/ |
| fpu_subr.c | 71 u_int m0, m1, m2, m3, s; local in function:fpu_shr
79 m0 = fp->fp_mant[0];
87 if ((m0 | m1 | m2 | m3) == 0)
95 if ((m0 | m1 | m2 | m3) == 0)
107 m3 = m0, m2 = 0, m1 = 0, m0 = 0;
110 m3 = m1, m2 = m0, m1 = 0, m0 = 0;
113 m3 = m2, m2 = m1, m1 = m0, m0 = 0
145 u_int m0, m1, m2, m3, top, sup, nrm; local in function:fpu_norm
[all...] |
| /src/sys/arch/m68k/fpe/ |
| fpu_subr.c | 86 uint32_t m0, m1, m2, s; local in function:fpu_shr
94 m0 = fp->fp_mant[0];
101 if ((m0 | m1 | m2) == 0)
108 if ((m0 | m1 | m2) == 0)
120 m2 = m0, m1 = 0, m0 = 0;
123 m2 = m1, m1 = m0, m0 = 0;
131 m1 = (m1 >> rsh) | (m0 << lsh);
132 m0 >>= rsh
153 uint32_t m0, m1, m2, sup, nrm; local in function:fpu_norm
[all...] |
| fpu_fscale.c | 59 uint32_t m0, m1; local in function:fpu_emul_fscale
208 m0 = fpregs[regnum * 3 + 1];
217 m0 = m1 = 0xffffffff;
222 (exp == 0 && (m0 | m1) != 0)) {
231 m1 = m0 << (32 + exp) | m1 >> -exp;
232 m0 >>= -exp;
240 ++m0 == 0) {
241 m0 = 0x80000000;
251 ++m0 == 0) {
252 m0 = 0x80000000
[all...] |
| /src/sys/altq/ |
| altq_classq.h | 97 struct mbuf *m0; local in function:_addq
99 if ((m0 = qtail(q)) != NULL)
100 m->m_nextpkt = m0->m_nextpkt;
102 m0 = m;
103 m0->m_nextpkt = m;
111 struct mbuf *m, *m0; local in function:_getq
115 if ((m0 = m->m_nextpkt) != m)
116 m->m_nextpkt = m0->m_nextpkt;
120 m0->m_nextpkt = NULL;
121 return m0;
128 struct mbuf *m, *m0, *prev; local in function:_getq_tail
177 struct mbuf *m0, *prev; local in function:_removeq
[all...] |
| altq_subr.c | 639 struct mbuf *m0; local in function:read_dsfield
647 for (m0 = m; m0 != NULL; m0 = m0->m_next)
648 if (((char *)pktattr->pattr_hdr >= m0->m_data) &&
649 ((char *)pktattr->pattr_hdr < m0->m_data + m0->m_len))
651 if (m0 == NULL) {
684 struct mbuf *m0; local in function:write_dsfield
893 struct mbuf *m0; local in function:extract_ports4
988 struct mbuf *m0; local in function:extract_ports6
[all...] |
| /src/usr.sbin/npf/npftest/libnpftest/ |
| npf_nbuf_test.c | 109 struct mbuf *m0 = NULL, *m = NULL; local in function:mbuf_bytesize
115 m0 = mbuf_alloc_with_off(n & 0xf, 1);
118 memset(m0->m_data, 'a' + n, 1);
122 m0->m_next = m;
123 m = m0;
126 m0 = m_gethdr(M_WAITOK, MT_HEADER);
127 m0->m_pkthdr.len = clen;
128 m0->m_len = 0;
129 m0->m_next = m;
130 return m0;
139 struct mbuf *m0 = NULL, *m = NULL; local in function:mbuf_random_len
[all...] |
| npf_mbuf_subr.c | 61 const struct mbuf *m0; local in function:npfkern_m_length
66 for (m0 = m; m0 != NULL; m0 = m0->m_next)
67 pktlen += m0->m_len;
89 npfkern_m_ensure_contig(struct mbuf **m0, size_t len)
95 tlen = npfkern_m_length(*m0);
101 for (struct mbuf *m = *m0; m != NULL; m = m->m_next) {
105 npfkern_m_freem(*m0);
130 struct mbuf *m0, *m1; local in function:mbuf_construct_ether
310 struct mbuf *m0; local in function:mbuf_get_frame
[all...] |
| /src/sys/netipsec/ |
| ipsec_mbuf.c | 56 m_clone(struct mbuf *m0)
62 KASSERT(m0 != NULL);
65 for (m = m0; m != NULL; m = mprev->m_next) {
116 m_freem(m0);
123 m_freem(m0);
129 m_freem(m0);
163 m_freem(m0);
169 m0 = mfirst; /* new head of chain */
176 return m0;
188 m_makespace(struct mbuf *m0, int skip, int hlen, int *off
296 register struct mbuf *m0, *m1; local in function:m_pad
[all...] |
| /src/sys/net/ |
| if_ieee1394subr.c | 85 ieee1394_output(struct ifnet *ifp, struct mbuf *m0, const struct sockaddr *dst,
107 IFQ_CLASSIFY(&ifp->if_snd, m0, dst->sa_family);
118 unicast = !(m0->m_flags & (M_BCAST | M_MCAST));
120 mtag = m_tag_find(m0, MTAG_FIREWIRE_HWADDR);
128 m_tag_prepend(m0, mtag);
139 (error = arpresolve(ifp, rt, m0, dst, hwdst,
143 if ((m0->m_flags & M_BCAST) && (ifp->if_flags & IFF_SIMPLEX))
144 mcopy = m_copypacket(m0, M_DONTWAIT);
148 ah = mtod(m0, struct arphdr *);
161 if (m0->m_flags & M_BCAST
[all...] |
| /src/sys/dev/pci/cxgb/ |
| cxgb_osdep.c | 115 struct mbuf *m0, *head = NULL; local in function:_m_explode
120 m0 = m->m_next;
121 while (m0) {
122 KASSERT((m0->m_flags & M_PKTHDR) == 0,
124 len += m0->m_len;
125 m0 = m0->m_next;
140 m0 = (struct mbuf *)cl;
141 KASSERT((m0->m_flags & M_EXT) == 0);
142 m0->m_len = len
[all...] |
| /src/sys/external/bsd/drm2/dist/drm/amd/amdkfd/ |
| cwsr_trap_handler_gfx10.asm | 284 s_mov_b32 s_save_m0, m0
342 s_mov_b32 m0, 0x0 //SGPR initial index value =0
346 s_movrels_b64 s0, s0 //s0 = s[0+m0], s1 = s[1+m0]
347 s_movrels_b64 s2, s2 //s2 = s[2+m0], s3 = s[3+m0]
348 s_movrels_b64 s4, s4 //s4 = s[4+m0], s5 = s[5+m0]
349 s_movrels_b64 s6, s6 //s6 = s[6+m0], s7 = s[7+m0]
[all...] |
| cwsr_trap_handler_gfx9.asm | 349 s_mov_b32 s_save_m0, m0 //save M0
371 write_hwreg_to_mem(s_save_m0, s_save_buf_rsrc0, s_save_mem_offset) //M0
420 s_mov_b32 m0, 0x0 //SGPR initial index value =0
424 s_movrels_b64 s0, s0 //s0 = s[0+m0], s1 = s[1+m0]
425 s_movrels_b64 s2, s2 //s2 = s[2+m0], s3 = s[3+m0]
426 s_movrels_b64 s4, s4 //s4 = s[4+m0], s5 = s[5+m0]
[all...] |
| cwsr_trap_handler_gfx8.asm | 244 s_mov_b32 s_save_m0, m0 //save M0
266 write_hwreg_to_mem(s_save_m0, s_save_buf_rsrc0, s_save_mem_offset) //M0
317 s_mov_b32 m0, 0x0 //SGPR initial index value =0
320 s_movrels_b64 s0, s0 //s0 = s[0+m0], s1 = s[1+m0]
321 s_movrels_b64 s2, s2 //s2 = s[2+m0], s3 = s[3+m0]
322 s_movrels_b64 s4, s4 //s4 = s[4+m0], s5 = s[5+m0]
[all...] |
| /src/sys/crypto/aes/ |
| aes_ccm_mbuf.c | 65 aes_ccm_dec_mbuf(struct aes_ccm *C, struct mbuf *m0, size_t off0, size_t len0,
73 while (off0 >= m0->m_len) {
74 KASSERT(m0->m_next);
75 m0 = m0->m_next;
76 off0 -= m0->m_len;
79 for (m = m0, off = off0, len = len0;
95 for (m = m0, off = off0, len = len0;
|
| /src/sys/external/isc/libsodium/dist/src/libsodium/crypto_generichash/blake2b/ref/ |
| blake2b-load-sse41.h | 21 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...] |
| blake2b-load-avx2.h | 6 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...] |
| 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...] |
| /src/sys/arch/riscv/include/ |
| byte_swap.h | 66 const uint64_t m0 = 0x00ff00ff00ff00ffull; local in function:__byte_swap_u64_variable
70 v = ((v >> 8) & m0) | ((v & m0) << 8);
|
| /src/sys/external/isc/libsodium/dist/src/libsodium/randombytes/salsa20/ |
| randombytes_salsa20_random.c | 332 unsigned char m0[crypto_stream_salsa20_KEYBYTES + local in function:randombytes_salsa20_random_stir
348 arc4random_buf(m0, sizeof m0);
351 if (randombytes_linux_getrandom(m0, sizeof m0) != 0) {
355 safe_read(global.random_data_source_fd, m0,
356 sizeof m0) != (ssize_t) sizeof m0) {
361 safe_read(global.random_data_source_fd, m0,
362 sizeof m0) != (ssize_t) sizeof m0)
[all...] |
| /src/sys/netbt/ |
| hci_misc.c | 117 struct hci_memo *memo, *m0; local in function:hci_memo_find
122 m0 = LIST_FIRST(&unit->hci_memos);
123 while ((memo = m0) != NULL) {
124 m0 = LIST_NEXT(memo, next);
|
| /src/lib/libc/citrus/modules/ |
| citrus_viqr.c | 172 mnemonic_t *m0; local in function:mnemonic_append_child
180 m0 = mnemonic_list_find(&m->child, ch);
181 if (m0 == NULL) {
182 m0 = mnemonic_create(m, ch, (wchar_t)ch);
183 if (m0 == NULL)
185 TAILQ_INSERT_TAIL(&m->child, m0, entry);
187 m = m0;
188 for (m0 = NULL; (ch = (unsigned char)*s) != '\0'; ++s) {
189 m0 = mnemonic_list_find(&m->child, ch);
190 if (m0 == NULL)
208 mnemonic_t *m0; local in function:mnemonic_destroy
298 mnemonic_t *m, *m0; local in function:_citrus_VIQR_mbrtowc_priv
[all...] |
| /src/sys/arch/evbmips/isa/ |
| isadma_bounce.c | 226 struct mbuf *m0, int flags)
238 if ((m0->m_flags & M_PKTHDR) == 0)
242 if (m0->m_pkthdr.len > map->_dm_size)
249 error = _bus_dmamap_load_mbuf(t, map, m0, flags);
261 error = isadma_bounce_alloc_bouncebuf(t, map, m0->m_pkthdr.len,
271 cookie->id_origbuf = m0;
272 cookie->id_origbuflen = m0->m_pkthdr.len; /* not really used */
275 m0->m_pkthdr.len, NULL, flags);
415 struct mbuf *m, *m0 = cookie->id_origbuf; local in function:isadma_bounce_dmamap_sync
426 m_copydata(m0, offset, len
[all...] |
| /src/sys/kern/ |
| uipc_socket2.c | 822 #define SBLINKRECORDCHAIN(sb, m0, mlast) \
825 (sb)->sb_lastrecord->m_nextpkt = (m0); \
827 (sb)->sb_mb = (m0); \
832 #define SBLINKRECORD(sb, m0) \
833 SBLINKRECORDCHAIN(sb, m0, m0)
939 sbappendrecord(struct sockbuf *sb, struct mbuf *m0)
945 if (m0 == NULL)
949 m_claimm(m0, sb->sb_mowner);
955 sballoc(sb, m0);
[all...] |
| /src/lib/libutil/ |
| getmntopts.c | 123 getmntopts(const char *options, const struct mntopt *m0, int *flagp,
133 for (nopts = 0, m = m0; m->m_option != NULL; ++m, nopts++)
151 mp->mopts = m0;
172 for (m = m0; m->m_option != NULL; ++m)
178 mp->optarg[m - m0] = p;
|
