| /netbsd-src/sys/arch/powerpc/fpu/ |
| H A D | fpu_subr.c | 70 u_int m0, m1, m2, m3, s; in fpu_shr() local
77 m1 = fp->fp_mant[1]; in fpu_shr()
83 KASSERT((m0 | m1 | m2 | m3) != 0); in fpu_shr()
89 if ((m0 | m1 | m2 | m3) == 0) in fpu_shr()
100 s |= m3 | m2 | m1; in fpu_shr()
101 m3 = m0, m2 = 0, m1 = 0, m0 = 0; in fpu_shr()
104 m3 = m1, m2 = m0, m1 = 0, m0 = 0; in fpu_shr()
107 m3 = m2, m2 = m1, m1 = m0, m0 = 0; in fpu_shr()
115 m2 = (m2 >> rsh) | (m1 << lsh); in fpu_shr()
116 m1 = (m1 >> rsh) | (m0 << lsh); in fpu_shr()
[all …]
|
| /netbsd-src/sys/arch/sparc/fpu/ |
| H A D | fpu_subr.c | 71 u_int m0, m1, m2, m3, s; in fpu_shr() local
80 m1 = fp->fp_mant[1]; in fpu_shr()
87 if ((m0 | m1 | m2 | m3) == 0) in fpu_shr()
95 if ((m0 | m1 | m2 | m3) == 0) in fpu_shr()
106 s |= m3 | m2 | m1; in fpu_shr()
107 m3 = m0, m2 = 0, m1 = 0, m0 = 0; in fpu_shr()
110 m3 = m1, m2 = m0, m1 = 0, m0 = 0; in fpu_shr()
113 m3 = m2, m2 = m1, m1 = m0, m0 = 0; in fpu_shr()
121 m2 = (m2 >> rsh) | (m1 << lsh); in fpu_shr()
122 m1 = (m1 >> rsh) | (m0 << lsh); in fpu_shr()
[all …]
|
| /netbsd-src/external/gpl3/gcc.old/dist/libgcc/config/visium/ |
| H A D | memcpy.c | 35 m1 = in [1]; \
39 out [1] = m1; \
44 m1 = in [5]; \
48 out [5] = m1; \
53 m1 = in [9]; \
57 out [9] = m1; \
62 m1 = in [13]; \
66 out [13] = m1; \
71 m1 = in [17]; \
75 out [17] = m1; \
[all …]
|
| /netbsd-src/external/gpl3/gcc/dist/libgcc/config/visium/ |
| H A D | memcpy.c | 35 m1 = in [1]; \
39 out [1] = m1; \
44 m1 = in [5]; \
48 out [5] = m1; \
53 m1 = in [9]; \
57 out [9] = m1; \
62 m1 = in [13]; \
66 out [13] = m1; \
71 m1 = in [17]; \
75 out [17] = m1; \
[all …]
|
| /netbsd-src/sys/arch/m68k/fpe/ |
| H A D | fpu_subr.c | 86 uint32_t m0, m1, m2, s; in fpu_shr() local
95 m1 = fp->fp_mant[1]; in fpu_shr()
101 if ((m0 | m1 | m2) == 0) in fpu_shr()
108 if ((m0 | m1 | m2) == 0) in fpu_shr()
119 s |= m2 | m1; in fpu_shr()
120 m2 = m0, m1 = 0, m0 = 0; in fpu_shr()
123 m2 = m1, m1 = m0, m0 = 0; in fpu_shr()
130 m2 = (m2 >> rsh) | (m1 << lsh); in fpu_shr()
131 m1 = (m1 >> rsh) | (m0 << lsh); in fpu_shr()
135 fp->fp_mant[1] = m1; in fpu_shr()
[all …]
|
| H A D | fpu_fscale.c | 59 uint32_t m0, m1; in fpu_emul_fscale()
209 m1 = fpregs[regnum * 3 + 2]; in fpu_emul_fscale()
217 m0 = m1 = 0xffffffff; in fpu_emul_fscale()
222 (exp == 0 && (m0 | m1) != 0)) { in fpu_emul_fscale()
230 grs = m1 << (32 + exp); in fpu_emul_fscale()
231 m1 = m0 << (32 + exp) | m1 >> -exp; in fpu_emul_fscale()
239 if (++m1 == 0 && in fpu_emul_fscale()
249 if ((m1 & 1) && in fpu_emul_fscale()
250 ++m1 in fpu_emul_fscale()
58 uint32_t m0, m1; fpu_emul_fscale() local
[all...] |
| /netbsd-src/sys/netipsec/ |
| H A D | ipsec_mbuf.c | 296 register struct mbuf *m0, *m1; in m_pad() local
325 for (m1 = m0; m1->m_next; m1 = m1->m_next) { in m_pad()
326 if (m1->m_next->m_len != 0) { in m_pad()
330 m->m_pkthdr.len + m1->m_next->m_len); in m_pad()
335 m0 = m1->m_next; in m_pad()
340 MGET(m1, M_DONTWAIT, MT_DATA); in m_pad()
341 if (m1 == NULL) { in m_pad()
347 m0->m_next = m1; in m_pad()
348 m0 = m1; in m_pad()
367 struct mbuf *m1; in m_striphdr() local
[all …]
|
| /netbsd-src/crypto/external/bsd/openssl/dist/test/testutil/ |
| H A D | format_output.c | 42 const char *op, const char *m1, size_t l1, in test_fail_string_common() argument
53 if (m1 == NULL) in test_fail_string_common()
58 if ((m1 == NULL) == (m2 == NULL)) { in test_fail_string_common()
59 test_string_null_empty(m1, ' '); in test_fail_string_common()
62 test_string_null_empty(m1, '-'); in test_fail_string_common()
68 if (l1 != l2 || strncmp(m1, m2, l1) != 0) in test_fail_string_common()
76 b1[i] = isprint((unsigned char)m1[i]) ? m1[i] : '.'; in test_fail_string_common()
89 if (m1[i] == m2[i]) { in test_fail_string_common()
100 if (cnt == 0 && (m1 == NULL || *m1 == '\0')) in test_fail_string_common()
101 test_string_null_empty(m1, '-'); in test_fail_string_common()
[all …]
|
| /netbsd-src/crypto/external/bsd/openssl.old/dist/test/testutil/ |
| H A D | format_output.c | 42 const char *op, const char *m1, size_t l1, in test_fail_string_common() argument
52 if (m1 == NULL) in test_fail_string_common()
57 if ((m1 == NULL) == (m2 == NULL)) { in test_fail_string_common()
58 test_string_null_empty(m1, ' '); in test_fail_string_common()
61 test_string_null_empty(m1, '-'); in test_fail_string_common()
67 if (l1 != l2 || strcmp(m1, m2) != 0) in test_fail_string_common()
75 b1[i] = isprint((unsigned char)m1[i]) ? m1[i] : '.'; in test_fail_string_common()
88 if (m1[i] == m2[i]) { in test_fail_string_common()
99 if (cnt == 0 && (m1 == NULL || *m1 == '\0')) in test_fail_string_common()
100 test_string_null_empty(m1, '-'); in test_fail_string_common()
[all …]
|
| /netbsd-src/external/gpl3/gcc/dist/libphobos/libdruntime/rt/ |
| H A D | minfo.d | 956 auto m1 = mockMI(0); variable
958 checkExp("no ctors", false, [&m0.mi, &m1.mi, &m2.mi]);
963 auto m1 = mockMI(0); variable
965 auto mgroup = ModuleGroup([&m0.mi, &m1.mi, &m2.mi]);
966 checkExp("independent ctors", false, [&m0.mi, &m1.mi, &m2.mi]);
971 auto m1 = mockMI(0); variable
973 auto mgroup = ModuleGroup([&m0.mi, &m1.mi, &m2.mi]);
974 checkExp("standalone ctor", false, [&m0.mi, &m1.mi, &m2.mi], [&m0.mi]);
979 auto m1 = mockMI(MIstandalone | MIctor); variable
981 m1.setImports(&m0.mi);
[all …]
|
| /netbsd-src/external/gpl3/gcc.old/dist/libphobos/libdruntime/rt/ |
| H A D | minfo.d | 956 auto m1 = mockMI(0); variable
958 checkExp("no ctors", false, [&m0.mi, &m1.mi, &m2.mi]);
963 auto m1 = mockMI(0); variable
965 auto mgroup = ModuleGroup([&m0.mi, &m1.mi, &m2.mi]);
966 checkExp("independent ctors", false, [&m0.mi, &m1.mi, &m2.mi]);
971 auto m1 = mockMI(0); variable
973 auto mgroup = ModuleGroup([&m0.mi, &m1.mi, &m2.mi]);
974 checkExp("standalone ctor", false, [&m0.mi, &m1.mi, &m2.mi], [&m0.mi]);
979 auto m1 = mockMI(MIstandalone | MIctor); variable
981 m1.setImports(&m0.mi);
[all …]
|
| /netbsd-src/external/apache2/llvm/dist/clang/lib/Headers/ppc_wrappers/ |
| H A D | mmintrin.h | 237 __m64_union m1, m2, res; in _mm_unpackhi_pi8()
239 m1.as_m64 = __m1; in _mm_unpackhi_pi8()
242 res.as_char[0] = m1.as_char[4]; in _mm_unpackhi_pi8()
244 res.as_char[2] = m1.as_char[5]; in _mm_unpackhi_pi8()
246 res.as_char[4] = m1.as_char[6]; in _mm_unpackhi_pi8()
248 res.as_char[6] = m1.as_char[7]; in _mm_unpackhi_pi8()
266 __m64_union m1, m2, res; in _mm_unpackhi_pi16() local
268 m1.as_m64 = __m1; in _mm_unpackhi_pi16()
271 res.as_short[0] = m1.as_short[2]; in _mm_unpackhi_pi16()
273 res.as_short[2] = m1.as_short[3]; in _mm_unpackhi_pi16()
[all …]
|
| /netbsd-src/sys/external/isc/libsodium/dist/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); \
63 b0 = _mm_unpacklo_epi64(m6, m1); \
64 b1 = _mm_unpackhi_epi64(m3, m1); \
76 b1 = _mm_blend_epi16(m1, m6, 0xF0); \
81 b0 = _mm_blend_epi16(m5, m1, 0xF0); \
93 b0 = _mm_unpackhi_epi64(m3, m1); \
105 b0 = _mm_blend_epi16(m1, m2, 0xF0); \
118 b1 = _mm_unpacklo_epi64(m1, m5); \
130 b1 = _mm_blend_epi16(m3, m1, 0xF0); \
[all …]
|
| H A D | blake2b-load-avx2.h | 6 t0 = _mm256_unpacklo_epi64(m0, m1); \
13 t0 = _mm256_unpackhi_epi64(m0, m1); \
55 t0 = _mm256_unpacklo_epi64(m6, m1); \
56 t1 = _mm256_unpackhi_epi64(m3, m1); \
70 t1 = _mm256_blend_epi32(m6, m1, 0x33); \
76 t0 = _mm256_blend_epi32(m1, m5, 0x33); \
90 t0 = _mm256_unpackhi_epi64(m3, m1); \
104 t0 = _mm256_blend_epi32(m2, m1, 0x33); \
119 t1 = _mm256_unpacklo_epi64(m1, m5); \
133 t1 = _mm256_blend_epi32(m1, m3, 0x33); \
[all …]
|
| /netbsd-src/crypto/external/bsd/openssl/dist/crypto/bn/asm/ |
| H A D | vis3-mont.pl | 47 ($n0,$m0,$m1,$lo0,$hi0, $lo1,$hi1,$aj,$alo,$nj,$nlo,$tj)=
133 mulx $lo0, $n0, $m1 ! "tp[0]"*n0
139 mulx $nj, $m1, $lo1 ! np[0]*m1
140 umulxhi $nj, $m1, $hi1
150 mulx $nj, $m1, $nlo ! np[1]*m1
151 umulxhi $nj, $m1, $nj ! nhi=nj
181 mulx $nj, $m1, $nlo ! np[j]*m1
182 addcc $lo0, $lo1, $lo1 ! np[j]*m1+ap[j]*bp[0]
183 umulxhi $nj, $m1, $nj ! nhi=nj
196 addcc $lo0, $lo1, $lo1 ! np[j]*m1+ap[j]*bp[0]
[all …]
|
| H A D | x86_64-mont.pl | 98 $m1="%rbp";
187 mov $n0,$m1
192 imulq $lo0,$m1 # "tp[0]"*n0
195 mulq $m1 # np[0]*m1
209 add $hi0,$hi1 # np[j]*m1+ap[j]*bp[0]
223 mulq $m1 # np[j]*m1
230 add $hi0,$hi1 # np[j]*m1+ap[j]*bp[0]
248 mov $n0,$m1
255 imulq $lo0,$m1 # tp[0]*n0
258 mulq $m1 # np[0]*m1
[all …]
|
| H A D | sparct4-mont.pl | 671 ($n0,$m0,$m1,$lo0,$hi0, $lo1,$hi1,$aj,$alo,$nj,$nlo,$tj)=
726 mulx $lo0, $n0, $m1 ! "tp[0]"*n0
731 mulx $nj, $m1, $lo1 ! np[0]*m1
732 umulxhi $nj, $m1, $hi1
740 mulx $nj, $m1, $nlo ! np[1]*m1
741 umulxhi $nj, $m1, $nj ! nhi=nj
761 mulx $nj, $m1, $nlo ! np[j]*m1
762 addcc $lo0, $lo1, $lo1 ! np[j]*m1+ap[j]*bp[0]
763 umulxhi $nj, $m1, $nj ! nhi=nj
776 addcc $lo0, $lo1, $lo1 ! np[j]*m1+ap[j]*bp[0]
[all …]
|
| H A D | alpha-mont.pl | 50 $m1="s5";
101 mulq $lo0,$n0,$m1
103 mulq $hi1,$m1,$lo1
104 umulh $hi1,$m1,$hi1
115 mulq $nj,$m1,$nlo
117 umulh $nj,$m1,$nhi
132 mulq $nj,$m1,$nlo
142 umulh $nj,$m1,$nhi
189 mulq $lo0,$n0,$m1
191 mulq $hi1,$m1,$lo1
[all …]
|
| /netbsd-src/crypto/external/bsd/openssl.old/dist/crypto/bn/asm/ |
| H A D | vis3-mont.pl | 45 ($n0,$m0,$m1,$lo0,$hi0, $lo1,$hi1,$aj,$alo,$nj,$nlo,$tj)=
131 mulx $lo0, $n0, $m1 ! "tp[0]"*n0
137 mulx $nj, $m1, $lo1 ! np[0]*m1
138 umulxhi $nj, $m1, $hi1
148 mulx $nj, $m1, $nlo ! np[1]*m1
149 umulxhi $nj, $m1, $nj ! nhi=nj
179 mulx $nj, $m1, $nlo ! np[j]*m1
180 addcc $lo0, $lo1, $lo1 ! np[j]*m1+ap[j]*bp[0]
181 umulxhi $nj, $m1, $nj ! nhi=nj
194 addcc $lo0, $lo1, $lo1 ! np[j]*m1+ap[j]*bp[0]
[all …]
|
| H A D | x86_64-mont.pl | 96 $m1="%rbp";
185 mov $n0,$m1
190 imulq $lo0,$m1 # "tp[0]"*n0
193 mulq $m1 # np[0]*m1
207 add $hi0,$hi1 # np[j]*m1+ap[j]*bp[0]
221 mulq $m1 # np[j]*m1
228 add $hi0,$hi1 # np[j]*m1+ap[j]*bp[0]
246 mov $n0,$m1
253 imulq $lo0,$m1 # tp[0]*n0
256 mulq $m1 # np[0]*m1
[all …]
|
| H A D | sparct4-mont.pl | 669 ($n0,$m0,$m1,$lo0,$hi0, $lo1,$hi1,$aj,$alo,$nj,$nlo,$tj)=
724 mulx $lo0, $n0, $m1 ! "tp[0]"*n0
729 mulx $nj, $m1, $lo1 ! np[0]*m1
730 umulxhi $nj, $m1, $hi1
738 mulx $nj, $m1, $nlo ! np[1]*m1
739 umulxhi $nj, $m1, $nj ! nhi=nj
759 mulx $nj, $m1, $nlo ! np[j]*m1
760 addcc $lo0, $lo1, $lo1 ! np[j]*m1+ap[j]*bp[0]
761 umulxhi $nj, $m1, $nj ! nhi=nj
774 addcc $lo0, $lo1, $lo1 ! np[j]*m1+ap[j]*bp[0]
[all …]
|
| H A D | alpha-mont.pl | 51 $m1="s5";
102 mulq $lo0,$n0,$m1
104 mulq $hi1,$m1,$lo1
105 umulh $hi1,$m1,$hi1
116 mulq $nj,$m1,$nlo
118 umulh $nj,$m1,$nhi
133 mulq $nj,$m1,$nlo
143 umulh $nj,$m1,$nhi
190 mulq $lo0,$n0,$m1
192 mulq $hi1,$m1,$lo1
[all …]
|
| /netbsd-src/crypto/external/bsd/openssl.old/lib/libdes/ |
| H A D | oede_cbcm_enc.c | 80 register DES_LONG tout0,tout1,xor0,xor1,m0,m1; in des_ede3_cbcm_encrypt() local
91 c2l(iv1,m1); in des_ede3_cbcm_encrypt()
97 tin[1]=m1; in des_ede3_cbcm_encrypt()
100 m1=tin[1]; in des_ede3_cbcm_encrypt()
118 tin[1]^=m1; in des_ede3_cbcm_encrypt()
121 tin[1]^=m1; in des_ede3_cbcm_encrypt()
131 l2c(m1,iv1); in des_ede3_cbcm_encrypt()
142 c2l(iv1,m1); in des_ede3_cbcm_encrypt()
148 tin[1]=m1; in des_ede3_cbcm_encrypt()
151 m1=tin[1]; in des_ede3_cbcm_encrypt()
[all …]
|
| /netbsd-src/crypto/external/bsd/openssl/lib/libdes/ |
| H A D | oede_cbcm_enc.c | 80 register DES_LONG tout0,tout1,xor0,xor1,m0,m1; in des_ede3_cbcm_encrypt() local
91 c2l(iv1,m1); in des_ede3_cbcm_encrypt()
97 tin[1]=m1; in des_ede3_cbcm_encrypt()
100 m1=tin[1]; in des_ede3_cbcm_encrypt()
118 tin[1]^=m1; in des_ede3_cbcm_encrypt()
121 tin[1]^=m1; in des_ede3_cbcm_encrypt()
131 l2c(m1,iv1); in des_ede3_cbcm_encrypt()
142 c2l(iv1,m1); in des_ede3_cbcm_encrypt()
148 tin[1]=m1; in des_ede3_cbcm_encrypt()
151 m1=tin[1]; in des_ede3_cbcm_encrypt()
[all …]
|
| /netbsd-src/external/gpl3/gdb/dist/sim/testsuite/sh/ |
| H A D | pswap.s | 18 pcopy y1, m1
33 assert_sreg2 0xa5a5a5a5, m1
44 pcopy y1, m1
59 assert_sreg2 0xa5a5a5a5, m1
70 pcopy y1, m1
86 assert_sreg2 0xa5a5a5a5, m1
97 pcopy y1, m1
101 pcopy a0, m1
102 pswap m1, y0
108 assert_sreg2 0xa5a57777, m1
[all …]
|