Home
last modified time | relevance | path

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

1234

/freebsd/sys/powerpc/fpu/
H A Dfpu_subr.c99 s |= m3 | m2 | m1; in fpu_shr()
102 s |= m3 | m2; in fpu_shr()
105 s |= m3; in fpu_shr()
112 s |= m3 << lsh; in fpu_shr()
113 m3 = (m3 >> rsh) | (m2 << lsh); in fpu_shr()
150 m0 = m1, m1 = m2, m2 = m3, m3 = 0, exp -= 32; in fpu_norm()
152 m0 = m2, m1 = m3, m2 = 0, m3 = 0, exp -= 2 * 32; in fpu_norm()
153 else if (m3) in fpu_norm()
154 m0 = m3, m1 = 0, m2 = 0, m3 = 0, exp -= 3 * 32; in fpu_norm()
173 m3 = m2 << lsh; in fpu_norm()
[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.h31 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); \
106 t0 = _mm_unpackhi_epi64(m1,m3); \
111 t0 = _mm_unpackhi_epi64(m3,m1); \
133 t1 = _mm_srli_si128(m3, 4); \
[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); \
180 b0 = _mm_unpacklo_epi64(m1, m3); \
228 b0 = _mm_unpacklo_epi64(m0, m3); \
[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); \
87 b0 = _mm_unpacklo_epi64(m7, m3); \
93 b0 = _mm_unpackhi_epi64(m3, m1); \
111 b0 = _mm_unpacklo_epi64(m3, m5); \
141 b0 = _mm_unpacklo_epi64(m1, m3); \
208 b1 = _mm_unpacklo_epi64(m3, m5); \
213 b0 = _mm_unpacklo_epi64(m3, m7); \
[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.cc519 Matcher<int> m3 = in TEST() local
521 EXPECT_TRUE(m3.Matches(42)); in TEST()
522 EXPECT_FALSE(m3.Matches(239)); in TEST()
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
1026 Matcher<void*> m3 = IsNull(); in TEST() local
1028 EXPECT_TRUE(m3.Matches(p3)); in TEST()
1268 EXPECT_TRUE(m3.Matches(str2)); in TEST()
1272 EXPECT_FALSE(m3.Matches(str2)); in TEST()
[all …]
H A Dgmock-matchers-arithmetic_test.cc420 Matcher<int&> m3 = Not(m); in TEST() local
1061 EXPECT_TRUE(m3.Matches(close_to_one_)); in TestMatches()
1065 EXPECT_FALSE(m3.Matches(0.0)); in TestMatches()
1240 Matcher<float> m3 = FloatEq(nan1_); in TEST_F() local
1241 EXPECT_EQ("never matches", Describe(m3)); in TEST_F()
1255 EXPECT_EQ("is NaN", Describe(m3)); in TEST_F()
1281 EXPECT_EQ("never matches", Describe(m3)); in TEST_F()
1297 EXPECT_EQ("is NaN", Describe(m3)); in TEST_F()
1353 Matcher<double> m3 = DoubleEq(nan1_); in TEST_F() local
1368 EXPECT_EQ("is NaN", Describe(m3)); in TEST_F()
[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/contrib/llvm-project/llvm/lib/Support/BLAKE3/
H A Dblake3_sse41.c116 m3 = t3; 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()
151 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
155 t3 = _mm_unpackhi_epi32(m1, m3); in compress_pre()
163 m3 = t3; in compress_pre()
174 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
186 m3 = t3; in compress_pre()
209 m3 = t3; in compress_pre()
[all …]
H A Dblake3_sse2.c122 m3 = t3; 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()
157 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
161 t3 = _mm_unpackhi_epi32(m1, m3); in compress_pre()
169 m3 = t3; in compress_pre()
180 t2 = _mm_unpacklo_epi64(m3, m1); in compress_pre()
192 m3 = t3; in compress_pre()
215 m3 = t3; in compress_pre()
[all …]
/freebsd/usr.sbin/bhyve/amd64/
H A Dvga.c470 c3 |= m3; in vga_mem_wr_handler()
481 c3 = enb_set_reset & 8 ? c3 & m3 : val & m3; in vga_mem_wr_handler()
492 c3 = enb_set_reset & 8 ? c3 | m3 : val | m3; in vga_mem_wr_handler()
503 c3 = enb_set_reset & 8 ? c3 ^ m3 : val ^ m3; in vga_mem_wr_handler()
529 c3 |= m3; in vga_mem_wr_handler()
540 c3 &= m3; in vga_mem_wr_handler()
551 c3 |= m3; in vga_mem_wr_handler()
562 c3 ^= m3; in vga_mem_wr_handler()
588 c3 |= m3; in vga_mem_wr_handler()
599 c3 &= m3; 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 \
44 ${DTBDIR}/sun8i-a83t-bananapi-m3.dtb ${DTBDIR}/sinovoip-bpi-m3.dtb \
45 ${DTBDIR}/sun8i-a83t-bananapi-m3.dtb ${DTBDIR}/sun8i-a83t-sinovoip-bpi-m3.dtb
/freebsd/sys/contrib/device-tree/Bindings/mailbox/
H A Dapple,mailbox.yaml42 - apple,t8103-m3-mailbox
43 - apple,t8112-m3-mailbox
44 - apple,t6000-m3-mailbox
45 - const: apple,m3-mailbox-v2
/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.yaml4 $id: http://devicetree.org/schemas/soc/ti/wkup-m3-ipc.yaml#
52 - ti,am3352-wkup-m3-ipc # for AM33xx SoCs
53 - ti,am4372-wkup-m3-ipc # for AM43xx SoCs
98 const: ti,am4372-wkup-m3-ipc
124 compatible = "ti,am3352-wkup-m3-ipc";
165 compatible = "ti,am4372-wkup-m3-ipc";
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";

1234