/freebsd/sys/powerpc/fpu/ |
H A D | fpu_subr.c | 99 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 D | fpu_implode.c | 78 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 D | blake2s-load-sse41.h | 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); \ 106 t0 = _mm_unpackhi_epi64(m1,m3); \ 111 t0 = _mm_unpackhi_epi64(m3,m1); \ 133 t1 = _mm_srli_si128(m3, 4); \ [all …]
|
H A D | blake2b-load-sse41.h | 21 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 D | blake2s-load-xop.h | 37 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 D | blake2s-load-sse2.h | 18 #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 D | blake2b-load-sse2.h | 18 #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 D | blake2b-load-sse41.h | 22 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 D | blake2b-load-avx2.h | 7 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 D | blake2b-load-sse2.h | 23 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 D | rsa_i15_keygen.c | 230 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 D | rsa_i31_keygen_inner.c | 244 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 D | gmock-matchers-comparisons_test.cc | 519 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 D | gmock-matchers-arithmetic_test.cc | 420 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 D | 9_test.sh | 12 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 D | blake3_sse41.c | 116 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 D | blake3_sse2.c | 122 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 D | vga.c | 470 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 D | bhnd_pwrctl_subr.c | 192 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 D | secretstream.c | 14 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 D | Makefile | 15 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 D | apple,mailbox.yaml | 42 - 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 D | nullfs30.sh | 84 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 D | wkup-m3-ipc.yaml | 4 $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 D | wkup_m3_ipc.txt | 20 "ti,am3352-wkup-m3-ipc" for AM33xx SoCs 21 "ti,am4372-wkup-m3-ipc" for AM43xx SoCs 48 compatible = "ti,am3352-wkup-m3-ipc";
|