Home
last modified time | relevance | path

Searched refs:m3 (Results 1 – 25 of 72) sorted by relevance

123

/freebsd/sys/powerpc/fpu/
H A Dfpu_subr.c64 u_int m0, m1, m2, m3, s; in fpu_shr() local
75 m3 = fp->fp_mant[3]; in fpu_shr()
80 if ((m0 | m1 | m2 | m3) == 0) in fpu_shr()
88 if ((m0 | m1 | m2 | m3) == 0) in fpu_shr()
99 s |= m3 | m2 | m1; in fpu_shr()
100 m3 = m0, m2 = 0, m1 = 0, m0 = 0; in fpu_shr()
102 s |= m3 | m2; in fpu_shr()
103 m3 = m1, m2 = m0, m1 = 0, m0 = 0; in fpu_shr()
105 s |= m3; in fpu_shr()
106 m3 = m2, m2 = m1, m1 = m0, m0 = 0; in fpu_shr()
[all …]
H A Dfpu_implode.c78 u_int m0, m1, m2, m3; in round() local
85 m3 = fp->fp_mant[3]; in round()
86 gr = m3 & 3; in round()
90 m3 = (m3 >> FP_NG) | (m2 << (32 - FP_NG)); in round()
111 if ((gr & 1) || fp->fp_sticky || (m3 & 1)) in round()
135 FPU_ADDS(m3, m3, 1); in round()
142 fp->fp_mant[3] = m3; in round()
149 fp->fp_mant[3] = m3; in round()
/freebsd/sys/contrib/libb2/
H A Dblake2s-load-sse41.h24 buf = TOI(_mm_shuffle_ps(TOF(m2), TOF(m3), _MM_SHUFFLE(2,0,2,0)));
27 buf = TOI(_mm_shuffle_ps(TOF(m2), TOF(m3), _MM_SHUFFLE(3,1,3,1)));
31 t1 = _mm_slli_si128(m3, 4); \
37 t1 = _mm_blend_epi16(m1,m3,0xC0); \
49 t1 = _mm_slli_si128(m3, 4); \
54 t0 = _mm_unpackhi_epi32(m2,m3); \
55 t1 = _mm_blend_epi16(m3,m1,0x0C); \
62 t2 = _mm_slli_si128(m3, 8); \
72 t0 = _mm_slli_si128(m3, 4); \
80 t2 = _mm_blend_epi16(t1, m3, 0x0C); \
[all …]
H A Dblake2b-load-sse41.h21 b1 = _mm_unpacklo_epi64(m2, m3); \
29 b1 = _mm_unpackhi_epi64(m2, m3); \
61 b1 = _mm_alignr_epi8(m3, m7, 8); \
77 b1 = _mm_unpackhi_epi64(m3, m1); \
101 b1 = _mm_unpackhi_epi64(m3, m4); \
108 b0 = _mm_unpacklo_epi64(m7, m3); \
116 b0 = _mm_unpackhi_epi64(m3, m1); \
140 b0 = _mm_unpacklo_epi64(m3, m5); \
156 b0 = _mm_blend_epi16(m0, m3, 0xF0); \
165 b1 = _mm_blend_epi16(m3, m1, 0xF0); \
[all …]
H A Dblake2s-load-xop.h37 buf = _mm_perm_epi8(m2, m3, _mm_set_epi32(TOB(6),TOB(4),TOB(2),TOB(0)) );
40 buf = _mm_perm_epi8(m2, m3, _mm_set_epi32(TOB(7),TOB(5),TOB(3),TOB(1)) );
44 buf = _mm_perm_epi8(t0, m3, _mm_set_epi32(TOB(5),TOB(2),TOB(1),TOB(6)) );
48 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(3),TOB(7),TOB(1),TOB(0)) );
56 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(3),TOB(2),TOB(1),TOB(4)) );
60 buf = _mm_perm_epi8(t0, m3, _mm_set_epi32(TOB(7),TOB(2),TOB(4),TOB(0)) );
64 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(5),TOB(2),TOB(1),TOB(0)) );
72 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(3),TOB(2),TOB(1),TOB(6)) );
77 buf = _mm_perm_epi8(t0, m3, _mm_set_epi32(TOB(3),TOB(5),TOB(1),TOB(0)) );
81 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(6),TOB(4),TOB(1),TOB(0)) );
[all …]
H A Dblake2s-load-sse2.h18 #define LOAD_MSG_0_2(buf) buf = _mm_set_epi32(m7,m5,m3,m1)
24 #define LOAD_MSG_1_4(buf) buf = _mm_set_epi32(m3,m7,m2,m12)
27 #define LOAD_MSG_2_3(buf) buf = _mm_set_epi32(m9,m7,m3,m10)
29 #define LOAD_MSG_3_1(buf) buf = _mm_set_epi32(m11,m13,m3,m7)
35 #define LOAD_MSG_4_3(buf) buf = _mm_set_epi32(m3,m6,m11,m14)
38 #define LOAD_MSG_5_2(buf) buf = _mm_set_epi32(m3,m11,m10,m12)
44 #define LOAD_MSG_6_4(buf) buf = _mm_set_epi32(m11,m2,m3,m7)
45 #define LOAD_MSG_7_1(buf) buf = _mm_set_epi32(m3,m12,m7,m13)
50 #define LOAD_MSG_8_2(buf) buf = _mm_set_epi32(m8,m3,m9,m15)
55 #define LOAD_MSG_9_3(buf) buf = _mm_set_epi32(m13,m3,m9,m15)
H A Dblake2b-load-sse2.h18 #define LOAD_MSG_0_2(b0, b1) b0 = _mm_set_epi64x(m3, m1); b1 = _mm_set_epi64x(m7, m5)
24 #define LOAD_MSG_1_4(b0, b1) b0 = _mm_set_epi64x(m2, m12); b1 = _mm_set_epi64x(m3, m7)
27 #define LOAD_MSG_2_3(b0, b1) b0 = _mm_set_epi64x(m3, m10); b1 = _mm_set_epi64x(m9, m7)
29 #define LOAD_MSG_3_1(b0, b1) b0 = _mm_set_epi64x(m3, m7); b1 = _mm_set_epi64x(m11, m13)
35 #define LOAD_MSG_4_3(b0, b1) b0 = _mm_set_epi64x(m11, m14); b1 = _mm_set_epi64x(m3, m6)
38 #define LOAD_MSG_5_2(b0, b1) b0 = _mm_set_epi64x(m10, m12); b1 = _mm_set_epi64x(m3, m11)
44 #define LOAD_MSG_6_4(b0, b1) b0 = _mm_set_epi64x(m3, m7); b1 = _mm_set_epi64x(m11, m2)
45 #define LOAD_MSG_7_1(b0, b1) b0 = _mm_set_epi64x(m7, m13); b1 = _mm_set_epi64x(m3, m12)
50 #define LOAD_MSG_8_2(b0, b1) b0 = _mm_set_epi64x(m9, m15); b1 = _mm_set_epi64x(m8, m3)
55 #define LOAD_MSG_9_3(b0, b1) b0 = _mm_set_epi64x(m9, m15); b1 = _mm_set_epi64x(m13, m3)
[all …]
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-load-sse41.h22 b1 = _mm_unpacklo_epi64(m2, m3); \
28 b1 = _mm_unpackhi_epi64(m2, m3); \
52 b1 = _mm_alignr_epi8(m3, m7, 8); \
64 b1 = _mm_unpackhi_epi64(m3, m1); \
82 b1 = _mm_unpackhi_epi64(m3, m4); \
87 b0 = _mm_unpacklo_epi64(m7, m3); \
93 b0 = _mm_unpackhi_epi64(m3, m1); \
111 b0 = _mm_unpacklo_epi64(m3, m5); \
123 b0 = _mm_blend_epi16(m0, m3, 0xF0); \
130 b1 = _mm_blend_epi16(m3, m1, 0xF0); \
[all …]
H A Dblake2b-load-avx2.h7 t1 = _mm256_unpacklo_epi64(m2, m3); \
14 t1 = _mm256_unpackhi_epi64(m2, m3); \
42 t1 = _mm256_alignr_epi8(m3, m7, 8); \
56 t1 = _mm256_unpackhi_epi64(m3, m1); \
77 t1 = _mm256_unpackhi_epi64(m3, m4); \
83 t0 = _mm256_unpacklo_epi64(m7, m3); \
90 t0 = _mm256_unpackhi_epi64(m3, m1); \
111 t0 = _mm256_unpacklo_epi64(m3, m5); \
125 t0 = _mm256_blend_epi32(m3, m0, 0x33); \
133 t1 = _mm256_blend_epi32(m1, m3, 0x33); \
[all …]
H A Dblake2b-load-sse2.h23 b0 = _mm_set_epi64x(m3, m1); \
42 b1 = _mm_set_epi64x(m3, m7)
50 b0 = _mm_set_epi64x(m3, m10); \
56 b0 = _mm_set_epi64x(m3, m7); \
75 b1 = _mm_set_epi64x(m3, m6)
84 b1 = _mm_set_epi64x(m3, m11)
101 b0 = _mm_set_epi64x(m3, m7); \
105 b1 = _mm_set_epi64x(m3, m12)
120 b1 = _mm_set_epi64x(m8, m3)
135 b1 = _mm_set_epi64x(m13, m3)
[all …]
/freebsd/contrib/bearssl/src/rsa/
H A Drsa_i15_keygen.c230 uint32_t m3, m5, m7, m11; in mkprime() local
257 m3 = 0; in mkprime()
265 m3 += w << (u & 1); in mkprime()
266 m3 = (m3 & 0xFF) + (m3 >> 8); in mkprime()
284 m3 = (m3 & 0x0F) + (m3 >> 4); /* max: 46 */ in mkprime()
285 m3 = (m3 & 0x0F) + (m3 >> 4); /* max: 16 */ in mkprime()
286 m3 = ((m3 * 43) >> 5) & 3; in mkprime()
317 if (m3 == 0 || m5 == 0 || m7 == 0 || m11 == 0) { in mkprime()
320 if ((pubexp == 3 && m3 == 1) in mkprime()
H A Drsa_i31_keygen_inner.c244 uint32_t m3, m5, m7, m11; in mkprime() local
271 m3 = 0; in mkprime()
286 m3 += w3 << (u & 1); in mkprime()
287 m3 = (m3 & 0xFF) + (m3 >> 8); /* max: 1025 */ in mkprime()
305 m3 = (m3 & 0x3F) + (m3 >> 6); /* max: 78 */ in mkprime()
306 m3 = (m3 & 0x0F) + (m3 >> 4); /* max: 18 */ in mkprime()
307 m3 = ((m3 * 43) >> 5) & 3; in mkprime()
339 if (m3 == 0 || m5 == 0 || m7 == 0 || m11 == 0) { in mkprime()
342 if ((pubexp == 3 && m3 == 1) in mkprime()
/freebsd/contrib/googletest/googlemock/test/
H A Dgmock-matchers-comparisons_test.cc424 Matcher<IntValue> m3 = Truly(IsPositiveIntValue); in TEST() local
425 Matcher<int> m4 = MatcherCast<int>(m3); in TEST()
519 Matcher<int> m3 = in TEST() local
521 EXPECT_TRUE(m3.Matches(42)); in TEST()
522 EXPECT_FALSE(m3.Matches(239)); in TEST()
631 Matcher<char> m3 = SafeMatcherCast<char>(TypedEq<int>('a')); in TEST() local
632 EXPECT_TRUE(m3.Matches('a')); in TEST()
633 EXPECT_FALSE(m3.Matches('b')); in TEST()
645 Matcher<Base&> m3 = Ref(d); in TEST() local
646 Matcher<Derived&> m4 = SafeMatcherCast<Derived&>(m3); in TEST()
[all …]
H A Dgmock-matchers-arithmetic_test.cc420 Matcher<int&> m3 = Not(m); in TEST() local
551 Matcher<int&> m3 = AllOf(greater_than_5, m2); in TEST() local
767 Matcher<int&> m3 = AnyOf(greater_than_5, m2); in TEST() local
1060 Matcher<RawType> m3 = matcher_maker(1.0); in TestMatches() local
1061 EXPECT_TRUE(m3.Matches(close_to_one_)); in TestMatches()
1062 EXPECT_FALSE(m3.Matches(further_from_one_)); in TestMatches()
1065 EXPECT_FALSE(m3.Matches(0.0)); in TestMatches()
1150 Matcher<RawType> m3 = matcher_maker(ParentType::infinity_, 0.0); in TestNearMatches() local
1151 EXPECT_TRUE(m3.Matches(ParentType::infinity_)); in TestNearMatches()
1152 EXPECT_FALSE(m3.Matches(ParentType::close_to_infinity_)); in TestNearMatches()
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Support/BLAKE3/
H A Dblake3_sse41.c95 __m128i m3 = loadu(&block[sizeof(__m128i) * 3]); in compress_pre() local
106 t2 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(2, 0, 2, 0)); // 14 12 10 8 in compress_pre()
109 t3 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 1, 3, 1)); // 15 13 11 9 in compress_pre()
116 m3 = t3; in compress_pre()
123 t1 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 3, 2, 2)); in compress_pre()
128 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
132 t3 = _mm_unpackhi_epi32(m1, m3); in compress_pre()
140 m3 = t3; in compress_pre()
146 t1 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 3, 2, 2)); in compress_pre()
151 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
[all …]
H A Dblake3_sse2.c101 __m128i m3 = loadu(&block[sizeof(__m128i) * 3]); in compress_pre() local
112 t2 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(2, 0, 2, 0)); // 14 12 10 8 in compress_pre()
115 t3 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 1, 3, 1)); // 15 13 11 9 in compress_pre()
122 m3 = t3; in compress_pre()
129 t1 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 3, 2, 2)); in compress_pre()
134 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
138 t3 = _mm_unpackhi_epi32(m1, m3); in compress_pre()
146 m3 = t3; in compress_pre()
152 t1 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 3, 2, 2)); in compress_pre()
157 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
[all …]
H A Dblake3_avx512.c128 __m128i m3 = loadu_128(&block[sizeof(__m128i) * 3]); in compress_pre() local
139 t2 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(2, 0, 2, 0)); // 14 12 10 8 in compress_pre()
142 t3 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 1, 3, 1)); // 15 13 11 9 in compress_pre()
149 m3 = t3; in compress_pre()
156 t1 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 3, 2, 2)); in compress_pre()
161 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
165 t3 = _mm_unpackhi_epi32(m1, m3); in compress_pre()
173 m3 = t3; in compress_pre()
179 t1 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(3, 3, 2, 2)); in compress_pre()
184 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
[all …]
/freebsd/tests/sys/geom/class/mirror/
H A D9_test.sh12 m3=`mktemp $base.XXXXXX` || exit 1
16 dd if=/dev/zero of=$m3 bs=$ddbs count=1024 >/dev/null 2>&1
20 attach_md us2 -t vnode -f $m3 || exit 1
51 if cmp -s $m1 $m3; then
57 rm -f $m1 $m2 $m3
/freebsd/usr.sbin/bhyve/amd64/
H A Dvga.c403 uint8_t m0, m1, m2, m3; in vga_mem_wr_handler() local
460 m3 = (set_reset & 8) ? mask : 0x00; in vga_mem_wr_handler()
470 c3 |= m3; in vga_mem_wr_handler()
476 m3 = set_reset & 8 ? 0xff : ~mask; in vga_mem_wr_handler()
481 c3 = enb_set_reset & 8 ? c3 & m3 : val & m3; in vga_mem_wr_handler()
487 m3 = set_reset & 8 ? mask : 0x00; in vga_mem_wr_handler()
492 c3 = enb_set_reset & 8 ? c3 | m3 : val | m3; in vga_mem_wr_handler()
498 m3 = set_reset & 8 ? mask : 0x00; in vga_mem_wr_handler()
503 c3 = enb_set_reset & 8 ? c3 ^ m3 : val ^ m3; in vga_mem_wr_handler()
519 m3 = (val & 8 ? 0xff : 0x00) & mask; in vga_mem_wr_handler()
[all …]
/freebsd/sys/dev/bhnd/cores/chipc/pwrctl/
H A Dbhnd_pwrctl_subr.c192 uint32_t n1, n2, clock, m1, m2, m3, mc; in bhnd_pwrctl_clock_rate() local
241 m3 = CHIPC_GET_BITS(m, CHIPC_M3); in bhnd_pwrctl_clock_rate()
255 m3 = bhnd_pwrctl_factor6(m3); in bhnd_pwrctl_clock_rate()
265 return (clock / (m1 * m2 * m3)); in bhnd_pwrctl_clock_rate()
267 return (clock / (m1 * m3)); in bhnd_pwrctl_clock_rate()
275 m3 += CHIPC_T2_BIAS; in bhnd_pwrctl_clock_rate()
278 KASSERT(m3 >= 2 && m3 <= 7, ("invalid m3 value")); in bhnd_pwrctl_clock_rate()
285 clock /= m3; in bhnd_pwrctl_clock_rate()
/freebsd/sys/contrib/libsodium/test/default/
H A Dsecretstream.c14 unsigned char *m1, *m2, *m3; in main() local
46 m3 = (unsigned char *) sodium_malloc(m3_len); in main()
57 randombytes_buf(m3, m3_len); in main()
58 memcpy(m3_, m3, m3_len); in main()
79 (state, c3, NULL, m3, m3_len, ad, ad_len, in main()
105 (state, m3, NULL, &tag, in main()
110 (state, m3, NULL, &tag, in main()
114 assert(memcmp(m3, m3_, m3_len) == 0); in main()
119 (state, m3, NULL, &tag, in main()
295 sodium_free(m3); in main()
/freebsd/sys/modules/dtb/allwinner/
H A DMakefile15 allwinner/sun8i-a83t-bananapi-m3.dts \
43 ${DTBDIR}/sun8i-a83t-bananapi-m3.dtb ${DTBDIR}/sinovoip-bpi-m3.dtb \
44 ${DTBDIR}/sun8i-a83t-bananapi-m3.dtb ${DTBDIR}/sun8i-a83t-sinovoip-bpi-m3.dtb
/freebsd/tools/test/stress2/misc/
H A Dnullfs30.sh84 while mount | grep -q "on $mp2/m3 "; do umount $mp2/m3; done 2> /dev/null
85 mount -t nullfs $mp1/f3 $mp2/m3
90 cat $mp2/m1 $mp2/m2 $mp2/m3 > /dev/null
/freebsd/sys/contrib/device-tree/Bindings/soc/ti/
H A Dwkup_m3_ipc.txt20 "ti,am3352-wkup-m3-ipc" for AM33xx SoCs
21 "ti,am4372-wkup-m3-ipc" for AM43xx SoCs
48 compatible = "ti,am3352-wkup-m3-ipc";
/freebsd/sys/contrib/device-tree/Bindings/remoteproc/
H A Dwkup_m3_rproc.txt19 "ti,am3352-wkup-m3" for AM33xx SoCs
20 "ti,am4372-wkup-m3" for AM43xx SoCs
42 compatible = "ti,am3352-wkup-m3";

123