Home
last modified time | relevance | path

Searched full:m3 (Results 1 – 25 of 221) sorted by relevance

123456789

/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 …]
/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/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/sys/contrib/device-tree/Bindings/remoteproc/
H A Dwkup_m3_rproc.txt1 TI Wakeup M3 Remoteproc Driver
4 The TI AM33xx and AM43xx family of devices use a small Cortex M3 co-processor
5 (commonly referred to as Wakeup M3 or CM3) to help with various low power tasks
10 Wkup M3 Device Node:
12 A wkup_m3 device node is used to represent the Wakeup M3 processor instance
19 "ti,am3352-wkup-m3" for AM33xx SoCs
20 "ti,am4372-wkup-m3" for AM43xx SoCs
42 compatible = "ti,am3352-wkup-m3";
/freebsd/sys/contrib/device-tree/Bindings/soc/ti/
H A Dwkup_m3_ipc.txt1 Wakeup M3 IPC Driver
4 The TI AM33xx and AM43xx family of devices use a small Cortex M3 co-processor
5 (commonly referred to as Wakeup M3 or CM3) to help with various low power tasks
12 Wkup M3 Device Node:
20 "ti,am3352-wkup-m3-ipc" for AM33xx SoCs
21 "ti,am4372-wkup-m3-ipc" for AM43xx SoCs
23 with the Wakeup M3 processor
48 compatible = "ti,am3352-wkup-m3-ipc";
H A Dwkup-m3-ipc.yaml4 $id: http://devicetree.org/schemas/soc/ti/wkup-m3-ipc.yaml#
7 title: Wakeup M3 IPC device
14 The TI AM33xx and AM43xx family of devices use a small Cortex M3 co-processor
15 (commonly referred to as Wakeup M3 or CM3) to help with various low power tasks
22 Wkup M3 Device Node
52 - ti,am3352-wkup-m3-ipc # for AM33xx SoCs
53 - ti,am4372-wkup-m3-ipc # for AM43xx SoCs
57 The IPC register address space to communicate with the Wakeup M3 processor
98 const: ti,am4372-wkup-m3-ipc
124 compatible = "ti,am3352-wkup-m3-ipc";
[all …]
/freebsd/sys/contrib/openzfs/tests/zfs-tests/tests/functional/cli_root/zpool_split/
H A Dzpool_split_vdevs.ksh47 # "m3" - 3-way mirror
64 disks[m3]="m1 m2 m3"
76 m|m3) # 2-way or 3-way mirror
117 typeset -a goodconfs=("m" "m l" "m s" "m c" "m m" "m3" "m3 m3" "m m3 l s c" "m m sc")
118 typeset -a badconfs=("d" "z1" "z2" "z3" "m d" "m3 d" "m z1" "m z2" "m z3")
/freebsd/contrib/llvm-project/llvm/lib/Target/SystemZ/
H A DSystemZInstrFormats.td284 bits<4> M3;
290 let Inst{15-12} = M3;
302 bits<4> M3;
309 let Inst{15-12} = M3;
321 bits<4> M3;
326 let Inst{35-32} = M3;
407 bits<4> M3;
412 let Inst{35-32} = M3;
467 bits<4> M3;
473 let Inst{35-32} = M3;
[all …]
/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()
538 // in m3.Matcher().
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
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Support/BLAKE3/
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_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 …]
/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/contrib/device-tree/Bindings/mailbox/
H A Dapple,mailbox.yaml37 M3 mailboxes are an older variant with a slightly different MMIO
42 - apple,t8103-m3-mailbox
43 - apple,t8112-m3-mailbox
44 - apple,t6000-m3-mailbox
45 - const: apple,m3-mailbox-v2
/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/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/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()
277 * m3: 511 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()
/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()

123456789