Home
last modified time | relevance | path

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

1234

/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/lib/libmd/aarch64/
H A Dmd5block.S69 .macro rounds f, m0, m1, m2, m3, s0, s1, s2, s3, k0, k1, k2, k3
73 round b, c, d, a, \f, \k3, \m3, \s3
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
85 round1 b, c, d, a, \k3, \m3, 20
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/contrib/googletest/googlemock/test/
H A Dgmock-matchers-comparisons_test.cc444 Matcher<IntValue> m3 = Truly(IsPositiveIntValue); in TEST() local
445 Matcher<int> m4 = MatcherCast<int>(m3); in TEST()
490 Matcher<int&> m3 = Ref(n); in TEST() local
491 Matcher<int> m4 = MatcherCast<int>(m3); in TEST()
565 Matcher<int> m3 = in TEST() local
567 EXPECT_TRUE(m3.Matches(42)); in TEST()
568 EXPECT_FALSE(m3.Matches(239)); in TEST()
677 Matcher<char> m3 = SafeMatcherCast<char>(TypedEq<int>('a')); in TEST() local
678 EXPECT_TRUE(m3.Matches('a')); in TEST()
679 EXPECT_FALSE(m3.Matches('b')); in TEST()
[all …]
H A Dgmock-matchers-arithmetic_test.cc605 Matcher<int&> m3 = Not(m); in TEST() local
736 Matcher<int&> m3 = AllOf(greater_than_5, m2); in TEST() local
952 Matcher<int&> m3 = AnyOf(greater_than_5, m2); in TEST() local
1243 Matcher<RawType> m3 = matcher_maker(1.0); in TestMatches() local
1244 EXPECT_TRUE(m3.Matches(close_to_one_)); in TestMatches()
1245 EXPECT_FALSE(m3.Matches(further_from_one_)); in TestMatches()
1248 EXPECT_FALSE(m3.Matches(0.0)); in TestMatches()
1333 Matcher<RawType> m3 = matcher_maker(ParentType::infinity_, 0.0); in TestNearMatches() local
1334 EXPECT_TRUE(m3.Matches(ParentType::infinity_)); in TestNearMatches()
1335 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 …]
/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/lib/libmd/amd64/
H A Dmd5block.S255 .macro vrounds f, i, m0, i0, m1, i1, m2, i2, m3, i3, s0, s1, s2, s3
259 vround %xmm1, %xmm2, %xmm3, %xmm0, \f, \i+3, \m3, \i3, \s3
278 .macro vrounds1 i, m0, i0, m1, i1, m2, i2, m3, i3
279 vrounds 0xe4, \i, \m0, \i0, \m1, \i1, \m2, \i2, \m3, \i3, 5, 9, 14, 20
282 .macro vrounds2 i, m0, i0, m1, i1, m2, i2, m3, i3
283 vrounds 0x96, \i, \m0, \i0, \m1, \i1, \m2, \i2, \m3, \i3, 4, 11, 16, 23
286 .macro vrounds3 i, m0, i0, m1, i1, m2, i2, m3, i3
287 vrounds 0x39, \i, \m0, \i0, \m1, \i1, \m2, \i2, \m3, \i3, 6, 10, 15, 21
/freebsd/sys/contrib/device-tree/src/arm64/exynos/
H A Dexynos9810.dtsi96 compatible = "samsung,mongoose-m3";
103 compatible = "samsung,mongoose-m3";
110 compatible = "samsung,mongoose-m3";
117 compatible = "samsung,mongoose-m3";
141 pmu-mongoose-m3 {
/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

1234