You can subscribe to this list here.
| 2002 |
Jan
|
Feb
|
Mar
|
Apr
|
May
|
Jun
|
Jul
|
Aug
|
Sep
(1) |
Oct
(122) |
Nov
(152) |
Dec
(69) |
|---|---|---|---|---|---|---|---|---|---|---|---|---|
| 2003 |
Jan
(6) |
Feb
(25) |
Mar
(73) |
Apr
(82) |
May
(24) |
Jun
(25) |
Jul
(10) |
Aug
(11) |
Sep
(10) |
Oct
(54) |
Nov
(203) |
Dec
(182) |
| 2004 |
Jan
(307) |
Feb
(305) |
Mar
(430) |
Apr
(312) |
May
(187) |
Jun
(342) |
Jul
(487) |
Aug
(637) |
Sep
(336) |
Oct
(373) |
Nov
(441) |
Dec
(210) |
| 2005 |
Jan
(385) |
Feb
(480) |
Mar
(636) |
Apr
(544) |
May
(679) |
Jun
(625) |
Jul
(810) |
Aug
(838) |
Sep
(634) |
Oct
(521) |
Nov
(965) |
Dec
(543) |
| 2006 |
Jan
(494) |
Feb
(431) |
Mar
(546) |
Apr
(411) |
May
(406) |
Jun
(322) |
Jul
(256) |
Aug
(401) |
Sep
(345) |
Oct
(542) |
Nov
(308) |
Dec
(481) |
| 2007 |
Jan
(427) |
Feb
(326) |
Mar
(367) |
Apr
(255) |
May
(244) |
Jun
(204) |
Jul
(223) |
Aug
(231) |
Sep
(354) |
Oct
(374) |
Nov
(497) |
Dec
(362) |
| 2008 |
Jan
(322) |
Feb
(482) |
Mar
(658) |
Apr
(422) |
May
(476) |
Jun
(396) |
Jul
(455) |
Aug
(267) |
Sep
(280) |
Oct
(253) |
Nov
(232) |
Dec
(304) |
| 2009 |
Jan
(486) |
Feb
(470) |
Mar
(458) |
Apr
(423) |
May
(696) |
Jun
(461) |
Jul
(551) |
Aug
(575) |
Sep
(134) |
Oct
(110) |
Nov
(157) |
Dec
(102) |
| 2010 |
Jan
(226) |
Feb
(86) |
Mar
(147) |
Apr
(117) |
May
(107) |
Jun
(203) |
Jul
(193) |
Aug
(238) |
Sep
(300) |
Oct
(246) |
Nov
(23) |
Dec
(75) |
| 2011 |
Jan
(133) |
Feb
(195) |
Mar
(315) |
Apr
(200) |
May
(267) |
Jun
(293) |
Jul
(353) |
Aug
(237) |
Sep
(278) |
Oct
(611) |
Nov
(274) |
Dec
(260) |
| 2012 |
Jan
(303) |
Feb
(391) |
Mar
(417) |
Apr
(441) |
May
(488) |
Jun
(655) |
Jul
(590) |
Aug
(610) |
Sep
(526) |
Oct
(478) |
Nov
(359) |
Dec
(372) |
| 2013 |
Jan
(467) |
Feb
(226) |
Mar
(391) |
Apr
(281) |
May
(299) |
Jun
(252) |
Jul
(311) |
Aug
(352) |
Sep
(481) |
Oct
(571) |
Nov
(222) |
Dec
(231) |
| 2014 |
Jan
(185) |
Feb
(329) |
Mar
(245) |
Apr
(238) |
May
(281) |
Jun
(399) |
Jul
(382) |
Aug
(500) |
Sep
(579) |
Oct
(435) |
Nov
(487) |
Dec
(256) |
| 2015 |
Jan
(338) |
Feb
(357) |
Mar
(330) |
Apr
(294) |
May
(191) |
Jun
(108) |
Jul
(142) |
Aug
(261) |
Sep
(190) |
Oct
(54) |
Nov
(83) |
Dec
(22) |
| 2016 |
Jan
(49) |
Feb
(89) |
Mar
(33) |
Apr
(50) |
May
(27) |
Jun
(34) |
Jul
(53) |
Aug
(53) |
Sep
(98) |
Oct
(206) |
Nov
(93) |
Dec
(53) |
| 2017 |
Jan
(65) |
Feb
(82) |
Mar
(102) |
Apr
(86) |
May
(187) |
Jun
(67) |
Jul
(23) |
Aug
(93) |
Sep
(65) |
Oct
(45) |
Nov
(35) |
Dec
(17) |
| 2018 |
Jan
(26) |
Feb
(35) |
Mar
(38) |
Apr
(32) |
May
(8) |
Jun
(43) |
Jul
(27) |
Aug
(30) |
Sep
(43) |
Oct
(42) |
Nov
(38) |
Dec
(67) |
| 2019 |
Jan
(32) |
Feb
(37) |
Mar
(53) |
Apr
(64) |
May
(49) |
Jun
(18) |
Jul
(14) |
Aug
(53) |
Sep
(25) |
Oct
(30) |
Nov
(49) |
Dec
(31) |
| 2020 |
Jan
(87) |
Feb
(45) |
Mar
(37) |
Apr
(51) |
May
(99) |
Jun
(36) |
Jul
(11) |
Aug
(14) |
Sep
(20) |
Oct
(24) |
Nov
(40) |
Dec
(23) |
| 2021 |
Jan
(14) |
Feb
(53) |
Mar
(85) |
Apr
(15) |
May
(19) |
Jun
(3) |
Jul
(14) |
Aug
(1) |
Sep
(57) |
Oct
(73) |
Nov
(56) |
Dec
(22) |
| 2022 |
Jan
(3) |
Feb
(22) |
Mar
(6) |
Apr
(55) |
May
(46) |
Jun
(39) |
Jul
(15) |
Aug
(9) |
Sep
(11) |
Oct
(34) |
Nov
(20) |
Dec
(36) |
| 2023 |
Jan
(79) |
Feb
(41) |
Mar
(99) |
Apr
(169) |
May
(48) |
Jun
(16) |
Jul
(16) |
Aug
(57) |
Sep
(19) |
Oct
|
Nov
|
Dec
|
| S | M | T | W | T | F | S |
|---|---|---|---|---|---|---|
|
|
|
|
|
|
|
1
(2) |
|
2
(2) |
3
(3) |
4
(3) |
5
|
6
|
7
|
8
|
|
9
|
10
(1) |
11
|
12
|
13
(2) |
14
(6) |
15
(4) |
|
16
|
17
(2) |
18
(8) |
19
(1) |
20
|
21
|
22
(2) |
|
23
|
24
(1) |
25
|
26
(3) |
27
(1) |
28
|
29
|
|
30
(2) |
|
|
|
|
|
|
|
From: Mark W. <ma...@so...> - 2018-09-14 21:13:20
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=5d41dadeb3cb805546497b350750ca3bee365210 commit 5d41dadeb3cb805546497b350750ca3bee365210 Author: Mark Wielaard <ma...@kl...> Date: Fri Sep 14 23:12:45 2018 +0200 Update vg-entities.xml and valgrind.h for next version number. Diff: --- docs/xml/vg-entities.xml | 6 +++--- include/valgrind.h | 2 +- 2 files changed, 4 insertions(+), 4 deletions(-) diff --git a/docs/xml/vg-entities.xml b/docs/xml/vg-entities.xml index c3d7e6d..f048f11 100644 --- a/docs/xml/vg-entities.xml +++ b/docs/xml/vg-entities.xml @@ -2,12 +2,12 @@ <!ENTITY vg-jemail "ju...@va..."> <!ENTITY vg-vemail "val...@va..."> <!ENTITY cl-email "Jos...@gm..."> -<!ENTITY vg-lifespan "2000-2017"> +<!ENTITY vg-lifespan "2000-2018"> <!-- valgrind release + version stuff --> <!ENTITY rel-type "Release"> -<!ENTITY rel-version "3.13.0"> -<!ENTITY rel-date "15 June 2017"> +<!ENTITY rel-version "3.14.0"> +<!ENTITY rel-date "?? September 2018"> <!-- where the docs are installed --> <!ENTITY vg-docs-path "$INSTALL/share/doc/valgrind/html/index.html"> diff --git a/include/valgrind.h b/include/valgrind.h index 07c4f43..577c8f0 100644 --- a/include/valgrind.h +++ b/include/valgrind.h @@ -89,7 +89,7 @@ || (__VALGRIND_MAJOR__ == 3 && __VALGRIND_MINOR__ >= 6)) */ #define __VALGRIND_MAJOR__ 3 -#define __VALGRIND_MINOR__ 13 +#define __VALGRIND_MINOR__ 14 #include <stdarg.h> |
|
From: Mark W. <ma...@so...> - 2018-09-14 20:56:44
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=1ca0fe21abd909fa11b8c8bf684d9276b3d0f392 commit 1ca0fe21abd909fa11b8c8bf684d9276b3d0f392 Author: Mark Wielaard <ma...@kl...> Date: Fri Sep 14 22:55:17 2018 +0200 Include suppsrc_lineno.supp and suppsrc_sanlineno.supp in EXTRA_DIST. These are test file that are needed in the dist tar. Diff: --- memcheck/tests/Makefile.am | 2 ++ 1 file changed, 2 insertions(+) diff --git a/memcheck/tests/Makefile.am b/memcheck/tests/Makefile.am index 84e4940..76e0e90 100644 --- a/memcheck/tests/Makefile.am +++ b/memcheck/tests/Makefile.am @@ -277,7 +277,9 @@ EXTRA_DIST = \ suppfreecollision.stderr.exp suppfreecollision.supp suppfreecollision.vgtest \ supponlyobj.stderr.exp supponlyobj.supp supponlyobj.vgtest \ suppsrc_lineno.stderr.exp suppsrc_lineno.stdout.exp suppsrc_lineno.vgtest \ + suppsrc_lineno.supp \ suppsrc_sanlineno.stderr.exp suppsrc_sanlineno.stdout.exp suppsrc_sanlineno.vgtest \ + suppsrc_sanlineno.supp \ suppvarinfo5.stderr.exp suppvarinfo5.supp suppvarinfo5.vgtest \ test-plo-no.vgtest test-plo-no.stdout.exp \ test-plo-no.stderr.exp-le64 test-plo-no.stderr.exp-le32 \ |
|
From: Julian S. <se...@so...> - 2018-09-14 11:50:01
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=36ca427809c7099cb46e8f178259e9a42421dcb2 commit 36ca427809c7099cb46e8f178259e9a42421dcb2 Author: Julian Seward <js...@ac...> Date: Fri Sep 14 13:48:54 2018 +0200 Update somewhat more for 3.14 final. Diff: --- NEWS | 51 ++++++++++++++++++++++++++++++++------------------- 1 file changed, 32 insertions(+), 19 deletions(-) diff --git a/NEWS b/NEWS index d7a3416..6310b37 100644 --- a/NEWS +++ b/NEWS @@ -1,6 +1,5 @@ -Release 3.14.0 (?? ????????? 201?) -~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~-- -Release 3.14.0 is under development, not yet released. +Release 3.14.0 (?? September 2018) +~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 3.14.0 is a feature release with many improvements and the usual collection of bug fixes. @@ -8,41 +7,52 @@ bug fixes. This release supports X86/Linux, AMD64/Linux, ARM32/Linux, ARM64/Linux, PPC32/Linux, PPC64BE/Linux, PPC64LE/Linux, S390X/Linux, MIPS32/Linux, MIPS64/Linux, ARM/Android, ARM64/Android, MIPS32/Android, X86/Android, -X86/Solaris, AMD64/Solaris and AMD64/MacOSX 10.12. There is also preliminary +X86/Solaris, AMD64/Solaris and AMD64/MacOSX 10.12. There is also preliminary support for X86/macOS 10.13, AMD64/macOS 10.13. * ==================== CORE CHANGES =================== -* The new option --keep-debuginfo=no|yes (default no) can be used to - keep symbols etc for unloaded code. This allows saved stack traces - (e.g. memory leaks) to include file/line info for code that has been - dlclose'd (or similar). See user manual for more information and - known limitations. +* The new option --keep-debuginfo=no|yes (default no) can be used to retain + debug info for unloaded code. This allows saved stack traces (e.g. for + memory leaks) to include file/line info for code that has been dlclose'd (or + similar). See the user manual for more information and known limitations. + * Ability to specify suppressions based on source file name and line number. -* Majorly overhauled register allocator (add details) + +* Majorly overhauled register allocator. No end-user changes, but the JIT + generates code a bit more quickly now. * ================== PLATFORM CHANGES ================= * Preliminary support for macOS 10.13 has been added. + * mips: support for MIPS32/MIPS64 Revision 6 has been added. + * mips: support for MIPS SIMD architecture (MSA) has been added. + * mips: support for MIPS N32 ABI support has been added. * ==================== TOOL CHANGES ==================== -* Helgrind: +* Helgrind: Addition of a flag + --delta-stacktrace=no|yes [yes on linux amd64/x86] + which specifies how full history stack traces should be computed. + Setting this to =yes can speed up Helgrind by 25% when using + --history-level=full. - - Addition of a flag --delta-stacktrace=no|yes [yes on linux amd64/x86], - specifying how full history stack traces are computed. Using yes can speed - up Helgrind by 25% when using --history-level=full. +* Memcheck: reduced false positive rate for optimised code created by Clang 6 + / LLVM 6 on x86, amd64 and arm64. In particular, Memcheck analyses code + blocks more carefully to determine where it can avoid expensive definedness + checks without loss of precision. This is controlled by the flag + --expensive-definedness-checks=no|auto|yes [auto]. * ==================== OTHER CHANGES ==================== -* A new configure option --enable-lto=yes allows to build Valgrind - with link time optimisation. If the toolchain supports it, - this produces a smaller/faster Valgrind (up to 10%). - Note that if you are doing some Valgrind development, --enable-lto=yes - significantly slows down the build. +* Valgrind is now buildable with link-time optimisation (LTO). A new + configure option --enable-lto=yes allows building Valgrind with LTO. If the + toolchain supports it, this produces a smaller/faster Valgrind (up to 10%). + Note that if you are doing Valgrind development, --enable-lto=yes massively + slows down the build process. * ==================== FIXED BUGS ==================== @@ -152,6 +162,7 @@ where XXXXXX is the bug number as listed below. 396906 compile tests failure on mips32-linux: broken inline asm in tests on mips32-linux 397012 glibc ld.so uses arch_prctl on i386 +397089 amd64: Incorrect decoding of three-register vmovss/vmovsd opcode 11h 397354 utimensat should ignore timespec tv_sec if tv_nsec is UTIME_NOW/OMIT 397424 glibc 2.27 and gdb_server tests 398066 s390x: cgijl dep1, 0 reports false unitialised values warning @@ -163,6 +174,8 @@ n-i-bz Add support for the Linux BLKREPORTZONE and BLKRESETZONE ioctls n-i-bz Fix possible stack trashing by semctl syscall wrapping n-i-bz Add support for the Linux membarrier() system call + + Release 3.13.0 (15 June 2017) ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ |
|
From: Julian S. <se...@so...> - 2018-09-14 11:26:02
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=529436ff596203a451cf525824b3538d006de0bb commit 529436ff596203a451cf525824b3538d006de0bb Author: Julian Seward <js...@ac...> Date: Fri Sep 14 13:23:19 2018 +0200 Bug 397089 - (TESTCASES FOR) Incorrect decoding of three-register vmovss/vmovsd opcode 11h. Adds test cases, that check both the 10h and 11h decodings. For some reason the expected output diff is huge. I don't know why. It is the same as what the hardware produces, though. Diff: --- none/tests/amd64/avx-1.c | 26 +- none/tests/amd64/avx-1.stdout.exp | 7366 +++++++++++++++++++------------------ 2 files changed, 3866 insertions(+), 3526 deletions(-) diff --git a/none/tests/amd64/avx-1.c b/none/tests/amd64/avx-1.c index e25fee0..1c6f0c0 100644 --- a/none/tests/amd64/avx-1.c +++ b/none/tests/amd64/avx-1.c @@ -1322,9 +1322,21 @@ GEN_test_RandM(VPALIGNR_128_3of3, "vpalignr $12, %%xmm6, %%xmm8, %%xmm7", "vpalignr $15, (%%rsi), %%xmm8, %%xmm7") -GEN_test_Ronly(VMOVSD_REG_XMM, "vmovsd %%xmm9, %%xmm7, %%xmm8") - -GEN_test_Ronly(VMOVSS_REG_XMM, "vmovss %%xmm9, %%xmm7, %%xmm8") +// These (3 arg) vmovss and vmovsd gave some difficulty in testing. See +// bug 397089. +GEN_test_Ronly(VMOVSD_REG_XMM_1of3, + "vmovsd %%xmm9, %%xmm7, %%xmm8") // encoding 10 +GEN_test_Ronly(VMOVSD_REG_XMM_2of3, + "vmovsd %%xmm7, %%xmm8, %%xmm9") // encoding 10 +GEN_test_Ronly(VMOVSD_REG_XMM_3of3, + "vmovsd %%xmm8, %%xmm9, %%xmm7") // encoding 11 + +GEN_test_Ronly(VMOVSS_REG_XMM_1of3, + "vmovss %%xmm9, %%xmm7, %%xmm8") // encoding 10 +GEN_test_Ronly(VMOVSS_REG_XMM_2of3, + "vmovss %%xmm7, %%xmm8, %%xmm9") // encoding 10 +GEN_test_Ronly(VMOVSS_REG_XMM_3of3, + "vmovss %%xmm8, %%xmm9, %%xmm7") // encoding 11 GEN_test_Monly(VMOVLPD_128_M64_XMM_XMM, "vmovlpd (%%rsi), %%xmm8, %%xmm7") @@ -2566,8 +2578,12 @@ int main ( void ) DO_D( VPALIGNR_128_1of3 ); DO_D( VPALIGNR_128_2of3 ); DO_D( VPALIGNR_128_3of3 ); - DO_D( VMOVSD_REG_XMM ); - DO_D( VMOVSS_REG_XMM ); + DO_D( VMOVSD_REG_XMM_1of3 ); + DO_D( VMOVSD_REG_XMM_2of3 ); + DO_D( VMOVSD_REG_XMM_3of3 ); + DO_D( VMOVSS_REG_XMM_1of3 ); + DO_D( VMOVSS_REG_XMM_2of3 ); + DO_D( VMOVSS_REG_XMM_3of3 ); DO_D( VMOVLPD_128_M64_XMM_XMM ); DO_D( VMOVLPD_128_XMM_M64 ); DO_D( VSHUFPD_128_1of2 ); diff --git a/none/tests/amd64/avx-1.stdout.exp b/none/tests/amd64/avx-1.stdout.exp index f9eda1a..d530552 100644 --- a/none/tests/amd64/avx-1.stdout.exp +++ b/none/tests/amd64/avx-1.stdout.exp @@ -24460,7 +24460,7 @@ VPALIGNR_128_3of3(mem) 3b65996f871e91df.f8359ef94c0a3eb4.c76fcaff94518adf.0ac2a2e7c863e911 8e67e9a25bd1e1f5 -VMOVSD_REG_XMM(reg) +VMOVSD_REG_XMM_1of3(reg) before fece8c8c8a2352c7.fc786aa864c62371.a67213ff19396b1a.097a24381bdf1793 b6418912f1e47a33.dd358590c3aa4b62.2f55a42991d1f003.bf894a6b56649c4f @@ -24473,7 +24473,7 @@ VMOVSD_REG_XMM(reg) 120ddb9e2da093e4.bc686615bfd6c6de.ed2b4be44f5e081c.c367b98460ead640 6e7e7e9edae4d987.73dd892175574f10.3e40069df06df010.f2e1eb6f55808192 29c45e19522f5870 -VMOVSD_REG_XMM(mem) +VMOVSD_REG_XMM_1of3(mem) before 42da8d6c72051806.26e06e7c933b8ac7.df5f6aa20038a425.7ce0d0be0f89e48d 1aeff455d20d7d82.967fa8a6f432e051.ddbc86837d867f49.0557a6b5493e203c @@ -24487,7 +24487,7 @@ VMOVSD_REG_XMM(mem) 784a5b9ac0e425d6.0da3e68b202d6df2.fa325c15ba96b96b.64f962d27ba55fe6 f2bd41d0ac6eda39 -VMOVSD_REG_XMM(reg) +VMOVSD_REG_XMM_1of3(reg) before 3a871c5368018c6f.b52853ce87cce007.cdc0e31e23491c61.d2e40e9eb37090c3 98a4edc74ae9b334.21357348fc1530cc.b54a1aac3e3561c9.aba0ea370ee7ded8 @@ -24500,7 +24500,7 @@ VMOVSD_REG_XMM(reg) 6960b298eeb28936.983e37f43ecdd153.218d85a10e7c78d7.61316dcde6075ed9 07076633f1e94a1f.f60f1cbe66ff7ec5.6cd5226a2eab9c36.d165124a57dacef0 d506559c7e6ee849 -VMOVSD_REG_XMM(mem) +VMOVSD_REG_XMM_1of3(mem) before 4ae1b2ad77ce6912.cfe40502ef19349b.17749d9293b8f451.f46eec713b4d0a94 0cc2a66b5c070c74.1d448b7382ce8157.d738365cde03ee21.14a3e024d0eefe9a @@ -24514,7 +24514,7 @@ VMOVSD_REG_XMM(mem) e7c6409b6131abba.bbbe3ee7def9373e.a411a0824480623f.8b15323a045e6754 9ae98976da465460 -VMOVSD_REG_XMM(reg) +VMOVSD_REG_XMM_1of3(reg) before b28af90da95cb7c5.b780dee5b73b1ff4.c36f62c3dd8617c1.69bd6ab796ca53e4 2d437e6b0d2ecb30.4571028b6b4da579.c1d35df0e3c94b33.3df93c9177d6b87f @@ -24527,7 +24527,7 @@ VMOVSD_REG_XMM(reg) 696215fca147cd4c.6c6329799873fa75.11352cda8b4d0f41.fc9192fe04b14e3a c031b92c0134f9c6.0823ce9b5abada14.0fe3c9ed719f9e97.8250e8e95966d141 ab04ba3e9101fdc1 -VMOVSD_REG_XMM(mem) +VMOVSD_REG_XMM_1of3(mem) before 527785e9c88f8de6.90fd6667ca808b49.f57d6ddecf2d0180.17273295334936e0 5576c4d61b1b3edc.3312181997b7be82.0f3c822c10d82ae8.854e623f6ada10c8 @@ -24541,7 +24541,7 @@ VMOVSD_REG_XMM(mem) db488e26835ef3e8.66477c93af18fac5.391dff9d6c087557.03750845adda8229 cb0d7679f06290f8 -VMOVSS_REG_XMM(reg) +VMOVSD_REG_XMM_2of3(reg) before 68b79b5f1900d117.17b31261d02d6e57.adff263332597a27.02d75f98bea40eb6 38c07362c53e8332.1ed9fa8ea92afa47.382fc5fa29b68cef.6726264f4da99ac0 @@ -24550,11 +24550,11 @@ VMOVSS_REG_XMM(reg) de8eb61484a14795 after 68b79b5f1900d117.17b31261d02d6e57.adff263332597a27.02d75f98bea40eb6 - 0000000000000000.0000000000000000.adff263332597a27.02d75f98951b7b84 + 38c07362c53e8332.1ed9fa8ea92afa47.382fc5fa29b68cef.6726264f4da99ac0 9675fbed90abe0f5.cb88c29a296253e3.6324555431ba6cc8.46d7ceae3622d5a1 - dd202d6e15d0250a.fc8ae6706de03458.8b2bd3ade5f1565e.79b6d5a1951b7b84 + 0000000000000000.0000000000000000.382fc5fa29b68cef.02d75f98bea40eb6 de8eb61484a14795 -VMOVSS_REG_XMM(mem) +VMOVSD_REG_XMM_2of3(mem) before 4f2dedf322bff602.6b0e0750f03b8e20.8bace3fb90b05ad1.0a8e3a71e2e8855f aa5df62a898244f5.9b8a8400be7756e1.56ba3329aedf817c.3d99860cc32a3674 @@ -24568,7 +24568,7 @@ VMOVSS_REG_XMM(mem) 8aa36f512324ab1e.50605875a194f616.0cc9c11b4e88c112.2fdcbd77a2c00e91 a6aaa120d92cacef -VMOVSS_REG_XMM(reg) +VMOVSD_REG_XMM_2of3(reg) before 41515a4f6414bc14.c751d7198e1b3dad.8d52a714ee8c46e2.af63f6b7071a5255 5c1de472df0379a9.5dc101e833e75e72.dd02892f9e86e509.fd1870a52b3ad47a @@ -24577,11 +24577,11 @@ VMOVSS_REG_XMM(reg) 82d74e94366855e3 after 41515a4f6414bc14.c751d7198e1b3dad.8d52a714ee8c46e2.af63f6b7071a5255 - 0000000000000000.0000000000000000.8d52a714ee8c46e2.af63f6b727559915 + 5c1de472df0379a9.5dc101e833e75e72.dd02892f9e86e509.fd1870a52b3ad47a 535a3bf3e785215d.29be6aac2d93c99a.9abdfa344c0d1039.d3b5aad1d7f402ab - 82545c401826eeda.05168c50982c3b50.22cff68d95ad031b.0b06202727559915 + 0000000000000000.0000000000000000.dd02892f9e86e509.af63f6b7071a5255 82d74e94366855e3 -VMOVSS_REG_XMM(mem) +VMOVSD_REG_XMM_2of3(mem) before 15f4b002203af242.455641c40c731dcc.ce93e5c092bc70c1.cf837aa814f2f95d 9e28c35f02d62b5d.f8aee8eb62f7e9e0.6102f0e834522319.fe2781f065692fab @@ -24595,7 +24595,7 @@ VMOVSS_REG_XMM(mem) 0509e9921c9c647a.9d8b6ad29ed64b1d.50e60d11e6b9f62c.536a08b7f01b4b1a 30a2810e616ea892 -VMOVSS_REG_XMM(reg) +VMOVSD_REG_XMM_2of3(reg) before fff96d43142335c7.9b4df4418cdfdcd3.48a93d6abc48599e.65f216e92da38e3f 1dbbc7c0a6c52e63.98d8a08e641ce099.534cc056ac21f5f1.b321c2298dc294e9 @@ -24604,11 +24604,11 @@ VMOVSS_REG_XMM(reg) 8b6f6b935fd09827 after fff96d43142335c7.9b4df4418cdfdcd3.48a93d6abc48599e.65f216e92da38e3f - 0000000000000000.0000000000000000.48a93d6abc48599e.65f216e90accddb1 + 1dbbc7c0a6c52e63.98d8a08e641ce099.534cc056ac21f5f1.b321c2298dc294e9 e4338ef3b3e0cf12.d8786765bf602df7.19bff10007ee5ac1.163d8cbe2321c556 - b1afbb46d5005381.37f8c7b2b9b67e1a.f850ccd56b3ac4bb.6a13f1920accddb1 + 0000000000000000.0000000000000000.534cc056ac21f5f1.65f216e92da38e3f 8b6f6b935fd09827 -VMOVSS_REG_XMM(mem) +VMOVSD_REG_XMM_2of3(mem) before 551d78ac3d37b1e3.e0794c27abb2f75c.91233c626f2a912e.4b494b427492718a a4e993c9c110e512.cdde3b01cf81f64e.c2c6405ffdc9205e.6df76cb2bd819bdb @@ -24622,7 +24622,7 @@ VMOVSS_REG_XMM(mem) 410ae4bf29418d78.51a9294f72a7f929.19a4e9f40eb5a4c4.92a2814a815559b2 4d376d4b3352648f -VMOVLPD_128_M64_XMM_XMM(reg) +VMOVSD_REG_XMM_3of3(reg) before 47b1ebff9616de9f.47f7117045b37907.a0a61e9c2916746a.f7778664ca1b1152 de5bf6d3452d008b.42323dd577c470b8.1d6f63929ed33a73.1cf2a4d1cedbebac @@ -24630,12 +24630,12 @@ VMOVLPD_128_M64_XMM_XMM(reg) 4e72a386fa8733ae.86c1806c8bf96e33.1190ca2a35639a8a.aa0f4f571b9ad577 cc49d5479db15d40 after - 47b1ebff9616de9f.47f7117045b37907.a0a61e9c2916746a.f7778664ca1b1152 + 0000000000000000.0000000000000000.1190ca2a35639a8a.1cf2a4d1cedbebac de5bf6d3452d008b.42323dd577c470b8.1d6f63929ed33a73.1cf2a4d1cedbebac 6c828a31dd240902.0d87e3dbda822db8.244ef39e6f6888ef.64e0bd293501ee00 4e72a386fa8733ae.86c1806c8bf96e33.1190ca2a35639a8a.aa0f4f571b9ad577 cc49d5479db15d40 -VMOVLPD_128_M64_XMM_XMM(mem) +VMOVSD_REG_XMM_3of3(mem) before a55bcbe5d6524285.e1773d3f36e0bb3c.88ae8e76a533ed54.4081e4a38e50acf2 1011ad1de38a4072.7fdd55c630bddd57.ee188be3443e6648.0d6d3e7616baf9d1 @@ -24645,11 +24645,11 @@ VMOVLPD_128_M64_XMM_XMM(mem) after a55bcbe5d6524285.e1773d3f36e0bb3c.88ae8e76a533ed54.4081e4a38e50acf2 1011ad1de38a4072.7fdd55c630bddd57.ee188be3443e6648.0d6d3e7616baf9d1 - 0000000000000000.0000000000000000.ee188be3443e6648.4081e4a38e50acf2 + eb36f8dcdf641234.85efe68981aad5ac.96cdf2a18526973a.d3a0d30d682dbed3 1198270ce7ec75f7.4ffbecf3c831dee6.5b973f9b84f63a57.f0659fd6203537a5 bf0a9e3cdb5fa0f3 -VMOVLPD_128_M64_XMM_XMM(reg) +VMOVSD_REG_XMM_3of3(reg) before 9cd9ccab35363468.5d01b69b162f25e6.3a4b636f9ee035b2.1843eebd5cba0cca e21f268fc94730b1.ad3e21738938dd2e.a02c486ba24315bc.ab9d7cf3297ec8c0 @@ -24657,12 +24657,12 @@ VMOVLPD_128_M64_XMM_XMM(reg) 1d404b6610444f6e.c5647cb3a8cd5878.50d149909d526438.bf8a224b1538f1e4 f8b532456a45d66a after - 9cd9ccab35363468.5d01b69b162f25e6.3a4b636f9ee035b2.1843eebd5cba0cca + 0000000000000000.0000000000000000.50d149909d526438.ab9d7cf3297ec8c0 e21f268fc94730b1.ad3e21738938dd2e.a02c486ba24315bc.ab9d7cf3297ec8c0 ef28a754331dd07a.db1be4825b145afb.deea96526de5bcaf.ee706429084f2b65 1d404b6610444f6e.c5647cb3a8cd5878.50d149909d526438.bf8a224b1538f1e4 f8b532456a45d66a -VMOVLPD_128_M64_XMM_XMM(mem) +VMOVSD_REG_XMM_3of3(mem) before 77be110426839623.cab20e31fb49ea3a.45e564f18e7193d1.522d5d92ce164902 1671397262fdec3a.51cced2291b7dd89.396a182a260cc634.4049cec29bbea9ba @@ -24672,11 +24672,11 @@ VMOVLPD_128_M64_XMM_XMM(mem) after 77be110426839623.cab20e31fb49ea3a.45e564f18e7193d1.522d5d92ce164902 1671397262fdec3a.51cced2291b7dd89.396a182a260cc634.4049cec29bbea9ba - 0000000000000000.0000000000000000.396a182a260cc634.522d5d92ce164902 + b39a287d3dc095db.0dd8e3a36d1a6408.7bbe14498ea9aecb.7673998da0d5be0c 28055a10d0d74c34.5c23eb212cffba62.e8aed53ae25407c2.50f5b9607ae7c5a3 2a1c2aa5c581fa2c -VMOVLPD_128_M64_XMM_XMM(reg) +VMOVSD_REG_XMM_3of3(reg) before 6034e8ca1c2e9852.527d4916394ecf6f.98f9040969f01c44.5d07d6ea3c198c46 4e89f03a1b7bdcc2.0ed0727d9431d8b8.1ea627c6c17cc65a.b4939343bb05fa83 @@ -24684,12 +24684,12 @@ VMOVLPD_128_M64_XMM_XMM(reg) c219caab8322452f.a732641b8e6d6e27.79b4806f2f8ee0d0.7c7631a4928081d6 a4660b8423271144 after - 6034e8ca1c2e9852.527d4916394ecf6f.98f9040969f01c44.5d07d6ea3c198c46 + 0000000000000000.0000000000000000.79b4806f2f8ee0d0.b4939343bb05fa83 4e89f03a1b7bdcc2.0ed0727d9431d8b8.1ea627c6c17cc65a.b4939343bb05fa83 50663c615ff20228.36c85230fc8d233c.4b7552c4cf2cf34f.ca1e883279230da4 c219caab8322452f.a732641b8e6d6e27.79b4806f2f8ee0d0.7c7631a4928081d6 a4660b8423271144 -VMOVLPD_128_M64_XMM_XMM(mem) +VMOVSD_REG_XMM_3of3(mem) before 1fb991bd47247a1b.00ec96842494e384.3dda252a65de73a4.05adad337e2ec989 c93c3f3d1b837887.652c9a58ddd616d2.d48c0f4a9debefe0.4cadd57c5896ea25 @@ -24699,11 +24699,11 @@ VMOVLPD_128_M64_XMM_XMM(mem) after 1fb991bd47247a1b.00ec96842494e384.3dda252a65de73a4.05adad337e2ec989 c93c3f3d1b837887.652c9a58ddd616d2.d48c0f4a9debefe0.4cadd57c5896ea25 - 0000000000000000.0000000000000000.d48c0f4a9debefe0.05adad337e2ec989 + 7ebb91efba51c7b3.4f25d4934b731ac6.4913a06553a09d06.a800f4b658547e50 1a0204bf419a22cc.19233ea109f82d0b.763d5368a3093b43.76f2074d1af4c2b8 12cf09ad3b00f206 -VMOVLPD_128_XMM_M64(reg) +VMOVSS_REG_XMM_1of3(reg) before d9e3f643560649e9.79dd1299cb6846fd.1f71d7efb4f0894e.38d4a440a83383c3 2579cb790892050b.7717396974c9ee73.bc5d98e7e7e76b3b.6ba50fd77e2a32b1 @@ -24712,11 +24712,11 @@ VMOVLPD_128_XMM_M64(reg) 426cc657024efecb after d9e3f643560649e9.79dd1299cb6846fd.1f71d7efb4f0894e.38d4a440a83383c3 - 2579cb790892050b.7717396974c9ee73.bc5d98e7e7e76b3b.6ba50fd77e2a32b1 + 0000000000000000.0000000000000000.1f71d7efb4f0894e.38d4a4400fabb389 53de82bded2f5f19.f07ef41b5ac8d85a.4e317ef73e690e7e.eb7c111b42f8033a bf5e197a9f6996be.c0dcc09c9672bedd.2f3a868a5703b0c1.942524f70fabb389 426cc657024efecb -VMOVLPD_128_XMM_M64(mem) +VMOVSS_REG_XMM_1of3(mem) before d11c732736eea02c.c5458b1cbdcce4a7.c3fe17d646d25d29.bdc4ab0bcb408bb3 1c03a553c89654d7.c1dfd40fe0e5867f.d5b077b786f47069.521be9e838addbfe @@ -24724,13 +24724,13 @@ VMOVLPD_128_XMM_M64(mem) 5ba18d6f742fe5bd.0b5bdc98ab66b6ae.96f3401a23b0e578.055fa1636b44ce51 dbe513d96a87e8b1 after - d11c732736eea02c.c5458b1cbdcce4a7.c3fe17d646d25d29.4c8b3c8c3ad5de4f + d11c732736eea02c.c5458b1cbdcce4a7.c3fe17d646d25d29.bdc4ab0bcb408bb3 1c03a553c89654d7.c1dfd40fe0e5867f.d5b077b786f47069.521be9e838addbfe 01ebdac7d352d7f9.0f78f1bfa73fb8f3.d2be5b2971e5b4ca.4c8b3c8c3ad5de4f 5ba18d6f742fe5bd.0b5bdc98ab66b6ae.96f3401a23b0e578.055fa1636b44ce51 dbe513d96a87e8b1 -VMOVLPD_128_XMM_M64(reg) +VMOVSS_REG_XMM_1of3(reg) before 28678e5bd129671a.06f13a38c6383a50.11d593068ae7bb5e.fd1da075b961bf9e 4a320e533cb68939.dea65d0ce67991dd.7d331275e04d04ac.e206f9264e05fd69 @@ -24739,11 +24739,11 @@ VMOVLPD_128_XMM_M64(reg) 2639ac7523166d5c after 28678e5bd129671a.06f13a38c6383a50.11d593068ae7bb5e.fd1da075b961bf9e - 4a320e533cb68939.dea65d0ce67991dd.7d331275e04d04ac.e206f9264e05fd69 + 0000000000000000.0000000000000000.11d593068ae7bb5e.fd1da075e753989c 9b928f2f48bb88ba.be8e72d9efffa792.abbf53524825cd47.237bc619ffa75c04 78d30e5990c3a048.8473f689fdd53898.f6c553075ffa51d9.9b48833ae753989c 2639ac7523166d5c -VMOVLPD_128_XMM_M64(mem) +VMOVSS_REG_XMM_1of3(mem) before 9f1abeb6cefb9671.3e40863fb15a0f90.0b23640a2d07ff1e.bc930f02c058cd0e e4b634ea050ed007.4727f34b460d0f3e.2e6838479ba2b94e.587482ad07cb7d93 @@ -24751,13 +24751,13 @@ VMOVLPD_128_XMM_M64(mem) 3e533cd785f06664.958e9d8a3ef4b479.bce403a59e41f65d.819d7ec8ba22683c c77eff0f5c1e1bb8 after - 9f1abeb6cefb9671.3e40863fb15a0f90.0b23640a2d07ff1e.26b3a876d1e09c14 + 9f1abeb6cefb9671.3e40863fb15a0f90.0b23640a2d07ff1e.bc930f02c058cd0e e4b634ea050ed007.4727f34b460d0f3e.2e6838479ba2b94e.587482ad07cb7d93 cfdb8afbe35cd74a.f0d252ebec67ddfd.cb0fef2c62b12254.26b3a876d1e09c14 3e533cd785f06664.958e9d8a3ef4b479.bce403a59e41f65d.819d7ec8ba22683c c77eff0f5c1e1bb8 -VMOVLPD_128_XMM_M64(reg) +VMOVSS_REG_XMM_1of3(reg) before 53a226b7565ff134.0bebc66806d73a84.92a7d294d941d25f.dfb2f29e6c5cf095 8055f22c4271285b.146fa59c831b0fd4.4369ec7558d9715b.0f473703e711cd27 @@ -24766,11 +24766,11 @@ VMOVLPD_128_XMM_M64(reg) 839fe4f382370cb6 after 53a226b7565ff134.0bebc66806d73a84.92a7d294d941d25f.dfb2f29e6c5cf095 - 8055f22c4271285b.146fa59c831b0fd4.4369ec7558d9715b.0f473703e711cd27 + 0000000000000000.0000000000000000.92a7d294d941d25f.dfb2f29e56721f0b ace25cdbbce1fada.33ab545e17cba181.0520e79a5748ce19.276d4fc12c694940 3197612e613aa45c.466a4f9adef0abb6.3217bf6d731b2444.04f1b4c256721f0b 839fe4f382370cb6 -VMOVLPD_128_XMM_M64(mem) +VMOVSS_REG_XMM_1of3(mem) before 7e435a41cbc4cc6a.6dbefe92cc08618e.277a123cf598eaa0.279b715b48ddb088 d3a992974e261b55.baa42e749ad76f1b.b4a51a3078ce1a6a.40f9f8d1711bae92 @@ -24778,13 +24778,13 @@ VMOVLPD_128_XMM_M64(mem) f6ea390a70975480.fbdd385eccab68f9.3d7fe6bf2f153b51.4e6e75013038efa8 fa1d6494fe2faa0b after - 7e435a41cbc4cc6a.6dbefe92cc08618e.277a123cf598eaa0.d97b50398a5f5a0e + 7e435a41cbc4cc6a.6dbefe92cc08618e.277a123cf598eaa0.279b715b48ddb088 d3a992974e261b55.baa42e749ad76f1b.b4a51a3078ce1a6a.40f9f8d1711bae92 5c9c08e02668b4a3.7695ed3e663408b0.c7b8e262829ef641.d97b50398a5f5a0e f6ea390a70975480.fbdd385eccab68f9.3d7fe6bf2f153b51.4e6e75013038efa8 fa1d6494fe2faa0b -VSHUFPD_128_1of2(reg) +VMOVSS_REG_XMM_2of3(reg) before 3bd6185e91d2c7e3.7d5da00047beb717.a7c8093f6ac6cda1.f2c6a2319c3ea5c5 6ce38dca85ac82dd.cec2b9aec7e99894.d4a15e4dd9137155.c35992a6e426f0ca @@ -24792,12 +24792,12 @@ VSHUFPD_128_1of2(reg) 0e2daa3efd36c0e6.3992f1e3357cc7f3.255182a0a0716890.2491004577601735 6dd07548facb6cf4 after - 0000000000000000.0000000000000000.2491004577601735.c35992a6e426f0ca + 3bd6185e91d2c7e3.7d5da00047beb717.a7c8093f6ac6cda1.f2c6a2319c3ea5c5 6ce38dca85ac82dd.cec2b9aec7e99894.d4a15e4dd9137155.c35992a6e426f0ca e992bf47744a16a5.c3e500000d24b425.dfb632f4b71e91c1.8a03330824d8d78b - 0e2daa3efd36c0e6.3992f1e3357cc7f3.255182a0a0716890.2491004577601735 + 0000000000000000.0000000000000000.d4a15e4dd9137155.c35992a69c3ea5c5 6dd07548facb6cf4 -VSHUFPD_128_1of2(mem) +VMOVSS_REG_XMM_2of3(mem) before 418a0efcc82492f3.36014b1cb9ffbc4d.0c9409415afd8d2d.00bf48bd2f9a346e 7c8b474ffe77445f.bf599d4d472e4586.18b9c30798b1c1fd.cd4c82b700252f09 @@ -24807,11 +24807,11 @@ VSHUFPD_128_1of2(mem) after 418a0efcc82492f3.36014b1cb9ffbc4d.0c9409415afd8d2d.00bf48bd2f9a346e 7c8b474ffe77445f.bf599d4d472e4586.18b9c30798b1c1fd.cd4c82b700252f09 - 0000000000000000.0000000000000000.00bf48bd2f9a346e.18b9c30798b1c1fd + faa19d2cb7d03f64.04839c3e4051983c.39cb9b220ca6208f.e8432bfbb09c960a 97978b80103c3e2c.60c9445942f3f11c.4b970d7dd2e76611.adf23ff3da8da420 79a3ba0d1b8496f5 -VSHUFPD_128_1of2(reg) +VMOVSS_REG_XMM_2of3(reg) before a6a499b30f0ba835.2f388d3524c7ffe6.3179910ce9a18bd1.2ae9960305814fac 913fd75350b1168e.9e5120380f7b3cbc.d2dd80c1d0e6a408.b28db1a2c17f968f @@ -24819,12 +24819,12 @@ VSHUFPD_128_1of2(reg) 1175602e2f83f435.711be5d9dd931c6e.f3f431e6cf653daa.2dfa8dd846d830d7 d85c4647474bfc96 after - 0000000000000000.0000000000000000.2dfa8dd846d830d7.b28db1a2c17f968f + a6a499b30f0ba835.2f388d3524c7ffe6.3179910ce9a18bd1.2ae9960305814fac 913fd75350b1168e.9e5120380f7b3cbc.d2dd80c1d0e6a408.b28db1a2c17f968f 96c170587dff1ba9.c0afbe76ee66b2db.9e420ce6934e766c.bf4fda4523edf8e4 - 1175602e2f83f435.711be5d9dd931c6e.f3f431e6cf653daa.2dfa8dd846d830d7 + 0000000000000000.0000000000000000.d2dd80c1d0e6a408.b28db1a205814fac d85c4647474bfc96 -VSHUFPD_128_1of2(mem) +VMOVSS_REG_XMM_2of3(mem) before 9c3f827e4152164a.5ea9a34105c8dddc.8d64104ff70f37a2.2b3fec2d20b8376e 5570bc6950fa3b22.d9a736fd985a124a.f055bbc358e5bfa3.a46e372721d39e63 @@ -24834,11 +24834,11 @@ VSHUFPD_128_1of2(mem) after 9c3f827e4152164a.5ea9a34105c8dddc.8d64104ff70f37a2.2b3fec2d20b8376e 5570bc6950fa3b22.d9a736fd985a124a.f055bbc358e5bfa3.a46e372721d39e63 - 0000000000000000.0000000000000000.2b3fec2d20b8376e.f055bbc358e5bfa3 + debb70f5924e2648.debd14ce86c6ce2d.76b963201d21709c.b8ce10406e40af36 15ec1a0c205a95e8.c93539216b974e2e.fa5e835461d005ba.c5ac72e5a48da593 255259805e46be25 -VSHUFPD_128_1of2(reg) +VMOVSS_REG_XMM_2of3(reg) before 350dc27e39f53498.d5ce379c182b422f.f55ca160e25acdfc.5a0e974a41fd3b28 5228a74cd128449a.fa2f428f96cce949.c07e49f9889a8941.71961beed9b4ce13 @@ -24846,12 +24846,12 @@ VSHUFPD_128_1of2(reg) 1eb2da04a54820f5.e299125391af19a4.a0e246e5cec1a3e1.335d64f19ef2fa0f 9735202703910b77 after - 0000000000000000.0000000000000000.335d64f19ef2fa0f.71961beed9b4ce13 + 350dc27e39f53498.d5ce379c182b422f.f55ca160e25acdfc.5a0e974a41fd3b28 5228a74cd128449a.fa2f428f96cce949.c07e49f9889a8941.71961beed9b4ce13 d6f10655c06b29d5.5fd9b7d3b5494861.85e62c56f8e3bca9.1bc28b2d43027aa7 - 1eb2da04a54820f5.e299125391af19a4.a0e246e5cec1a3e1.335d64f19ef2fa0f + 0000000000000000.0000000000000000.c07e49f9889a8941.71961bee41fd3b28 9735202703910b77 -VSHUFPD_128_1of2(mem) +VMOVSS_REG_XMM_2of3(mem) before 21143dbc91e9690d.86b920c7194d65a7.5d3bcffb4709193e.6cbc9311a7c17995 afc7379a6108cffb.6b50d209ba063497.ae8b6bb7f363035a.47c10f451e6e7b70 @@ -24861,11 +24861,11 @@ VSHUFPD_128_1of2(mem) after 21143dbc91e9690d.86b920c7194d65a7.5d3bcffb4709193e.6cbc9311a7c17995 afc7379a6108cffb.6b50d209ba063497.ae8b6bb7f363035a.47c10f451e6e7b70 - 0000000000000000.0000000000000000.6cbc9311a7c17995.ae8b6bb7f363035a + 1b1b88af91fafa6d.27c4ee3624fdc870.b0546173b0ca9425.8c3eb7efd055e51f 43d9aee63dcaa690.17616fbaf2c05edf.3e642d1b9a4988ca.967c867a5901f34e c3ca785354fee1a8 -VSHUFPD_128_2of2(reg) +VMOVSS_REG_XMM_3of3(reg) before 6e7389e45dd9eada.01d0242b80848f90.97725101c1db328f.36854b9cceed9b76 f2c2b69a111c4b8f.33cb666976347098.034591782cd97f2d.728437e067c08954 @@ -24873,12 +24873,12 @@ VSHUFPD_128_2of2(reg) f9865126e8100334.5ffc3f86eea80d72.0f5c17a247ae78e2.2a4c6b653a29e459 5dadaa7eacd6c9d7 after - 0000000000000000.0000000000000000.0f5c17a247ae78e2.728437e067c08954 + 0000000000000000.0000000000000000.0f5c17a247ae78e2.2a4c6b6567c08954 f2c2b69a111c4b8f.33cb666976347098.034591782cd97f2d.728437e067c08954 ad04fae20b563f74.b395f08f3ce706d5.b7242989cf468365.cf2d6ed482d10d91 f9865126e8100334.5ffc3f86eea80d72.0f5c17a247ae78e2.2a4c6b653a29e459 5dadaa7eacd6c9d7 -VSHUFPD_128_2of2(mem) +VMOVSS_REG_XMM_3of3(mem) before 451ba80bf3e37a38.3492b7d443d8d37c.11cacd3ba784409d.6739562d309e9a51 bf64dff72b5cb1a7.b8742856b83aebf8.a6cc189a83855c7f.1b07e29824a1275d @@ -24888,11 +24888,11 @@ VSHUFPD_128_2of2(mem) after 451ba80bf3e37a38.3492b7d443d8d37c.11cacd3ba784409d.6739562d309e9a51 bf64dff72b5cb1a7.b8742856b83aebf8.a6cc189a83855c7f.1b07e29824a1275d - 0000000000000000.0000000000000000.11cacd3ba784409d.a6cc189a83855c7f + a552cd30724e2a52.e27aa11ae4c08753.facd9c909fba1d46.8712b84ec24359b3 d4b2eda1e1c5a362.0fee1d8b63f8e23a.ea9bd307162c3f1e.07a6d3baa4116cff f60e2f4a66969eec -VSHUFPD_128_2of2(reg) +VMOVSS_REG_XMM_3of3(reg) before b297c869a55f2926.2850bb3796cbd605.991e9815d06d3959.50013bed05e97d33 968d9a83fcf74a5b.7ef8b4dcad6e8067.dd540e24c8acc75b.09ca4e2c87fc94b0 @@ -24900,12 +24900,12 @@ VSHUFPD_128_2of2(reg) 45f0db5964c43d60.9b9513076eb92817.0405dc82c6b67cba.e4b86b6ab6563d94 be756b409bb44652 after - 0000000000000000.0000000000000000.0405dc82c6b67cba.09ca4e2c87fc94b0 + 0000000000000000.0000000000000000.0405dc82c6b67cba.e4b86b6a87fc94b0 968d9a83fcf74a5b.7ef8b4dcad6e8067.dd540e24c8acc75b.09ca4e2c87fc94b0 fe3ca20508ea3d35.b075527d41b95cb4.38dd7c24e640caec.f1c38bb2b97240c1 45f0db5964c43d60.9b9513076eb92817.0405dc82c6b67cba.e4b86b6ab6563d94 be756b409bb44652 -VSHUFPD_128_2of2(mem) +VMOVSS_REG_XMM_3of3(mem) before 5bc608208398182a.c9f541ecad128789.1b22726451799ebc.9e182ca80598196e 9776bdf68b0f6e46.e596d02b7e60575c.0ce9ec8205057bd0.626167043e74dfb7 @@ -24915,11 +24915,11 @@ VSHUFPD_128_2of2(mem) after 5bc608208398182a.c9f541ecad128789.1b22726451799ebc.9e182ca80598196e 9776bdf68b0f6e46.e596d02b7e60575c.0ce9ec8205057bd0.626167043e74dfb7 - 0000000000000000.0000000000000000.1b22726451799ebc.0ce9ec8205057bd0 + 4e5306aece2506d2.f42184817338e984.4ab6fb4ba7697a7f.ac2e8a000ed6083f 5c27603568e49afb.54e05a59292878ae.b1551dad53b258f5.d8c98f0a1148d1b2 437f748de15876be -VSHUFPD_128_2of2(reg) +VMOVSS_REG_XMM_3of3(reg) before 479c34f41d92320c.9dbf4575775ae7ed.60204d213cbb4186.1d92cd9323ecd15d 416cccad5e81424b.ede7335c1493a8d4.732d5944477e80b7.6a3887e93621a1e3 @@ -24927,12 +24927,12 @@ VSHUFPD_128_2of2(reg) 875470c265ae4d46.2a1617cb6d7a792e.22ddad4bb6c14ed6.16f30a958eb234fc 2e9fcbc40d2470e6 after - 0000000000000000.0000000000000000.22ddad4bb6c14ed6.6a3887e93621a1e3 + 0000000000000000.0000000000000000.22ddad4bb6c14ed6.16f30a953621a1e3 416cccad5e81424b.ede7335c1493a8d4.732d5944477e80b7.6a3887e93621a1e3 8d3a362343b1e225.286ba5d45d999adb.eb527b2ee6fc70ee.7415c89ba55f83b4 875470c265ae4d46.2a1617cb6d7a792e.22ddad4bb6c14ed6.16f30a958eb234fc 2e9fcbc40d2470e6 -VSHUFPD_128_2of2(mem) +VMOVSS_REG_XMM_3of3(mem) before 97e586123dc3f39f.8a0475f76205c05c.cfb6062c614201fa.7518ed07535a561c 2d91b86c3b9b7853.f497412cd6417710.f315ede355fbed6b.415036ce5852c46b @@ -24942,11 +24942,11 @@ VSHUFPD_128_2of2(mem) after 97e586123dc3f39f.8a0475f76205c05c.cfb6062c614201fa.7518ed07535a561c 2d91b86c3b9b7853.f497412cd6417710.f315ede355fbed6b.415036ce5852c46b - 0000000000000000.0000000000000000.cfb6062c614201fa.f315ede355fbed6b + cb6edbbf22b6bc2d.2059d0ce5cefae11.710047dc63b3faac.e0d2840d6135d370 4f4a6df60e227b5a.6a961f4a9199a009.27439303aa76e4ea.b0e7d42e0b90c0d7 0bde209ff1eec74b -VSHUFPD_256_1of2(reg) +VMOVLPD_128_M64_XMM_XMM(reg) before 4e0266cab0db2379.94efe9fc1ceb7005.2e9a280a10ce8ba4.f0aa4a44444e6751 d59ea11de3e4110c.752acbbf681b585b.c8b0e97c7517a88f.a701e98b4d493e0c @@ -24954,12 +24954,12 @@ VSHUFPD_256_1of2(reg) 2072e7e817779314.8092b22927e6f1b7.ed468123631a6f04.53aed1dc1ed6db30 009c12be1d8118f1 after - 8092b22927e6f1b7.752acbbf681b585b.53aed1dc1ed6db30.a701e98b4d493e0c + 4e0266cab0db2379.94efe9fc1ceb7005.2e9a280a10ce8ba4.f0aa4a44444e6751 d59ea11de3e4110c.752acbbf681b585b.c8b0e97c7517a88f.a701e98b4d493e0c fd00ce032794cdb2.d0c7902a0dc1ef87.93265e0b5d023676.2a13edc5e2732648 2072e7e817779314.8092b22927e6f1b7.ed468123631a6f04.53aed1dc1ed6db30 009c12be1d8118f1 -VSHUFPD_256_1of2(mem) +VMOVLPD_128_M64_XMM_XMM(mem) before 0caa2a56fc7d9ab6.9b41ea384f1a9ee0.6056afa8d3981914.315d503024ec90e6 52a4978fd7d81dac.cab8d25f6d082bc2.4ee102932de224cd.bab7c69e3c03d5c8 @@ -24969,11 +24969,11 @@ VSHUFPD_256_1of2(mem) after 0caa2a56fc7d9ab6.9b41ea384f1a9ee0.6056afa8d3981914.315d503024ec90e6 52a4978fd7d81dac.cab8d25f6d082bc2.4ee102932de224cd.bab7c69e3c03d5c8 - 0caa2a56fc7d9ab6.52a4978fd7d81dac.6056afa8d3981914.4ee102932de224cd + 0000000000000000.0000000000000000.4ee102932de224cd.315d503024ec90e6 008b5d99efd815da.b4d342e2c4f6bb77.c0779b5e586fd2fd.0f63974dde30b93a 934deb67a15fd122 -VSHUFPD_256_1of2(reg) +VMOVLPD_128_M64_XMM_XMM(reg) before ccabd5912a04fdba.1f11ae416496026a.270dc117370e35a1.fc1bd91661caedcd 18c7533815a978ad.eab2443b44e2e0db.be2016d2fea12191.b5b55ce989eedba8 @@ -24981,12 +24981,12 @@ VSHUFPD_256_1of2(reg) 556cf9af84284e57.ef782bd6b7565d0d.c801308ff96a3e73.0ffa27959fbe1f2d 673e6644c782ed2f after - ef782bd6b7565d0d.eab2443b44e2e0db.0ffa27959fbe1f2d.b5b55ce989eedba8 + ccabd5912a04fdba.1f11ae416496026a.270dc117370e35a1.fc1bd91661caedcd 18c7533815a978ad.eab2443b44e2e0db.be2016d2fea12191.b5b55ce989eedba8 d1ee61c900dc7fa8.3b3b9973acc96a58.d5583c81b53cbaf3.c811a3c5e9e558b9 556cf9af84284e57.ef782bd6b7565d0d.c801308ff96a3e73.0ffa27959fbe1f2d 673e6644c782ed2f -VSHUFPD_256_1of2(mem) +VMOVLPD_128_M64_XMM_XMM(mem) before ada7dac07c3f7eec.fe8c19563f1a2065.e335754e82957528.f367ec6765b8e7bb bb0201f4db008d90.2a9cbb2acd3d327f.f13ef4c929926ed2.b2d56e7796b1f27a @@ -24996,11 +24996,11 @@ VSHUFPD_256_1of2(mem) after ada7dac07c3f7eec.fe8c19563f1a2065.e335754e82957528.f367ec6765b8e7bb bb0201f4db008d90.2a9cbb2acd3d327f.f13ef4c929926ed2.b2d56e7796b1f27a - ada7dac07c3f7eec.bb0201f4db008d90.e335754e82957528.f13ef4c929926ed2 + 0000000000000000.0000000000000000.f13ef4c929926ed2.f367ec6765b8e7bb a2be563504c0183b.76b77b09d0470686.ce627d7478f8f18a.5cfdb1ecb5d41c08 fe4e6a29db17b42f -VSHUFPD_256_1of2(reg) +VMOVLPD_128_M64_XMM_XMM(reg) before a5d8d94e36359e7c.33b67c1907d60c9a.4f5b8fec7d463fca.5517807d5879f4ef ace7f9c561bb159b.fdd1446624206e90.1b1e17ac6ca6a8cb.6747a83885e8c894 @@ -25008,12 +25008,12 @@ VSHUFPD_256_1of2(reg) 49c33c5d992c9dfd.ac9baae719836ff0.f730707482bbfaae.9d4a53742fc1d150 78b6cfcde6437ebf after - ac9baae719836ff0.fdd1446624206e90.9d4a53742fc1d150.6747a83885e8c894 + a5d8d94e36359e7c.33b67c1907d60c9a.4f5b8fec7d463fca.5517807d5879f4ef ace7f9c561bb159b.fdd1446624206e90.1b1e17ac6ca6a8cb.6747a83885e8c894 6ec7c6fbf9345737.dcd92a0676abfb49.344c0eb53af47d32.e0bf6f91185128a6 49c33c5d992c9dfd.ac9baae719836ff0.f730707482bbfaae.9d4a53742fc1d150 78b6cfcde6437ebf -VSHUFPD_256_1of2(mem) +VMOVLPD_128_M64_XMM_XMM(mem) before 4ecd5f8858e3ed1f.98285855de302698.49e341f32ab286b2.c0183953e1885ae9 fa5c7f91a2add89b.b643145163ca2cb5.8f7d6918c446fbba.eb4e66c0f2e5da8f @@ -25023,11 +25023,11 @@ VSHUFPD_256_1of2(mem) after 4ecd5f8858e3ed1f.98285855de302698.49e341f32ab286b2.c0183953e1885ae9 fa5c7f91a2add89b.b643145163ca2cb5.8f7d6918c446fbba.eb4e66c0f2e5da8f - 4ecd5f8858e3ed1f.fa5c7f91a2add89b.49e341f32ab286b2.8f7d6918c446fbba + 0000000000000000.0000000000000000.8f7d6918c446fbba.c0183953e1885ae9 4913613e2bf21499.d3c561029ef6a223.86d6625a05cbf14f.d7d7d9f19d8529cf 50c2178d6ddf70c1 -VSHUFPD_256_2of2(reg) +VMOVLPD_128_XMM_M64(reg) before 9b2ba96660fac6ce.a3d11abaa383dd73.8ac6ea8f8d9f89cd.ef2e294fe4d4eb33 146089e8126269a2.44385334636f1319.80ac03cf2c0fdfa8.7107730cbc71330e @@ -25035,12 +25035,12 @@ VSHUFPD_256_2of2(reg) 00592897214b8152.cb2d36d12886b57c.9d55da18eb76c2a4.306f7d8fc9999f57 2496352c363b3c1e after - 00592897214b8152.44385334636f1319.9d55da18eb76c2a4.7107730cbc71330e + 9b2ba96660fac6ce.a3d11abaa383dd73.8ac6ea8f8d9f89cd.ef2e294fe4d4eb33 146089e8126269a2.44385334636f1319.80ac03cf2c0fdfa8.7107730cbc71330e 17abb57f1ea493eb.0812899885c272b8.13c2aa2e17d3dd61.e82ebb7eaaaf860b 00592897214b8152.cb2d36d12886b57c.9d55da18eb76c2a4.306f7d8fc9999f57 2496352c363b3c1e -VSHUFPD_256_2of2(mem) +VMOVLPD_128_XMM_M64(mem) before a26e60420ca2168b.2bb6df9db6e46f86.6853d8cd66c99991.7cb18ffa4384c81c 85c578bc67d9ecca.f40ed4fb79f99831.bd51ea785b97da21.0a22c63ebc8a2c75 @@ -25048,13 +25048,13 @@ VSHUFPD_256_2of2(mem) e91b648b1fe87872.cfde6d73fccd8e9d.fb044f86dc006269.a673a6a07fabfe7e 6dea499601dfe384 after - a26e60420ca2168b.2bb6df9db6e46f86.6853d8cd66c99991.7cb18ffa4384c81c + a26e60420ca2168b.2bb6df9db6e46f86.6853d8cd66c99991.a4f47a52f1132a5d 85c578bc67d9ecca.f40ed4fb79f99831.bd51ea785b97da21.0a22c63ebc8a2c75 - 2bb6df9db6e46f86.85c578bc67d9ecca.7cb18ffa4384c81c.bd51ea785b97da21 + a865fb8564ec7909.b7ad051f081939ff.a5f3e9bc24fa345b.a4f47a52f1132a5d e91b648b1fe87872.cfde6d73fccd8e9d.fb044f86dc006269.a673a6a07fabfe7e 6dea499601dfe384 -VSHUFPD_256_2of2(reg) +VMOVLPD_128_XMM_M64(reg) before 53a65c9f143a161c.23b330b9b3d8a631.9aef0865f3a3d3b7.9d529ac2a0b52178 b5f3dc275348d2f2.31f9dafb3cc9be73.732ad360882643f8.66a7455d8b242db3 @@ -25062,12 +25062,12 @@ VSHUFPD_256_2of2(reg) 5d701564c7afd906.3dbeb76b9fda9f2f.be51e521ff6597a2.dc9aac5c48601a60 41ce609951467429 after - 5d701564c7afd906.31f9dafb3cc9be73.be51e521ff6597a2.66a7455d8b242db3 + 53a65c9f143a161c.23b330b9b3d8a631.9aef0865f3a3d3b7.9d529ac2a0b52178 b5f3dc275348d2f2.31f9dafb3cc9be73.732ad360882643f8.66a7455d8b242db3 ef1dc69a5b9655b1.f1b8dd3dd7c57d64.b5dcc8d058e31b0d.31d1cc41ba594147 5d701564c7afd906.3dbeb76b9fda9f2f.be51e521ff6597a2.dc9aac5c48601a60 41ce609951467429 -VSHUFPD_256_2of2(mem) +VMOVLPD_128_XMM_M64(mem) before 3e3b63e4f2160bce.5b38c5f134209a9c.f3d5e472b114e001.e9d525bf1738f262 adac342947dc9a7d.46c0d3ad3d73d620.edcade3c287efc06.91b385173fe869fa @@ -25075,13 +25075,13 @@ VSHUFPD_256_2of2(mem) 55c928517a7c93a3.4e44f56394f5aaa1.217e2ecdb712b356.ccb191a029119b60 176836ab23a2cd86 after - 3e3b63e4f2160bce.5b38c5f134209a9c.f3d5e472b114e001.e9d525bf1738f262 + 3e3b63e4f2160bce.5b38c5f134209a9c.f3d5e472b114e001.1439ff9310023815 adac342947dc9a7d.46c0d3ad3d73d620.edcade3c287efc06.91b385173fe869fa - 5b38c5f134209a9c.adac342947dc9a7d.e9d525bf1738f262.edcade3c287efc06 + 6bec4c546ba5de5f.785639057e36c73e.096923b72124ae69.1439ff9310023815 55c928517a7c93a3.4e44f56394f5aaa1.217e2ecdb712b356.ccb191a029119b60 176836ab23a2cd86 -VSHUFPD_256_2of2(reg) +VMOVLPD_128_XMM_M64(reg) before 4faaea1e9d400b34.450d450c916e7473.24d702351a3bbbf6.12d57b6c0755c6fb d2c3aa6730779116.18851e71cc863efc.555b5de5ad9435e8.b939867f2cf8a481 @@ -25089,12 +25089,12 @@ VSHUFPD_256_2of2(reg) 24a93a2817e26324.d840f5ea1b587de7.3d65e99469b05755.945cc8b16790b1e7 81b2f6a8b49c581e after - 24a93a2817e26324.18851e71cc863efc.3d65e99469b05755.b939867f2cf8a481 + 4faaea1e9d400b34.450d450c916e7473.24d702351a3bbbf6.12d57b6c0755c6fb d2c3aa6730779116.18851e71cc863efc.555b5de5ad9435e8.b939867f2cf8a481 faff70f17ad49ad7.abfc2f6d45d0ad69.3f1c00e1e98c5524.f078ccf243080a17 24a93a2817e26324.d840f5ea1b587de7.3d65e99469b05755.945cc8b16790b1e7 81b2f6a8b49c581e -VSHUFPD_256_2of2(mem) +VMOVLPD_128_XMM_M64(mem) before 9346d2c34838b9e7.ad0e0378a22d28a9.7c1cead6682b69a1.ab84136ac98b7629 a7e4d8ee3c71916f.ef7bc74db7422511.735b8c1c48552ec4.e5c37acfa6aaf049 @@ -25102,13 +25102,13 @@ VSHUFPD_256_2of2(mem) 406d5425b9e8956a.11973236f2f7b53b.ca35c56533da33f4.2cd4f0f645e1df24 f23ef7913f11ce35 after - 9346d2c34838b9e7.ad0e0378a22d28a9.7c1cead6682b69a1.ab84136ac98b7629 + 9346d2c34838b9e7.ad0e0378a22d28a9.7c1cead6682b69a1.476f1a2f9b98ff64 a7e4d8ee3c71916f.ef7bc74db7422511.735b8c1c48552ec4.e5c37acfa6aaf049 - ad0e0378a22d28a9.a7e4d8ee3c71916f.ab84136ac98b7629.735b8c1c48552ec4 + 97578515ae529be1.473a8313f3ac9508.99ca56a7d8e0887c.476f1a2f9b98ff64 406d5425b9e8956a.11973236f2f7b53b.ca35c56533da33f4.2cd4f0f645e1df24 f23ef7913f11ce35 -VPERMILPS_128_0x00(reg) +VSHUFPD_128_1of2(reg) before f4f82b6a25b50644.7ef0c1087a3e3936.aae0d0234fb0c156.e3685341754eea59 8d5088ef9558c4fd.2dad49ac0d604470.6c605944a662f405.be2f7e27bc496ad6 @@ -25116,12 +25116,12 @@ VPERMILPS_128_0x00(reg) f905aea97ccdc01b.4e0596e3163a7de0.de331dd6b4e2c2cc.2da898c2c201b4cb 79f27f4ebbd7f69a after - f4f82b6a25b50644.7ef0c1087a3e3936.aae0d0234fb0c156.e3685341754eea59 - 0000000000000000.0000000000000000.21d66e9821d66e98.21d66e9821d66e98 + 0000000000000000.0000000000000000.2da898c2c201b4cb.be2f7e27bc496ad6 + 8d5088ef9558c4fd.2dad49ac0d604470.6c605944a662f405.be2f7e27bc496ad6 1b900b8a2887430b.297066fc8d5b7145.b462c90794998bf3.3855c10321d66e98 f905aea97ccdc01b.4e0596e3163a7de0.de331dd6b4e2c2cc.2da898c2c201b4cb 79f27f4ebbd7f69a -VPERMILPS_128_0x00(mem) +VSHUFPD_128_1of2(mem) before f700f3942763f132.82fb6fb72db677d9.7838544fc509246e.461f4f1fa3c8d53e 859e6f8122b160be.14be4a20d6cfa4f0.83d41c2bb5d5221b.48725e4dfcd8fff2 @@ -25130,12 +25130,12 @@ VPERMILPS_128_0x00(mem) 82cc836d9f76655e after f700f3942763f132.82fb6fb72db677d9.7838544fc509246e.461f4f1fa3c8d53e - 0000000000000000.0000000000000000.a3c8d53ea3c8d53e.a3c8d53e461f4f1f - fe986f00c9cd006b.099a395013a3830d.4ba76b6303a93212.407843cc5c9c7d97 + 859e6f8122b160be.14be4a20d6cfa4f0.83d41c2bb5d5221b.48725e4dfcd8fff2 + 0000000000000000.0000000000000000.461f4f1fa3c8d53e.83d41c2bb5d5221b 3eb96ffc38c48d65.bfda39b381be4fdb.ac7bbbe3ca91117f.8a7dfb085ea38bd7 82cc836d9f76655e -VPERMILPS_128_0x00(reg) +VSHUFPD_128_1of2(reg) before 84b3d667baa346d9.21cfec638aa2c3d7.90cc47b5bcac4507.811d8a98279a7b90 ec7cf0634cb56bf4.83a46020db715ded.d9ba5ec25efaa03c.a859536c35cf2c6f @@ -25143,12 +25143,12 @@ VPERMILPS_128_0x00(reg) 5ee76a0d42b970b9.33be224cec18b0b9.44bd98ae4ee47974.59cec425d5ee5148 9aa064e2a0f03e9b after - 84b3d667baa346d9.21cfec638aa2c3d7.90cc47b5bcac4507.811d8a98279a7b90 - 0000000000000000.0000000000000000.103cdf48103cdf48.103cdf48103cdf48 + 0000000000000000.0000000000000000.59cec425d5ee5148.a859536c35cf2c6f + ec7cf0634cb56bf4.83a46020db715ded.d9ba5ec25efaa03c.a859536c35cf2c6f 1674cdcbf038105b.3f05491f484018d5.f7f17b4606349e27.fcfb924d103cdf48 5ee76a0d42b970b9.33be224cec18b0b9.44bd98ae4ee47974.59cec425d5ee5148 9aa064e2a0f03e9b -VPERMILPS_128_0x00(mem) +VSHUFPD_128_1of2(mem) before 9d3bee6e8c4e616c.1f20c293dfc3c8ba.3a9b6893e407e1c5.1e6ab364d2986dce 3d6cdeb7b51577e8.b76dd1cb63e3540b.2f6895e14b186626.df43c7d62fdcb8e2 @@ -25157,12 +25157,12 @@ VPERMILPS_128_0x00(mem) 2ad5b2c6707af12f after 9d3bee6e8c4e616c.1f20c293dfc3c8ba.3a9b6893e407e1c5.1e6ab364d2986dce - 0000000000000000.0000000000000000.d2986dced2986dce.d2986dce1e6ab364 - 55ffb0a838503c3b.8118932069a44f58.f0f027203e57fc08.e496d06f003a945b + 3d6cdeb7b51577e8.b76dd1cb63e3540b.2f6895e14b186626.df43c7d62fdcb8e2 + 0000000000000000.0000000000000000.1e6ab364d2986dce.2f6895e14b186626 c3c0e12d310b6c90.d96e04fd8d92f74c.5801993dd8d15f96.89adca9be2403ee6 2ad5b2c6707af12f -VPERMILPS_128_0x00(reg) +VSHUFPD_128_1of2(reg) before 245a825c4673ebe1.617aec32bb53c214.1abb21d06c3a8694.4265672536914afd d18838c901b766a9.0dfb4da4f233fbf2.a24be504a22638dc.8ce90ec373a37a69 @@ -25170,12 +25170,12 @@ VPERMILPS_128_0x00(reg) b70e44d89551d129.fb7d027ad9ec056e.f36452408000f91a.ac81d3d0fbef99fe 3a2cea187f41ff7f after - 245a825c4673ebe1.617aec32bb53c214.1abb21d06c3a8694.4265672536914afd - 0000000000000000.0000000000000000.ab14ab05ab14ab05.ab14ab05ab14ab05 + 0000000000000000.0000000000000000.ac81d3d0fbef99fe.8ce90ec373a37a69 + d18838c901b766a9.0dfb4da4f233fbf2.a24be504a22638dc.8ce90ec373a37a69 8eabcf793dd29f32.a10d806df3b8d357.cb6a4c06c9e54bcf.10590802ab14ab05 b70e44d89551d129.fb7d027ad9ec056e.f36452408000f91a.ac81d3d0fbef99fe 3a2cea187f41ff7f -VPERMILPS_128_0x00(mem) +VSHUFPD_128_1of2(mem) before 9728cac652149ab5.a8ff9253a5bf393a.f5174db8c1dd4e64.7584f41f60057f68 a03fedc6907726cb.bdc8b4540aa81310.6ca7df11c6976a65.ac172d10087f1866 @@ -25184,12 +25184,12 @@ VPERMILPS_128_0x00(mem) 2e7a3a80bc26b335 after 9728cac652149ab5.a8ff9253a5bf393a.f5174db8c1dd4e64.7584f41f60057f68 - 0000000000000000.0000000000000000.60057f6860057f68.60057f687584f41f - 2f3ed10556735eee.52b6a94960999b58.3df933730525159c.f669f97d11fb02bf + a03fedc6907726cb.bdc8b4540aa81310.6ca7df11c6976a65.ac172d10087f1866 + 0000000000000000.0000000000000000.7584f41f60057f68.6ca7df11c6976a65 21f1f16dc016ff4a.c3156a9c421d0cbd.42d8c6c999930a36.adc654d41a047720 2e7a3a80bc26b335 -VPERMILPS_128_0xFE(reg) +VSHUFPD_128_2of2(reg) before d6d1a8ec95eef4a9.5324c9ebe96bc50a.6c30f4bb4cc1a3ec.581212ff9eed065f ff16998641e77429.9fa3d66ced7f6c5b.a95544111b0f9c91.5c7195013240c542 @@ -25197,12 +25197,12 @@ VPERMILPS_128_0xFE(reg) 489ef4f17f9d23fc.f8b37b23f8114b5e.4ee9231276dfa3eb.99d12d1970ff7ae7 8b6a3b075483e902 after - d6d1a8ec95eef4a9.5324c9ebe96bc50a.6c30f4bb4cc1a3ec.581212ff9eed065f - 0000000000000000.0000000000000000.d5ce550ad5ce550a.d5ce550a4a963357 + 0000000000000000.0000000000000000.4ee9231276dfa3eb.5c7195013240c542 + ff16998641e77429.9fa3d66ced7f6c5b.a95544111b0f9c91.5c7195013240c542 079709b95b9d7061.e23992dae95caf68.d5ce550a4a963357.28c2cabb6e97020b 489ef4f17f9d23fc.f8b37b23f8114b5e.4ee9231276dfa3eb.99d12d1970ff7ae7 8b6a3b075483e902 -VPERMILPS_128_0xFE(mem) +VSHUFPD_128_2of2(mem) before da586f71352f0b88.1f78569a4a72cba6.bdde0c3237a7fc69.6ff0ab953a7829f8 626944442f109ba4.e8712c2158a8a20c.0e84c1f3c12c7eb4.9430e7ff33ec012b @@ -25211,12 +25211,12 @@ VPERMILPS_128_0xFE(mem) b23db4e070e5ca5e after da586f71352f0b88.1f78569a4a72cba6.bdde0c3237a7fc69.6ff0ab953a7829f8 - 0000000000000000.0000000000000000.bdde0c32bdde0c32.bdde0c32bdde0c32 - ff67396a5f315682.ffd471f044cce5da.c5721752b3ab8c6c.18f4d5bdfcc86630 + 626944442f109ba4.e8712c2158a8a20c.0e84c1f3c12c7eb4.9430e7ff33ec012b + 0000000000000000.0000000000000000.bdde0c3237a7fc69.0e84c1f3c12c7eb4 8e1fc7d1e09ef850.c1ef2175aa69cfbc.bf73893b2831e3bc.598a7039329795b2 b23db4e070e5ca5e -VPERMILPS_128_0xFE(reg) +VSHUFPD_128_2of2(reg) before 7e589e1f533e40df.e95d6b64cf633d37.880c391a270b9d5d.d855939a3cc93ed1 1b282961762f35e2.eceda20e488de066.b179b34d563f8b69.ece2b15b0c7f5bd7 @@ -25224,12 +25224,12 @@ VPERMILPS_128_0xFE(reg) 3417129ded07861c.5f32b65c453e3246.996ec2093c8bb675.75311ab44f77c664 a18a5d24fad08c43 after - 7e589e1f533e40df.e95d6b64cf633d37.880c391a270b9d5d.d855939a3cc93ed1 - 0000000000000000.0000000000000000.98808d7998808d79.98808d79d490d58e + 0000000000000000.0000000000000000.996ec2093c8bb675.ece2b15b0c7f5bd7 + 1b282961762f35e2.eceda20e488de066.b179b34d563f8b69.ece2b15b0c7f5bd7 e3f950127543e312.759be7bd65289e07.98808d79d490d58e.d7e85f6bb460f4f9 3417129ded07861c.5f32b65c453e3246.996ec2093c8bb675.75311ab44f77c664 a18a5d24fad08c43 -VPERMILPS_128_0xFE(mem) +VSHUFPD_128_2of2(mem) before 39bea4a5d07803c3.68ce68707a065cac.86808cd701dd5a50.108e4e6b2bba6bcd 189b6b25ed7ae710.dd6950f7b7cc9f6d.c64fe41bb811d051.592e2e0a3cab3040 @@ -25238,12 +25238,12 @@ VPERMILPS_128_0xFE(mem) b8fe988e577f35f6 after 39bea4a5d07803c3.68ce68707a065cac.86808cd701dd5a50.108e4e6b2bba6bcd - 0000000000000000.0000000000000000.86808cd786808cd7.86808cd786808cd7 - 1aeb2e8f6ee2f455.ed36c49c40e68c0c.fb6c391283e45175.d0995d520cea407a + 189b6b25ed7ae710.dd6950f7b7cc9f6d.c64fe41bb811d051.592e2e0a3cab3040 + 0000000000000000.0000000000000000.86808cd701dd5a50.c64fe41bb811d051 1b7c6acf6ebde5bf.f67fc2ccb2df5e35.01a309a9806498e6.d11ad6b03602d928 b8fe988e577f35f6 -VPERMILPS_128_0xFE(reg) +VSHUFPD_128_2of2(reg) before e1919c590aed9090.f6189ad10a167779.529146f3a8435393.b3c0d0cdcb9d63d3 a71fe07eebd928a1.898c3a815df966b0.5eb84a7ebf9fa5d2.ef8e08687f996b66 @@ -25251,12 +25251,12 @@ VPERMILPS_128_0xFE(reg) 7f5b1482aa59fad9.432bbb9b9a8f4a44.f774c76cbe6c52a6.7171c0b894102a30 701d37432ca157bf after - e1919c590aed9090.f6189ad10a167779.529146f3a8435393.b3c0d0cdcb9d63d3 - 0000000000000000.0000000000000000.7740ccd77740ccd7.7740ccd7927e91a0 + 0000000000000000.0000000000000000.f774c76cbe6c52a6.ef8e08687f996b66 + a71fe07eebd928a1.898c3a815df966b0.5eb84a7ebf9fa5d2.ef8e08687f996b66 68f35e6797ce37d5.afa4c7cb84736e8f.7740ccd7927e91a0.90db2f68b9666fcc 7f5b1482aa59fad9.432bbb9b9a8f4a44.f774c76cbe6c52a6.7171c0b894102a30 701d37432ca157bf -VPERMILPS_128_0xFE(mem) +VSHUFPD_128_2of2(mem) before 68ab11f79e28b3a5.48a1fe3abf05ac59.23ef94debc59b7f8.3ba237a8def62593 34e7c8bf05aef90d.1e1316fb725e8a00.2abacd7e05de71da.a01418f68fa74611 @@ -25265,12 +25265,12 @@ VPERMILPS_128_0xFE(mem) 24003b8e1c1ed3ad after 68ab11f79e28b3a5.48a1fe3abf05ac59.23ef94debc59b7f8.3ba237a8def62593 - 0000000000000000.0000000000000000.23ef94de23ef94de.23ef94de23ef94de - b29cda877e41e623.5ffb5a3160f0d07b.335ae26992293313.801767c46c0bf1cd + 34e7c8bf05aef90d.1e1316fb725e8a00.2abacd7e05de71da.a01418f68fa74611 + 0000000000000000.0000000000000000.23ef94debc59b7f8.2abacd7e05de71da bc98c23c25ec3615.66a6c5482448ba76.1c9950897e46bad2.38f71e7d12af6172 24003b8e1c1ed3ad -VPERMILPS_128_0x30(reg) +VSHUFPD_256_1of2(reg) before a07dba6126e48329.30a5fcc814bba50d.8e5f53ac5bf2849c.bf4491cce642c241 08bc9563cd8eac93.e89005186abbef37.357400c9a178699a.fa26231de528078d @@ -25278,12 +25278,12 @@ VPERMILPS_128_0x30(reg) 0cac54a561bc5ce0.983071b5b57c02d4.6cdea8dfc74d76cc.a3c3289919e4366a cb16929c87d19953 after - a07dba6126e48329.30a5fcc814bba50d.8e5f53ac5bf2849c.bf4491cce642c241 - 0000000000000000.0000000000000000.970544e1b52fc80c.970544e1970544e1 + 983071b5b57c02d4.e89005186abbef37.a3c3289919e4366a.fa26231de528078d + 08bc9563cd8eac93.e89005186abbef37.357400c9a178699a.fa26231de528078d b807ca00ada78c97.c225581940f7cfc0.b52fc80c9068a51b.a70d8168970544e1 0cac54a561bc5ce0.983071b5b57c02d4.6cdea8dfc74d76cc.a3c3289919e4366a cb16929c87d19953 -VPERMILPS_128_0x30(mem) +VSHUFPD_256_1of2(mem) before f9d03d5dfcd828c9.60f52fbc85575b1b.477dccdae254439e.b4cb9bb0dfb41658 0abea4c99406a0f8.102e57b3b607c4f3.acd7e573e68e4f4b.eb439de97628c26c @@ -25292,12 +25292,12 @@ VPERMILPS_128_0x30(mem) bae4d7454b4c658e after f9d03d5dfcd828c9.60f52fbc85575b1b.477dccdae254439e.b4cb9bb0dfb41658 - 0000000000000000.0000000000000000.dfb41658dfb41658.dfb41658477dccda - dbac43ca6c66bd0b.78a5c8f59055d215.a10c396cda33e306.6b91abf82835b6b4 + 0abea4c99406a0f8.102e57b3b607c4f3.acd7e573e68e4f4b.eb439de97628c26c + f9d03d5dfcd828c9.0abea4c99406a0f8.477dccdae254439e.acd7e573e68e4f4b 4665964d9f053b2f.f4a57feeadcfc12c.03e642b1dc51b8fc.9203bf4890682edb bae4d7454b4c658e -VPERMILPS_128_0x30(reg) +VSHUFPD_256_1of2(reg) before 407fee5bf46d9878.28b71a3f4aeed590.e079770aac00cfe6.ae327f2e08f38d59 812101f627580247.5d6c4a8b882d4859.976eacb5277536ec.7fbc69cf79261c48 @@ -25305,12 +25305,12 @@ VPERMILPS_128_0x30(reg) 9faa076b9eb96f3d.31329ee02fdea9d4.dbebbe6801580293.feb9382d9b6c5a8e 65c515c38597823d after - 407fee5bf46d9878.28b71a3f4aeed590.e079770aac00cfe6.ae327f2e08f38d59 - 0000000000000000.0000000000000000.4bf522f677d11b5b.4bf522f64bf522f6 + 31329ee02fdea9d4.5d6c4a8b882d4859.feb9382d9b6c5a8e.7fbc69cf79261c48 + 812101f627580247.5d6c4a8b882d4859.976eacb5277536ec.7fbc69cf79261c48 d7160a828198e0a4.c151a21d76ce50b6.77d11b5bbab833ed.50507d804bf522f6 9faa076b9eb96f3d.31329ee02fdea9d4.dbebbe6801580293.feb9382d9b6c5a8e 65c515c38597823d -VPERMILPS_128_0x30(mem) +VSHUFPD_256_1of2(mem) before 613e902c2483542f.3529f31d1948e8be.87dbbbc2d0680edf.1f0b93489adede8a cef12556943b8d8f.f5deca058ed08ad3.a01874ae74793c03.9e7c95681ed8047f @@ -25319,12 +25319,12 @@ VPERMILPS_128_0x30(mem) 1dab83794ff28908 after 613e902c2483542f.3529f31d1948e8be.87dbbbc2d0680edf.1f0b93489adede8a - 0000000000000000.0000000000000000.9adede8a9adede8a.9adede8a87dbbbc2 - 88aa512cf2cce88a.3c17888d9add8f27.58b44591381cee6b.b689c0322bd1b01e + cef12556943b8d8f.f5deca058ed08ad3.a01874ae74793c03.9e7c95681ed8047f + 613e902c2483542f.cef12556943b8d8f.87dbbbc2d0680edf.a01874ae74793c03 6b358f995941224b.641e2a23d8fc3466.8b7daa55375de243.c28011145d561e12 1dab83794ff28908 -VPERMILPS_128_0x30(reg) +VSHUFPD_256_1of2(reg) before 255712cc9e312eac.535e5b8be6a6f7ff.ca40ab32e5b8b53d.153d1fe78d49d2b8 34d0ba7be59f49a9.1cf031edb40823d2.cac907265c9d4d58.d2c1213457eb7bf6 @@ -25332,12 +25332,12 @@ VPERMILPS_128_0x30(reg) db58469acc3bcf60.c183ecb285f06e83.083f406dfa14b509.5445b9abb682e67b d2dc47ae828f211b after - 255712cc9e312eac.535e5b8be6a6f7ff.ca40ab32e5b8b53d.153d1fe78d49d2b8 - 0000000000000000.0000000000000000.b14f9828c0053a6b.b14f9828b14f9828 + c183ecb285f06e83.1cf031edb40823d2.5445b9abb682e67b.d2c1213457eb7bf6 + 34d0ba7be59f49a9.1cf031edb40823d2.cac907265c9d4d58.d2c1213457eb7bf6 a86177f1c0c915ab.a2b98dabe07261ef.c0053a6bda383963.9dd52a26b14f9828 db58469acc3bcf60.c183ecb285f06e83.083f406dfa14b509.5445b9abb682e67b d2dc47ae828f211b -VPERMILPS_128_0x30(mem) +VSHUFPD_256_1of2(mem) before f368511a32820533.2bff21e3a47fb372.541bc9ecc08f06b9.fec5169859befcf6 93b354dde1684df0.f2a40736e523fd8d.394da046ac5ae5be.fee1b75892c14bd7 @@ -25346,12 +25346,12 @@ VPERMILPS_128_0x30(mem) d1b7354f7459bfe8 after f368511a32820533.2bff21e3a47fb372.541bc9ecc08f06b9.fec5169859befcf6 - 0000000000000000.0000000000000000.59befcf659befcf6.59befcf6541bc9ec - 8d8acbe2ac4cb67d.8d91f1002bb3e85e.4be5edad665dc6be.64e01f1942a9de58 + 93b354dde1684df0.f2a40736e523fd8d.394da046ac5ae5be.fee1b75892c14bd7 + f368511a32820533.93b354dde1684df0.541bc9ecc08f06b9.394da046ac5ae5be bfb93215af3afc07.5913dcae10b9b191.66ae2d0b09a566e4.8b0e4b480402f125 d1b7354f7459bfe8 -VPERMILPS_128_0x21(reg) +VSHUFPD_256_2of2(reg) before 9127db9c2f398650.040c0563043fdbba.b075c5aa33c394d1.6576da4eb13d815d 27a93899d12f7f07.374fc1b6ca660ec1.ef05a7622d5dcccb.260772617b31d254 @@ -25359,12 +25359,12 @@ VPERMILPS_128_0x21(reg) 44170858378afe14.dcd4e11f124b637d.96db46b21c6d2e9b.5ab751a6e45f096e 866e90b1bab167e9 after - 9127db9c2f398650.040c0563043fdbba.b075c5aa33c394d1.6576da4eb13d815d - 0000000000000000.0000000000000000.838e16f69d11962a.838e16f6842e712f + 44170858378afe14.374fc1b6ca660ec1.96db46b21c6d2e9b.260772617b31d254 + 27a93899d12f7f07.374fc1b6ca660ec1.ef05a7622d5dcccb.260772617b31d254 ee8b48b4f5c6e9ba.364de1fb1abb5248.730d7e409d11962a.842e712f838e16f6 44170858378afe14.dcd4e11f124b637d.96db46b21c6d2e9b.5ab751a6e45f096e 866e90b1bab167e9 -VPERMILPS_128_0x21(mem) +VSHUFPD_256_2of2(mem) before e21ea83d228eeb93.849a72f13407fbc2.04ae3d0cce21fc8a.b5b9fc2349fdd0ca 4c95183437045297.096084eb87ca1c70.8ca871b0694ada9b.2cf49bffbd4bb762 @@ -25373,12 +25373,12 @@ VPERMILPS_128_0x21(mem) 39cac64ee62c685c after e21ea83d228eeb93.849a72f13407fbc2.04ae3d0cce21fc8a.b5b9fc2349fdd0ca - 0000000000000000.0000000000000000.49fdd0cab5b9fc23.49fdd0cace21fc8a - 9e9d5983161f5822.31b539b2cd5e9cc9.4e8efaf600d0b9dd.57d81fb216e52010 + 4c95183437045297.096084eb87ca1c70.8ca871b0694ada9b.2cf49bffbd4bb762 + 849a72f13407fbc2.4c95183437045297.b5b9fc2349fdd0ca.8ca871b0694ada9b b603e816daeab860.57e48eb3a250b879.282c53c9aec1557c.92b084a9f057477f 39cac64ee62c685c -VPERMILPS_128_0x21(reg) +VSHUFPD_256_2of2(reg) before a870e20e94f0be53.6e9342daa0712f7c.d63b7d58a02bac2e.f44df8178f2969a3 3befd356972f860f.a419e2ba83c079a2.0c04040e667bb492.8fbf65cbc013b27f @@ -25386,12 +25386,12 @@ VPERMILPS_128_0x21(reg) 3da8242a0b505b88.f537e47d12e875c0.091fc75eb3acee18.a3c18916819dd205 d3ea378448562106 after - a870e20e94f0be53.6e9342daa0712f7c.d63b7d58a02bac2e.f44df8178f2969a3 - 0000000000000000.0000000000000000.5d8bec3c8dcd0b51.5d8bec3cd64c17d2 + 3da8242a0b505b88.a419e2ba83c079a2.091fc75eb3acee18.8fbf65cbc013b27f + 3befd356972f860f.a419e2ba83c079a2.0c04040e667bb492.8fbf65cbc013b27f 4e9395908b76fb3d.326144a1a0e45200.538c1e428dcd0b51.d64c17d25d8bec3c 3da8242a0b505b88.f537e47d12e875c0.091fc75eb3acee18.a3c18916819dd205 d3ea378448562106 -VPERMILPS_128_0x21(mem) +VSHUFPD_256_2of2(mem) before 43939d09cfc1956c.647a7d8fb349e09d.c9663f39f6d99f0e.8809fbd074a49993 cd88378f31ebea63.1f559a2b20eec728.8bbbd0c167c28c17.2d95b7036b42476d @@ -25400,12 +25400,12 @@ VPERMILPS_128_0x21(mem) 9904ed5aaf73c1f2 after 43939d09cfc1956c.647a7d8fb349e09d.c9663f39f6d99f0e.8809fbd074a49993 - 0000000000000000.0000000000000000.74a499938809fbd0.74a49993f6d99f0e - 4e9482048bdfdb17.ca847969edca4bd4.1502130182aff707.5511f66335113553 + cd88378f31ebea63.1f559a2b20eec728.8bbbd0c167c28c17.2d95b7036b42476d + 647a7d8fb349e09d.cd88378f31ebea63.8809fbd074a49993.8bbbd0c167c28c17 a285f952f8a925b3.c15415b8b76aa94e.440784e562ac9d09.5ac7b45c6d9d9ff0 9904ed5aaf73c1f2 -VPERMILPS_128_0x21(reg) +VSHUFPD_256_2of2(reg) before 6f149ec9981ed602.a625186795568463.60116b8119591d41.f496a05923c63a4a 3643c115c42a1bce.34415b2e7df0b455.02077531b023e35a.017be14ae2088af5 @@ -25413,12 +25413,12 @@ VPERMILPS_128_0x21(reg) 0a2e53f55297254a.611c3e82a02175a9.c4ce9af7eb7954ad.a375c74ec836313c ef23643b2839012f after - 6f149ec9981ed602.a625186795568463.60116b8119591d41.f496a05923c63a4a - 0000000000000000.0000000000000000.ba7f483717543645.ba7f48374881c5a2 + 0a2e53f55297254a.34415b2e7df0b455.c4ce9af7eb7954ad.017be14ae2088af5 + 3643c115c42a1bce.34415b2e7df0b455.02077531b023e35a.017be14ae2088af5 4bdd54abce24cc02.29a53f93cd8670b2.0582313417543645.4881c5a2ba7f4837 0a2e53f55297254a.611c3e82a02175a9.c4ce9af7eb7954ad.a375c74ec836313c ef23643b2839012f -VPERMILPS_128_0x21(mem) +VSHUFPD_256_2of2(mem) before 08571654f595743d.cf81b861ed0f6151.b874d6e713cf7e64.9a36ade4c71e763e cadd5b854b554591.f62381593a19bdc3.0a7783ae419b490f.e507646947cddba6 @@ -25427,12 +25427,12 @@ VPERMILPS_128_0x21(mem) 15e842b9bc98eb95 after 08571654f595743d.cf81b861ed0f6151.b874d6e713cf7e64.9a36ade4c71e763e - 0000000000000000.0000000000000000.c71e763e9a36ade4.c71e763e13cf7e64 - 1181aeb947853158.dc60a84bd640744d.33f3bfc4469290d8.008ebdf00914bd8f + cadd5b854b554591.f62381593a19bdc3.0a7783ae419b490f.e507646947cddba6 + cf81b861ed0f6151.cadd5b854b554591.9a36ade4c71e763e.0a7783ae419b490f b80e8bde0432f3be.db842ba25c10c49b.0fb208133fbf10e8.4615b3e7a67e59a5 15e842b9bc98eb95 -VPERMILPS_128_0xD7(reg) +VPERMILPS_128_0x00(reg) before c75566d2e7edae0b.9d526fe09f6749ee.50db06ca6916e759.7a81d889482e846e baa71c9ec109e0b2.9b17d4a93330ed15.97b1332f98dd1932.4f2bad107ceca994 @@ -25441,11 +25441,11 @@ VPERMILPS_128_0xD7(reg) eb4b1e4c35739581 after c75566d2e7edae0b.9d526fe09f6749ee.50db06ca6916e759.7a81d889482e846e - 0000000000000000.0000000000000000.0c51b03d6c7e0396.6c7e03960c51b03d + 0000000000000000.0000000000000000.f7043b86f7043b86.f7043b86f7043b86 48295f89e979ba37.8e2a3826dd9a9c5e.0c51b03d86f298d2.6c7e0396f7043b86 ce282b00f9c87b46.52571643b8b011f6.0a087860cedf9ee6.ac445406d682f671 eb4b1e4c35739581 -VPERMILPS_128_0xD7(mem) +VPERMILPS_128_0x00(mem) before 055ddc542ee2d5e1.a9f07c6d8d825d8a.c36aebede07e0908.ef2387050d33681a d5470a0ae0db72be.33cd4e3d42349daf.bc2e310e721140c2.16ecd996de773219 @@ -25454,12 +25454,12 @@ VPERMILPS_128_0xD7(mem) af583c11d865e595 after 055ddc542ee2d5e1.a9f07c6d8d825d8a.c36aebede07e0908.ef2387050d33681a - 0000000000000000.0000000000000000.ef238705e07e0908.c36aebed0d33681a + 0000000000000000.0000000000000000.0d33681a0d33681a.0d33681aef238705 39d5245a646b2844.c90b9eddb3697763.1b7166948a74724d.dbaf6b81dd393790 0cd2a730d99db29e.c8f667b87dad264f.bbfd056a43b35bd8.9aba3830a704b42b af583c11d865e595 -VPERMILPS_128_0xD7(reg) +VPERMILPS_128_0x00(reg) before 75d4738f0be6067b.290c0e79587dcdf9.8ad9a5393b8de822.779f8a7cb9dbb68c 4a7bd915dc165288.6e4dd51f00183580.6c0154ce8a94f786.2d2371b509f74098 @@ -25468,11 +25468,11 @@ VPERMILPS_128_0xD7(reg) bbf24d8c2a7d4d7a after 75d4738f0be6067b.290c0e79587dcdf9.8ad9a5393b8de822.779f8a7cb9dbb68c - 0000000000000000.0000000000000000.cabb71e2b7553704.b7553704cabb71e2 + 0000000000000000.0000000000000000.4f13b4264f13b426.4f13b4264f13b426 89996b11e87e0669.b5637810ea79a560.cabb71e2054e8f27.b75537044f13b426 8d7a24eecaac5eca.dc18733634addac4.0051f7e14948eeb3.f3005752a63ccf63 bbf24d8c2a7d4d7a -VPERMILPS_128_0xD7(mem) +VPERMILPS_128_0x00(mem) before edf5959ef8e3ea98.b46a00191f2b9556.bd39437ffabe90d9.6b0fe237f10d4ed3 63d6ac752b7862e8.58b4fbfc8288e8b9.369163d657bb83cb.65432e509929eb36 @@ -25481,12 +25481,12 @@ VPERMILPS_128_0xD7(mem) 4b933267ae028f9f after edf5959ef8e3ea98.b46a00191f2b9556.bd39437ffabe90d9.6b0fe237f10d4ed3 - 0000000000000000.0000000000000000.6b0fe237fabe90d9.bd39437ff10d4ed3 + 0000000000000000.0000000000000000.f10d4ed3f10d4ed3.f10d4ed36b0fe237 fb610cfbe04a7098.d7a61204904e93a1.21ee4f2768ad6ec5.4b38d799de290386 8f62331e3265d1d1.8c8a3f9ee409d2b8.5c1a835e47a20ef4.7939da7c5c98d06f 4b933267ae028f9f -VPERMILPS_128_0xD7(reg) +VPERMILPS_128_0x00(reg) before 1d92dbc470f47cbf.fca59cc83ed440c1.d2ad80341b46e0aa.c1e37c6713a51f84 4b82d1013ff9d27e.1ff6c4e71fa37a94.065bd134d090fa24.2d13b52ee6c35ca0 @@ -25495,11 +25495,11 @@ VPERMILPS_128_0xD7(reg) 340ab831a33179f8 after 1d92dbc470f47cbf.fca59cc83ed440c1.d2ad80341b46e0aa.c1e37c6713a51f84 - 0000000000000000.0000000000000000.85e02c097d77aaa0.7d77aaa085e02c09 + 0000000000000000.0000000000000000.dc068274dc068274.dc068274dc068274 31af1189b69ece86.d2202566f2de3b76.85e02c09a0735cd2.7d77aaa0dc068274 2a6495c7726eac83.f2f03d31d2923f92.a9888f1e267c415f.8bdbd7a7127d4d2e 340ab831a33179f8 -VPERMILPS_128_0xD7(mem) +VPERMILPS_128_0x00(mem) before 54d2ca28ac30c1fe.94ef5b290ff5a722.5c328734dbca4214.d09ef4e1ff36e678 c7fd887a4985e26d.ca9a5f1a27bffd0f.eab27f5b2a93ff2a.546f5abdc62d87c8 @@ -25508,12 +25508,12 @@ VPERMILPS_128_0xD7(mem) ad3d5c20cafba8bf after 54d2ca28ac30c1fe.94ef5b290ff5a722.5c328734dbca4214.d09ef4e1ff36e678 - 0000000000000000.0000000000000000.d09ef4e1dbca4214.5c328734ff36e678 + 0000000000000000.0000000000000000.ff36e678ff36e678.ff36e678d09ef4e1 6a586e12943d9871.28b29b075959e8f6.793ca292dbf833fd.9248ba1e17ee60fc 17aff8dcab639f35.0a830d5a3e4ea482.e59c6bc6090599bc.e67311708f04acc0 ad3d5c20cafba8bf -VPERMILPS_128_0xB5(reg) +VPERMILPS_128_0xFE(reg) before 41f19698636090a6.abcea3c4aa03b2e6.cb59af80752b6f5f.0a9d56e1d0c7ef91 ffddbb46f6be9f21.0281e9b6ac298eaf.c97f7fe5977b833a.c40cdfd14d49efa8 @@ -25522,11 +25522,11 @@ VPERMILPS_128_0xB5(reg) 08e507d01dc84737 after 41f19698636090a6.abcea3c4aa03b2e6.cb59af80752b6f5f.0a9d56e1d0c7ef91 - 0000000000000000.0000000000000000.42ca1dbf5f4379f6.efb58280efb58280 + 0000000000000000.0000000000000000.5f4379f65f4379f6.5f4379f642ca1dbf 434bc89420a112db.f893489ecee2eebd.5f4379f642ca1dbf.efb582809b97562f 6988b7f07c962580.69d23b682b3a903c.e8ef971e12a47899.6764bcdcd7bddf4f 08e507d01dc84737 -VPERMILPS_128_0xB5(mem) +VPERMILPS_128_0xFE(mem) before ae04e14887c44a11.cde186c5a72814bd.31083f00e03b2e57.c2d0d7c8a296d175 358cc63034bba409.cb9f307e3ce31a3e.2c02ce5308f3853b.473234628e2c64ff @@ -25535,12 +25535,12 @@ VPERMILPS_128_0xB5(mem) 7855d2029737d065 after ae04e14887c44a11.cde186c5a72814bd.31083f00e03b2e57.c2d0d7c8a296d175 - 0000000000000000.0000000000000000.c2d0d7c8a296d175.e03b2e57e03b2e57 + 0000000000000000.0000000000000000.31083f0031083f00.31083f0031083f00 794b30743dbb104d.bf11b189d85474af.368c664bbf6d5013.d561aa5773f06de2 560b9d00c1d04b06.0582065116065ebb.2a7282d622b64c0c.c6a93513ed7028ca 7855d2029737d065 -VPERMILPS_128_0xB5(reg) +VPERMILPS_128_0xFE(reg) before 45b37c900dd2a25d.a89987c0d9041163.f93d29429386140e.e6809fdf4cd93551 8b0d2f29ecccd95e.4ac16da0a3651e8e.f79018c9ea5ed155.458137515ae2c710 @@ -25549,11 +25549,11 @@ VPERMILPS_128_0xB5(reg) cb34c25ff1dcc8d6 after 45b37c900dd2a25d.a89987c0d9041163.f93d29429386140e.e6809fdf4cd93551 - 0000000000000000.0000000000000000.b81dd23c5bc5ce50.2342c81a2342c81a + 0000000000000000.0000000000000000.5bc5ce505bc5ce50.5bc5ce50b81dd23c a4b0e73acfb1b215.1a4fc88d3bff2db3.5bc5ce50b81dd23c.2342c81a68debd72 ede8a02d530e6a2e.f30e1571bcdcfbff.81294844984c536e.5c8fcd2591d8d4a6 cb34c25ff1dcc8d6 -VPERMILPS_128_0xB5(mem) +VPERMILPS_128_0xFE(mem) before 4efd23b2a5f7552e.c3015770146e3a54.b0ccd13a430a449e.c508801226798f98 c0b66d0bc83436db.8046076dac5d6134.2f5377d3eb95c3bb.83ad7424ff2fc366 @@ -25562,12 +25562,12 @@ VPERMILPS_128_0xB5(mem) 303f8b336102865c after 4efd23b2a5f7552e.c3015770146e3a54.b0ccd13a430a449e.c508801226798f98 - 0000000000000000.0000000000000000.c508801226798f98.430a449e430a449e + 0000000000000000.0000000000000000.b0ccd13ab0ccd13a.b0ccd13ab0ccd13a fc2b1a5677a02809.8105ac92ba681979.4b708328d0873583.16661fe8bffb2b83 e027a980cd45e7e3.2288424ad71a9fd0.dfef72250fee5622.dc7d7dc90167029c 303f8b336102865c -VPERMILPS_128_0xB5(reg) +VPERMILPS_128_0xFE(reg) before 6df843927c55f170.46779373e6312e96.c01cc601a1ff2ee5.c99cbeb6c3d6e2c3 f1f4a352edee7f84.0ce7551de070ba4e.b50d3323b4a40463.e342e5c7094a9493 @@ -25576,11 +25576,11 @@ VPERMILPS_128_0xB5(reg) f1094f335c67ebd1 after 6df843927c55f170.46779373e6312e96.c01cc601a1ff2ee5.c99cbeb6c3d6e2c3 - 0000000000000000.0000000000000000.ab945bf75ea7851c.0baf62440baf6244 + 0000000000000000.0000000000000000.5ea7851c5ea7851c.5ea7851cab945bf7 177fa6df51586e43.0c436c69d40d4736.5ea7851cab945bf7.0baf6244fd5629bd 3ae549a54320f859.24575343e014917a.1736b858235c704c.1badb219b9065d6e f1094f335c67ebd1 -VPERMILPS_128_0xB5(mem) +VPERMILPS_128_0xFE(mem) before 678fb77cff849013.b871861160d15a74.2eee869720915348.3c05c843b7867e0f 5b0b65e2c16a0860.eb705b8d... [truncated message content] |
|
From: Julian S. <se...@so...> - 2018-09-14 11:22:30
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=27194eb985b22a66b439925e821a41800bcb881e commit 27194eb985b22a66b439925e821a41800bcb881e Author: Julian Seward <js...@ac...> Date: Fri Sep 14 13:19:34 2018 +0200 Bug 397089 - Incorrect decoding of three-register vmovss/vmovsd opcode 11h. This fixes the incorrect 11h decoding of three-register vmovss/vmovsd. Patch from Tomas Trnka (tom...@gm...). Diff: --- VEX/priv/guest_amd64_toIR.c | 12 ++++++------ 1 file changed, 6 insertions(+), 6 deletions(-) diff --git a/VEX/priv/guest_amd64_toIR.c b/VEX/priv/guest_amd64_toIR.c index f462030..2cabf80 100644 --- a/VEX/priv/guest_amd64_toIR.c +++ b/VEX/priv/guest_amd64_toIR.c @@ -24234,12 +24234,12 @@ Long dis_ESC_0F__VEX ( UInt rV = getVexNvvvv(pfx); delta++; DIP("vmovsd %s,%s,%s\n", - nameXMMReg(rE), nameXMMReg(rV), nameXMMReg(rG)); + nameXMMReg(rG), nameXMMReg(rV), nameXMMReg(rE)); IRTemp res = newTemp(Ity_V128); assign(res, binop(Iop_64HLtoV128, getXMMRegLane64(rV, 1), - getXMMRegLane64(rE, 0))); - putYMMRegLoAndZU(rG, mkexpr(res)); + getXMMRegLane64(rG, 0))); + putYMMRegLoAndZU(rE, mkexpr(res)); *uses_vvvv = True; goto decode_success; } @@ -24264,14 +24264,14 @@ Long dis_ESC_0F__VEX ( UInt rV = getVexNvvvv(pfx); delta++; DIP("vmovss %s,%s,%s\n", - nameXMMReg(rE), nameXMMReg(rV), nameXMMReg(rG)); + nameXMMReg(rG), nameXMMReg(rV), nameXMMReg(rE)); IRTemp res = newTemp(Ity_V128); assign( res, binop( Iop_64HLtoV128, getXMMRegLane64(rV, 1), binop(Iop_32HLto64, getXMMRegLane32(rV, 1), - getXMMRegLane32(rE, 0)) ) ); - putYMMRegLoAndZU(rG, mkexpr(res)); + getXMMRegLane32(rG, 0)) ) ); + putYMMRegLoAndZU(rE, mkexpr(res)); *uses_vvvv = True; goto decode_success; } |
|
From: Philippe W. <phi...@so...> - 2018-09-13 19:14:47
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=ee5464ce31201049eaff0ac2f8a7101287a6e982 commit ee5464ce31201049eaff0ac2f8a7101287a6e982 Author: Philippe Waroquiers <phi...@sk...> Date: Thu Sep 13 21:13:51 2018 +0200 Improve doc to describe limitations discussed in 398445 (false positive on shared memory) Diff: --- memcheck/docs/mc-manual.xml | 17 +++++++++++++++++ 1 file changed, 17 insertions(+) diff --git a/memcheck/docs/mc-manual.xml b/memcheck/docs/mc-manual.xml index 869a057..514d635 100644 --- a/memcheck/docs/mc-manual.xml +++ b/memcheck/docs/mc-manual.xml @@ -1568,6 +1568,23 @@ is necessary. This allows GCC to copy warning will only be emitted if the uninitialised values are later used.</para> +<para>As explained above, Memcheck maintains 8 V bits for each byte in your +process, including for bytes that are in shared memory. However, the same piece +of shared memory can be mapped multiple times, by several processes or even by +the same process (for example, if the process wants a read-only and a read-write +mapping of the same page). For such multiple mappings, Memcheck tracks the V +bits for each mapping independently. This can lead to false positive errors, as +the shared memory can be initialised via a first mapping, and accessed via +another mapping. The access via this other mapping will have its own V bits, +which have not been changed when the memory was initialised via the first +mapping. The bypass for these false positives is to use Memcheck's client +requests <varname>VALGRIND_MAKE_MEM_DEFINED</varname> and +<varname>VALGRIND_MAKE_MEM_UNDEFINED</varname> to inform +Memcheck about what your program does (or what another process does) +to these shared memory mappings. Alternatively, you can also use +<varname>VALGRIND_DISABLE_ADDR_ERROR_REPORTING_IN_RANGE</varname>. +</para> + </sect2> |
|
From: Philippe W. <phi...@so...> - 2018-09-13 19:14:41
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=c007cf5db9bda048d78480f60e809313a95b26c9 commit c007cf5db9bda048d78480f60e809313a95b26c9 Author: Philippe Waroquiers <phi...@sk...> Date: Thu Sep 13 21:12:56 2018 +0200 Mention --keep-debuginfo=yes in the FAQ for unloaded shared objects. Diff: --- docs/xml/FAQ.xml | 10 ++++++---- 1 file changed, 6 insertions(+), 4 deletions(-) diff --git a/docs/xml/FAQ.xml b/docs/xml/FAQ.xml index 47adf6b..d0d917e 100644 --- a/docs/xml/FAQ.xml +++ b/docs/xml/FAQ.xml @@ -293,10 +293,12 @@ collect2: ld returned 1 exit status symbol tables (programs should be unstripped unless you run 'strip' on them; some libraries ship stripped).</para> - <para>Also, for leak reports involving shared objects, if the shared - object is unloaded before the program terminates, Valgrind will - discard the debug information and the error message will be full of - <literal>???</literal> entries. The workaround here is to avoid + <para>Also, for leak reports involving shared objects, if the shared object + is unloaded before the program terminates, Valgrind will discard the debug + information and the error message will be full of <literal>???</literal> + entries. If you use the option <option>--keep-debuginfo=yes</option>, then + Valgrind will keep the debug information in order to show the stack traces, + at the price of increased memory. An alternate workaround is to avoid calling <function>dlclose</function> on these shared objects.</para> <para>Also, <option>-fomit-frame-pointer</option> and |
|
From: Petar J. <pe...@so...> - 2018-09-10 10:14:07
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=097b2076013bd6082be189ab55dbdb2eb1e572b7 commit 097b2076013bd6082be189ab55dbdb2eb1e572b7 Author: Petar Jovanovic <mip...@gm...> Date: Mon Sep 10 10:12:57 2018 +0000 Update NEWS with bug fix for KDE #373069 KDE #373069 memcheck/tests/leak_cpp_interior fails with GCC 5.1+ was (partially) fixed in r16217. Diff: --- NEWS | 1 + 1 file changed, 1 insertion(+) diff --git a/NEWS b/NEWS index 7d11362..d7a3416 100644 --- a/NEWS +++ b/NEWS @@ -65,6 +65,7 @@ where XXXXXX is the bug number as listed below. 368913 WARNING: unhandled arm64-linux syscall: 117 (ptrace) == 388664 unhandled arm64-linux syscall: 117 (ptrace) 372347 Replacement problem of the additional c++14/c++17 new/delete operators +373069 memcheck/tests/leak_cpp_interior fails with GCC 5.1+ 376257 helgrind history full speed up using a cached stack 379373 Fix syscall param msg->desc.port.name points to uninitialised byte(s) on macOS 10.12 |
|
From: Petar J. <pe...@so...> - 2018-09-04 21:27:34
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=a914015f7bf1b021e43fe871010983f4568babc6 commit a914015f7bf1b021e43fe871010983f4568babc6 Author: Petar Jovanovic <mip...@gm...> Date: Tue Sep 4 21:23:03 2018 +0000 Update NEWS with bug fix for KDE #396906 Fixed in the previous commit. Diff: --- NEWS | 2 ++ 1 file changed, 2 insertions(+) diff --git a/NEWS b/NEWS index 9657937..7d11362 100644 --- a/NEWS +++ b/NEWS @@ -148,6 +148,8 @@ where XXXXXX is the bug number as listed below. == 397286 crash before launching binary (Unsupported arch_prctl option) == 397393 valgrind: the 'impossible' happened: (Archlinux) == 397521 valgrind: the 'impossible' happened: Unsupported [..] +396906 compile tests failure on mips32-linux: broken inline asm in tests on + mips32-linux 397012 glibc ld.so uses arch_prctl on i386 397354 utimensat should ignore timespec tv_sec if tv_nsec is UTIME_NOW/OMIT 397424 glibc 2.27 and gdb_server tests |
|
From: Petar J. <pe...@so...> - 2018-09-04 21:27:28
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=b99acd0ad87f03ee73ada34f36f952cd508b1a24 commit b99acd0ad87f03ee73ada34f36f952cd508b1a24 Author: Petar Jovanovic <mip...@gm...> Date: Tue Sep 4 21:20:39 2018 +0000 mips32: fix broken inline asm in helgrind/tests/tc08_hbl2.c Remove the duplicated L1xyzzy1main, and use local symbol to replace. This fixes KDE #396906. Patch by Hongxu Jia <hon...@wi...> Diff: --- helgrind/tests/tc08_hbl2.c | 4 ++-- 1 file changed, 2 insertions(+), 2 deletions(-) diff --git a/helgrind/tests/tc08_hbl2.c b/helgrind/tests/tc08_hbl2.c index 2a757a0..f660d82 100644 --- a/helgrind/tests/tc08_hbl2.c +++ b/helgrind/tests/tc08_hbl2.c @@ -121,12 +121,12 @@ #elif defined(PLAT_mips32_linux) || defined(PLAT_mips64_linux) # define INC(_lval,_lqual) \ __asm__ __volatile__ ( \ - "L1xyzzy1" _lqual":\n" \ + "1:\n" \ " move $t0, %0\n" \ " ll $t1, 0($t0)\n" \ " addiu $t1, $t1, 1\n" \ " sc $t1, 0($t0)\n" \ - " beqz $t1, L1xyzzy1" _lqual \ + " beqz $t1, 1b\n" \ : /*out*/ : /*in*/ "r"(&(_lval)) \ : /*trash*/ "t0", "t1", "memory" \ ) |
|
From: Julian S. <se...@so...> - 2018-09-04 08:10:08
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=b2cb69bb73d6b046f716358cd5dee63365d2549a commit b2cb69bb73d6b046f716358cd5dee63365d2549a Author: Julian Seward <js...@ac...> Date: Tue Sep 4 10:07:58 2018 +0200 Complete first-pass triage of all reported bugs. Diff: --- NEWS | 1 + docs/internals/3_13_BUGSTATUS.txt | 33 ++++++++++++++------------------- 2 files changed, 15 insertions(+), 19 deletions(-) diff --git a/NEWS b/NEWS index de1b485..9657937 100644 --- a/NEWS +++ b/NEWS @@ -123,6 +123,7 @@ where XXXXXX is the bug number as listed below. 387766 asm shifts cause false positive "Conditional jump or move depends on uninitialised value" 387773 .gnu_debugaltlink paths resolve relative to .debug file, not symlink +388174 valgrind with Wine quits with "Assertion 'cfsi_fits' failed" 388786 Support bpf syscall in amd64 Linux 388862 Add replacements for wmemchr and wcsnlen on Linux 389065 valgrind meets gcc flag -Wlogical-op diff --git a/docs/internals/3_13_BUGSTATUS.txt b/docs/internals/3_13_BUGSTATUS.txt index 63f619f..ca1543c 100644 --- a/docs/internals/3_13_BUGSTATUS.txt +++ b/docs/internals/3_13_BUGSTATUS.txt @@ -28,9 +28,6 @@ Should look into this, but I can't see how it can have failed. 386602 .build-id/*/*.debug symbols not checked for --extra-debuginfo-path -388174 valgrind with Wine quits with "Assertion 'cfsi_fits' failed" -Is this still valid? - 388493 exp-sgcheck fails on DW_TAG_subrange_type 388526 Inconsistent severity in message text: "WARNING: Serious error" @@ -298,6 +295,9 @@ Has patch; dunno if it's any good 393415 Valgrind memory debugging for nodejs using child process failed on MacOS +398086 Unrecognised instruction with X11 + OpenGL programs +Is actually a syscall failure + === MPI ================================================================ === Output ============================================================= @@ -326,6 +326,9 @@ Has plausible patch 381838 Unused field tag_shift of struct cache_t2 +398178 cachegrind --LL=5242880,2,64 command parameter for Opteron 6174 + rejected + === Tools/Callgrind ==================================================== (carried over) @@ -376,6 +379,9 @@ Probably a trivial fix 392331 Spurious lock not held error from inside pthread_cond_timedwait Some glibc internal use is mishandled +397670 [Helgrind] False positive race detected with sig_atomic_t +False positives due to atomics + === Tools/Lackey ======================================================= === Tools/Massif ======================================================= @@ -474,9 +480,8 @@ Seems marginal 397313 False positive on long double "uninitialised bytes" -398066 cgijl dep1, 0 reports Conditional jump or move depends on - uninitialised value(s) -s390. Mjw has a fix in hand. +398153 Apparent false positive of uninitialised values in libjpeg-turbo +Probably sse inaccuracies === Tools/SGCheck ====================================================== @@ -646,6 +651,9 @@ Missing spec rule, fix this 397089 [PATCH] Incorrect decoding of three-register vmovss/vmovsd opcode 11h FIX FOR 3.14 +398183 Vex errors with _mm256_shuffle_epi8/vpshufb. +Generates too much code + === VEX/arm32 ========================================================== (carried over) @@ -923,17 +931,4 @@ Created Tues 24 July 2018. All bugs after the release of 3.13.0 go in here. Also, this contains bugs from 3_12_BUGSTATUS.txt that didn't get fixed in 3.12. These are marked "(carried over)". -Mon 6 Aug 11:04:50 CEST 2018 - -Tue 24 Jul 11:50:41 CEST 2018 - -397670 [Helgrind] False positive race detected with sig_atomic_t -398086 Unrecognised instruction with X11 + OpenGL programs -398153 Apparent false positive of uninitialised values in libjpeg-turbo -398178 cachegrind --LL=5242880,2,64 command parameter for Opteron 6174 - rejected -398183 Vex errors with _mm256_shuffle_epi8/vpshufb. - -## 388174 is fixed but not in NEWS - Mon 3 Sep 12:01:52 CEST 2018 |
|
From: Julian S. <se...@so...> - 2018-09-03 18:28:13
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=a8ebc1bb067c3d6cbd8d1c7db488ed19bc78c72a commit a8ebc1bb067c3d6cbd8d1c7db488ed19bc78c72a Author: Julian Seward <js...@ac...> Date: Mon Sep 3 12:02:19 2018 +0200 Almost catch up with first-pass triaging of bugs. Diff: --- NEWS | 5 + docs/internals/3_13_BUGSTATUS.txt | 215 ++++++++++++++++++++++++++------------ 2 files changed, 151 insertions(+), 69 deletions(-) diff --git a/NEWS b/NEWS index 9a6e2a3..de1b485 100644 --- a/NEWS +++ b/NEWS @@ -92,6 +92,7 @@ where XXXXXX is the bug number as listed below. == 384156 vex x86->IR: 0x67 0xE8 0x6B 0x6A == 386115 vex x86->IR: 0x67 0xE8 0xD3 0x8B any program == 388407 vex x86->IR: 0x67 0xE8 0xAB 0x29 + == 394903 vex x86->IR: 0x67 0xE8 0x1B 0xDA 384337 performance improvements to VEX register allocator v2 and v3 384526 reduce number of spill insns generated by VEX register allocator v3 384584 Callee saved regs listed first for AMD64, X86, and PPC architectures @@ -128,6 +129,7 @@ where XXXXXX is the bug number as listed below. 389373 exp-sgcheck the 'impossible' happened as Ist_LoadG is not instrumented 390471 suppression by specification of source-file line number 390723 make xtree dump files world wide readable, similar to log files +391164 constraint bug in tests/ppc64/test_isa_2_07_part1.c for mtfprwa 391861 Massif Assertion 'n_ips >= 1 && n_ips <= VG_(clo_backtrace_size)' 392118 unhandled amd64-linux syscall: 332 (statx) 392449 callgrind not clearing the number of calls properly @@ -142,6 +144,9 @@ where XXXXXX is the bug number as listed below. == 384727 396475 valgrind OS-X build: config.h not found (out-of-tree macOS builds) 396887 arch_prctl should return EINVAL on unknown option + == 397286 crash before launching binary (Unsupported arch_prctl option) + == 397393 valgrind: the 'impossible' happened: (Archlinux) + == 397521 valgrind: the 'impossible' happened: Unsupported [..] 397012 glibc ld.so uses arch_prctl on i386 397354 utimensat should ignore timespec tv_sec if tv_nsec is UTIME_NOW/OMIT 397424 glibc 2.27 and gdb_server tests diff --git a/docs/internals/3_13_BUGSTATUS.txt b/docs/internals/3_13_BUGSTATUS.txt index ac2ad29..63f619f 100644 --- a/docs/internals/3_13_BUGSTATUS.txt +++ b/docs/internals/3_13_BUGSTATUS.txt @@ -47,6 +47,27 @@ Is this still valid? 390871 ELF debug info reader confused with multiple .rodata* sections +393857 Please add support for gcc's artificial attribute +Wishlist + +396476 Reading debug info of binaries with zero-size PT_LOAD segment +Seems pretty marginal + +396656 Warnings while reading debug info +arm32-linux + +397238 Look up of separate debuginfo does not search by build-id in + --extra-debuginfo-path +Has plausible patch + +397357 symbols not loaded with binutils-2.31.1 unless -fuse-ld=gold + specified to gcc/g++ +Possibly fixed already? + +398028 Assertion `csfi_fits` failing in simple C program with embedded + Julia code. +Probably fixed already ( + === Documentation ====================================================== 382099 valgrind release archive is not maintained @@ -60,6 +81,15 @@ Is this still valid? (carried over) 356174 Enhance the embedded gdbserver to allow LLDB to use it +395416 --log-file output isn't split correctly after call vgdb +This is probably invalid (see 395414) + +397187 z13 vector register support for vgdb gdbserver + +397357 symbols not loaded with binutils-2.31.1 unless -fuse-ld=gold + specified to gcc/g++ +Fixed, but not yet closed (awaiting confirmation) + === KernelInterface ==================================================== === KernelInterface/Linux ============================================== @@ -165,6 +195,25 @@ ppc32, 3.11.0 390553 update xen support to Xen 4.10 Should possibly take +393083 Unimplemented fcntl + +393182 Add support for pthread_setname_np() to set thread name +(I thought this already worked) + +395991 wine's unit tests enter a signal delivery loop under valgrind on + armv7l when SIGSEGV is used +FIX for 3.14 (arm32 signal-resume stuff) + +396369 WARNING: unhandled amd64-linux syscall: 332 + +397265 [PATCH] Add (partial) support for userfaultfd syscall and related ioctl + +397354 utimensat should ignore timespec tv_sec when tv_nsec + is UTIME_NOW or UTIME_OMIT + +397605 ioctl FICLONE mishandled +Sounds plausible + === KernelInterface/OS X =============================================== (carried over) @@ -230,6 +279,8 @@ Should possibly take on macOS 10.12 379893 valgrind segfault os x 10.12.4 + == 396367 unhandled syscall amd64-darwin unix:520 + (terminate_with_payload) and unix:521 (abort_with_payload) 380269 No multithreading in macOS Sierra (10.12) Has a bunch of patches; worth looking at? @@ -245,6 +296,8 @@ Has patch; dunno if it's any good 390754 unhandled amd64-darwin syscall: unix:216 (open_dprotected_np) +393415 Valgrind memory debugging for nodejs using child process failed on MacOS + === MPI ================================================================ === Output ============================================================= @@ -265,6 +318,9 @@ Wishlist, has patch 390866 "at" is doubled in "Block was alloc'd at" Trivial to fix, but could cause breakage for consumers? +393926 helpful to have report timestamp in wall-clock time +Has plausible patch + === Tools ============================================================== === Tools/Cachegrind =================================================== @@ -282,6 +338,8 @@ Trivial to fix, but could cause breakage for consumers? 388740 Ordering by timestamp instead of core number +394307 Add macro to extract current instruction count for peak load monitoring + === Tools/DHAT ========================================================= 390792 'impossible' happened in dh_handle_noninsn_write() @@ -315,6 +373,9 @@ Wishlist 384261 Assert failure on helgrind with the SIDT instruction Probably a trivial fix +392331 Spurious lock not held error from inside pthread_cond_timedwait +Some glibc internal use is mishandled + === Tools/Lackey ======================================================= === Tools/Massif ======================================================= @@ -401,6 +462,22 @@ This seems like it is important. Check with mjw. but not for std::vector Almost certainly invalid +392373 Valgrind could have an option to search for pointers at unaligned + addresses +Wishlist + +396053 Memcheck does not support copy-stack style coroutine +Seems marginal + +397083 Likely false positive "uninitialised value(s)" for __wmemchr_avx2 + and __wmemcmp_avx2_movbe + +397313 False positive on long double "uninitialised bytes" + +398066 cgijl dep1, 0 reports Conditional jump or move depends on + uninitialised value(s) +s390. Mjw has a fix in hand. + === Tools/SGCheck ====================================================== === Uncategorised ====================================================== @@ -439,6 +516,16 @@ Wishlist 391311 [Patch] Fix arm64 valgrind tests compilation with clang +391853 Makefile.all.am:L247 and @SOLARIS_UNDEF_LARGESOURCE@ being empty + +392180 LTO build simplification: __asm__ in m_libcsetjmp.c + +396452 none/test/arm/vfp.c doesn't build with binutils 2.31 gas +I think the binutils crew fixed gas properly + +396906 compile tests failure on mips32-linux: broken inline asm in tests + on mips32-linux + === Uncategorised/run ================================================== (carried over) @@ -471,6 +558,18 @@ Wishlist 384630 The 'impossible' happened (__ubsan_handle_shift_out_of_bounds) as soon as starting anything under valgrind +394361 [Enhancement] : Client request to control thread-yielding in valgrind +Seems dubious to me + +395139 Terminate process and fail at errors. +Wishlist, marginal + +395266 Environment variables with slashes get dropped +Should fix + +396415 Valgrind is not looking up $ORIGIN rpath of shebang programs +Not sure what's going on here + === VEX ================================================================ === VEX/amd64 ========================================================== @@ -537,6 +636,16 @@ Potentially serious 391845 Unrecognised instruction: __svml_irem8_l9 Probably invalid (3.11.0) +393351 vex amd64->IR: 0x62 0xF1 0xFD 0x48 0x6F 0xD 0xE1 0xEC 0x8 + +394582 vex amd64->IR: 0x62 0xF1 0x7C 0x48 0x57 0xC0 0x48 0x8D 0x35 0x6A + +396706 VEX issue with AMD64 SHR instruction? +Missing spec rule, fix this + +397089 [PATCH] Incorrect decoding of three-register vmovss/vmovsd opcode 11h +FIX FOR 3.14 + === VEX/arm32 ========================================================== (carried over) @@ -593,6 +702,16 @@ On Android, may be important? instruction Potentially serious +393036 arm: unhandled instruction: 0xEBAD 0x1BC7 (sub.w fp, sp, r7, lsl #7) +Potentially serious + +395777 disInstr(arm): unhandled instruction: 0xE7F000F0 + (wine, dlls/msvcp90/tests/misc.c) +This is handled correctly, but shouldn't be so verbose (--sigill-diagnostics?) + +396001 unhandled instruction: 0xEC51 0x0F1E; ARMv7 libcrypto 'mrrc' + == disInstr(arm): unhandled instruction: 0xEC510F1E + === VEX/arm64 ========================================================== (carried over) @@ -611,8 +730,14 @@ Is this really not supported? 386861 ARM64: Pre-indexed store to the stack reported as invalid write More missing earlyWB problems? +392146 aarch64: unhandled instruction 0xD5380001 (MRS rT, mdir_el1) +Has patch, but looks pretty dirty + === VEX/mips =========================================================== +396905 compile tests failure on mips32-linux: Error: opcode not + supported on this processor: mips1 (mips1) + === VEX/other ========================================================== 384681 PUT(pc, <variable>) should specialize to help debugging @@ -621,6 +746,10 @@ Wishlist 384842 Reporting for VEX IR semantic bugs This does actually show 3 problems which look ungood! +394227 [x86] False negative "uninitialised value" report due to not + recognizing simd registers clear by pcmp* +Should fold these to constant zero in iropt; awaiting test case + === VEX/ppc ============================================================ (carried over) @@ -638,9 +767,14 @@ This does actually show 3 problems which look ungood! 385411 s390x: z13 vector floating-point instructions not implemented +396839 s390x: Trap instructions not implemented + === VEX/x86 ============================================================ === zz_other =========================================================== + +396290 [PATCH] Possible tool - allocfail + === zz_other/Android =================================================== (carried over) @@ -671,6 +805,9 @@ This does actually show 3 problems which look ungood! 374814 VALGRIND INTERNAL ERROR: signal 11 (SIGSEGV) - exiting possibly TLS related +393457 valgrind crash at _start with arm CPU +Not enough info to do anything with this + === zz_other/arm64 ===================================================== (carried over) @@ -786,77 +923,17 @@ Created Tues 24 July 2018. All bugs after the release of 3.13.0 go in here. Also, this contains bugs from 3_12_BUGSTATUS.txt that didn't get fixed in 3.12. These are marked "(carried over)". -391164 constraint bug in tests/ppc64/test_isa_2_07_part1.c for mtfprwa -** should be closed? queried carl - Mon 6 Aug 11:04:50 CEST 2018 -391853 Makefile.all.am:L247 and @SOLARIS_UNDEF_LARGESOURCE@ being empty -391861 Massif assertion failed -392118 unhandled amd64-linux syscall: 332 [KDE executables] -392146 aarch64: unhandled instruction 0xD5380001 (MRS rT, mdir_el1) -392180 LTO build simplification: __asm__ in m_libcsetjmp.c -392331 Spurious lock not held error from inside pthread_cond_timedwait -392373 Valgrind could have an option to search for pointers at unaligned - addresses -392449 callgrind not clearing the number of calls properly -393017 Add missing support for xsmaxcdp instruction, bug fixes for xsmincdp, - lxssp, stxssp and stxvl instructions -393023 callgrind_control risks using the wrong vgdb -393036 arm: unhandled instruction: 0xEBAD 0x1BC7 (sub.w fp, sp, r7, lsl #7) -393062 Reading build-id ELF note through phdrs triggers - "debuginfo reader: ensure_valid failed" -393083 NOT IMPLEMENTED -393099 posix_memalign() invalid write if alignment == 0 -393146 Memcheck fails assert "is_DebugInfo_active(di)" - even though code built with -g -393182 Add support for pthread_setname_np() to set thread name -393351 unhandled instruction bytes: 0x62 0xF1 0xFD 0x48 0x6F 0xD 0xE1 0xEC 0x8 -393415 Valgrind memory debugging for nodejs using child process failed on MacOS -393457 valgrind crash at _start with arm CPU -393769 Building 3.13.0 on MacOS High Sierra -393857 Please add support for gcc's artificial attribute -393926 helpful to have reort timestamp in wall-clock time -394036 xml file could not be able to parse from valgrind plugin in jenkins -394227 [x86] False negative "uninitialised value" report due to not - recognizing simd registers clear by pcmp* -394307 Add macro to extract current instruction count for peak load monitoring -394361 [Enhancement] : Client request to control thread-yielding in valgrind -394582 vex amd64->IR: 0x62 0xF1 0x7C 0x48 0x57 0xC0 0x48 0x8D 0x35 0x6A -394585 Valgrind on ARM without VFP, dead at dispatch-arm-linux.S - "fmxr fpscr, r4" -394731 allow building if arch=amd64 instead of x86-64 -394903 vex x86->IR: 0x67 0xE8 0x1B 0xDA -395136 Valgrind crashed when run -395139 Terminate process and fail at errors. -395246 vex amd64->IR: unhandled instruction bytes: -395266 Environment variables with slashes get dropped -395414 Valgrind hangs when about to exit -395416 --log-file output isn't split correctly after call vgdb -395434 valgrind XML output should setlinebuf() to facilitate online use -395682 Reading debug info -395709 PPC64 is missing support for the xvnegsp instruction -395777 disInstr(arm): unhandled instruction: 0xE7F000F0 - (wine, dlls/msvcp90/tests/misc.c) -395809 Unrecognised instruction by std::random_device::_M_getval() -395871 unhandled instruction bytes -395991 wine's unit tests enter a signal delivery loop under valgrind on - armv7l when SIGSEGV is used -396001 unhandled instruction: 0xEC51 0x0F1E; ARMv7 libcrypto 'mrrc' -396053 Memcheck does not support copy-stack style coroutine -396176 vex amd64->IR: 0xF 0xC7 0xF0 0xBA 0x1 0x0 0x0 0x0 0x89 0x6 -396220 vex x86->IR: 0xC4 0xE2 0x41 0xF7 -396290 [PATCH] Possible tool - allocfail -396367 unhandled syscall amd64-darwin unix:520 and unix:521 -396369 WARNING: unhandled amd64-linux syscall: 332 -396415 Valgrind is not looking up $ORIGIN rpath of shebang programs -396452 none/test/arm/vfp.c doesn't build with binutils 2.31 gas -396476 Reading debug info of binaries with zero-size PT_LOAD segment -396656 Warnings while reading debug info -396706 VEX issue with AMD64 SHR instruction? - Tue 24 Jul 11:50:41 CEST 2018 -Also: make arm32 resume with sigcontext regs after signal return (395991) +397670 [Helgrind] False positive race detected with sig_atomic_t +398086 Unrecognised instruction with X11 + OpenGL programs +398153 Apparent false positive of uninitialised values in libjpeg-turbo +398178 cachegrind --LL=5242880,2,64 command parameter for Opteron 6174 + rejected +398183 Vex errors with _mm256_shuffle_epi8/vpshufb. -396839 s390x: Trap instructions not implemented +## 388174 is fixed but not in NEWS + +Mon 3 Sep 12:01:52 CEST 2018 |
|
From: Mark W. <ma...@so...> - 2018-09-03 11:04:26
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=51736549e33fc8468e47861031a70c7f8cadd691 commit 51736549e33fc8468e47861031a70c7f8cadd691 Author: Mark Wielaard <ma...@kl...> Date: Mon Sep 3 12:56:53 2018 +0200 Bug 398066 s390x: cgijl dep1, 0 reports false uninitialised values warning. This is similar to bug #387712 (about cgijnl), but a newer gcc uses cgijl now. So use a similar fix when cc_dep2 is zero, only check whether the most significant bit of cc_dep1 is set to 1. Diff: --- NEWS | 1 + VEX/priv/guest_s390_helpers.c | 8 ++++++++ 2 files changed, 9 insertions(+) diff --git a/NEWS b/NEWS index c79d775..9a6e2a3 100644 --- a/NEWS +++ b/NEWS @@ -145,6 +145,7 @@ where XXXXXX is the bug number as listed below. 397012 glibc ld.so uses arch_prctl on i386 397354 utimensat should ignore timespec tv_sec if tv_nsec is UTIME_NOW/OMIT 397424 glibc 2.27 and gdb_server tests +398066 s390x: cgijl dep1, 0 reports false unitialised values warning n-i-bz Fix missing workq_ops operations (macOS) n-i-bz fix bug in strspn replacement diff --git a/VEX/priv/guest_s390_helpers.c b/VEX/priv/guest_s390_helpers.c index 52e4ce9..aeda677 100644 --- a/VEX/priv/guest_s390_helpers.c +++ b/VEX/priv/guest_s390_helpers.c @@ -1935,6 +1935,14 @@ guest_s390x_spechelper(const HChar *function_name, IRExpr **args, return unop(Iop_1Uto32, binop(Iop_CmpNE64, cc_dep1, cc_dep2)); } if (cond == 4 || cond == 4 + 1) { + if (isC64_exactly(cc_dep2, 0)) { + /* dep1 <signed 0 + --> m.s.bit of dep1 == 1 */ + return unop(Iop_64to32, + binop(Iop_And64, + binop(Iop_Shr64, cc_dep1, mkU8(63)), + mkU64(1))); + } return unop(Iop_1Uto32, binop(Iop_CmpLT64S, cc_dep1, cc_dep2)); } if (cond == 8 + 4 || cond == 8 + 4 + 1) { |
|
From: Mark W. <ma...@so...> - 2018-09-03 09:59:29
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=790f5f3018f807153339e441e7aea1414f4b5c8d commit 790f5f3018f807153339e441e7aea1414f4b5c8d Author: Mark Wielaard <ma...@kl...> Date: Mon Sep 3 11:54:38 2018 +0200 Bug 397354 utimensat should ignore tv_sec if tv_nsec is UTIME_NOW/OMIT. When code uses utimensat with UTIME_NOW or UTIME_OMIT valgrind memcheck would generate a warning. But as the utimensat manpage says: If the tv_nsec field of one of the timespec structures has the special value UTIME_NOW, then the corresponding file timestamp is set to the current time. If the tv_nsec field of one of the timespec structures has the special value UTIME_OMIT, then the corresponding file timestamp is left unchanged. In both of these cases, the value of the correâ sponding tv_sec field is ignored. So ignore the timespec tv_sec when tv_nsec is set to UTIME_NOW or UTIME_OMIT. Diff: --- NEWS | 1 + coregrind/m_syswrap/syswrap-linux.c | 21 +++++++++++++++++++-- include/vki/vki-linux.h | 4 ++++ 3 files changed, 24 insertions(+), 2 deletions(-) diff --git a/NEWS b/NEWS index 982e3ec..c79d775 100644 --- a/NEWS +++ b/NEWS @@ -143,6 +143,7 @@ where XXXXXX is the bug number as listed below. 396475 valgrind OS-X build: config.h not found (out-of-tree macOS builds) 396887 arch_prctl should return EINVAL on unknown option 397012 glibc ld.so uses arch_prctl on i386 +397354 utimensat should ignore timespec tv_sec if tv_nsec is UTIME_NOW/OMIT 397424 glibc 2.27 and gdb_server tests n-i-bz Fix missing workq_ops operations (macOS) diff --git a/coregrind/m_syswrap/syswrap-linux.c b/coregrind/m_syswrap/syswrap-linux.c index 2c96fed..90d4a85 100644 --- a/coregrind/m_syswrap/syswrap-linux.c +++ b/coregrind/m_syswrap/syswrap-linux.c @@ -5303,8 +5303,25 @@ PRE(sys_utimensat) int, dfd, char *, filename, struct timespec *, utimes, int, flags); if (ARG2 != 0) PRE_MEM_RASCIIZ( "utimensat(filename)", ARG2 ); - if (ARG3 != 0) - PRE_MEM_READ( "utimensat(tvp)", ARG3, 2 * sizeof(struct vki_timespec) ); + if (ARG3 != 0) { + /* If timespec.tv_nsec has the special value UTIME_NOW or UTIME_OMIT + then the tv_sec field is ignored. */ + struct vki_timespec *times = (struct vki_timespec *)(Addr)ARG3; + PRE_MEM_READ( "utimensat(times[0].tv_nsec)", + (Addr)×[0].tv_nsec, sizeof(times[0].tv_nsec)); + PRE_MEM_READ( "utimensat(times[1].tv_nsec)", + (Addr)×[1].tv_nsec, sizeof(times[1].tv_nsec)); + if (ML_(safe_to_deref)(times, 2 * sizeof(struct vki_timespec))) { + if (times[0].tv_nsec != VKI_UTIME_NOW + && times[0].tv_nsec != VKI_UTIME_OMIT) + PRE_MEM_READ( "utimensat(times[0].tv_sec)", + (Addr)×[0].tv_sec, sizeof(times[0].tv_sec)); + if (times[1].tv_nsec != VKI_UTIME_NOW + && times[1].tv_nsec != VKI_UTIME_OMIT) + PRE_MEM_READ( "utimensat(times[1].tv_sec)", + (Addr)×[1].tv_sec, sizeof(times[1].tv_sec)); + } + } } PRE(sys_newfstatat) diff --git a/include/vki/vki-linux.h b/include/vki/vki-linux.h index 815f658..b4c6085 100644 --- a/include/vki/vki-linux.h +++ b/include/vki/vki-linux.h @@ -285,6 +285,10 @@ struct vki_timespec { long tv_nsec; /* nanoseconds */ }; +/* Special values for vki_timespec.tv_nsec when used with utimensat. */ +#define VKI_UTIME_NOW ((1l << 30) - 1l) +#define VKI_UTIME_OMIT ((1l << 30) - 2l) + struct vki_timeval { vki_time_t tv_sec; /* seconds */ vki_suseconds_t tv_usec; /* microseconds */ |
|
From: Philippe W. <phi...@sk...> - 2018-09-02 13:55:15
|
On Fri, 2018-07-13 at 09:55 +0200, Julian Seward wrote: > Hi Carl, [All], > > I propose the following: > > * Up to 23 Aug: fix as many bugs as we can > * Fri 23 Aug: code freeze. After this, only "important" bug fixes to land > * Mon 10 Sept: release > > At an absolute minimum I would like to have the s390/z13 fixes in, and the > current PT_LOAD problem(s) resolved by then. Plus of course as many other > fixes as we have time for. I will create a docs/internals/3_13_BUGSTATUS.txt > file in the next day or so, so as to get a top-level overview of the bug > situation. Hello all, Recently, I have done another change for 393146 - failing assert "is_DebugInfo_active(di)" (at least, this solves the case reproduced on gnu/linux with qt5). I also updated gdbserver tests for glibc 2.27. I do not think I have anything more burning waiting for a fix in the 3.14 release. Is there anything needed for 3.14 still blocking/not done yet? (the s390/z13 fixes maybe ?) Thanks Philippe |
|
From: Philippe W. <phi...@so...> - 2018-09-02 12:23:25
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=0822ebca8f964f1685d667e0c21fea926633bb92 commit 0822ebca8f964f1685d667e0c21fea926633bb92 Author: Philippe Waroquiers <phi...@sk...> Date: Sun Sep 2 14:19:57 2018 +0200 Fix Bug 397424 - glibc 2.27 and gdb_server tests commit a214595daed7830a091dcd0f52c5b8073bfd04dd already handled some of the new differences created by glib 2.27. This commit should filter the new way gdb shows a select syscall with glibc 2.27 Diff: --- NEWS | 1 + gdbserver_tests/filter_gdb | 12 ++++++++++++ 2 files changed, 13 insertions(+) diff --git a/NEWS b/NEWS index bd3c61d..982e3ec 100644 --- a/NEWS +++ b/NEWS @@ -143,6 +143,7 @@ where XXXXXX is the bug number as listed below. 396475 valgrind OS-X build: config.h not found (out-of-tree macOS builds) 396887 arch_prctl should return EINVAL on unknown option 397012 glibc ld.so uses arch_prctl on i386 +397424 glibc 2.27 and gdb_server tests n-i-bz Fix missing workq_ops operations (macOS) n-i-bz fix bug in strspn replacement diff --git a/gdbserver_tests/filter_gdb b/gdbserver_tests/filter_gdb index ed78cfe..662028f 100755 --- a/gdbserver_tests/filter_gdb +++ b/gdbserver_tests/filter_gdb @@ -41,6 +41,14 @@ sed -e '/^\ \ \ \ \.\.\.$/d' | # (on 32 bits, we have an int_80, on 64 bits, directly select) # and yet another (gdb 7.0 way) to get a system call # and yet another (gdb 7.0 arm way) to get a system call +# +# Additions of 4 expressions to cover glibc 2.27 way to do a select, such as +# * 1 Thread 5548 (tid 1 VgTs_WaitSys) 0x0000000004f6203f in __GI___select ( +# nfds=0, readfds=0x0, writefds=0x0, exceptfds=0x0, timeout=0x30a0e0 <t>) +# at ../sysdeps/unix/sysv/linux/select.c:41 +# If select.c sources are present, we can also get a line containing: +# return SYSCALL_CANCEL.... +# # and cleanup some lines for a system call (on ubuntu 10 64 bits) # (pay attention : there are tab characters there in) # + yet another way to get a select system call @@ -98,6 +106,10 @@ sed -e '/Remote debugging using/,/vgdb launched process attached/d' -e '/^ from \/lib\/ld-linux.so.*$/d' \ -e 's/\(0x........\) in ?? () from \/lib.*$/\1 in syscall .../' \ -e 's/\(0x........\) in ?? ()$/\1 in syscall .../' \ + -e 's/in __select .*/in syscall .../' \ + -e '/exceptfds/d' \ + -e '/sysv\/linux\/select\.c/d' \ + -e '/return SYSCALL_CANCEL /d' \ -e 's/in \(.__\)\{0,1\}select () from \/.*$/in syscall .../' \ -e '/^ from \/lib\/libc.so.*$/d' \ -e '/^ from \/lib64\/libc.so.*$/d' \ |
|
From: Philippe W. <phi...@so...> - 2018-09-01 21:50:49
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=d457604d498081e402cb223e1a364719dc0c0793 commit d457604d498081e402cb223e1a364719dc0c0793 Author: Philippe Waroquiers <phi...@sk...> Date: Sat Sep 1 23:36:42 2018 +0200 Fix 393146 failing assert "is_DebugInfo_active(di)" Some applications are mapping an object ro, and then unmaps it directly. In such a case, we have a di that contains obsolete fsm.maps (not matching OS mappings). The di for this unmapped object is not active, and has no dinfo (have_dinfo == False). (more generally, fsm.maps can contain a whole bunch of obsolete mappings). Later on, some other libs can be mapped with a mapping overlapping this obsolete mapping. A di that never had its debug info loaded can really be discarded, even if CG_(clo_keep_debuginfo). In such a case, it is normal to have to discard a not active di. (it might be better to keep fsm.maps in sync with the real OS mapping, but that is a much bigger change/fix). The FSM debug tracing was static, it is now dynamic according to debug loglevel >= 3. The below is an extract of the trace showing what happens. SYSCALL[4384,1](257) sys_openat ( 4294967196, 0x4244398(/usr/lib/x86_64-linux-gnu/qt5/plugins/platforms/libqeglfs.so), 524288 ) --> [async] ... SYSCALL[4384,1](257) ... [async] --> Success(0x3) SYSCALL[4384,1](72) sys_fcntl[ARG3=='arg'] ( 3, 2, 1 )[sync] --> Success(0x0) SYSCALL[4384,1](5) sys_newfstat ( 3, 0x1ffefff8b0 )[sync] --> Success(0x0) SYSCALL[4384,1](5) sys_newfstat ( 3, 0x1ffefff9c0 )[sync] --> Success(0x0) SYSCALL[4384,1](9) sys_mmap ( 0x0, 10520, 1, 1, 3, 0 )--4384-- di_notify_mmap-0: --4384-- di_notify_mmap-1: 0x4027000-0x4029fff r-- --4384-- di_notify_mmap-2: /usr/lib/x86_64-linux-gnu/qt5/plugins/platforms/libqeglfs.so --4384-- di_notify_mmap-3: is_rx_map 0, is_rw_map 0, is_ro_map 1 --4384-- di_notify_mmap-4: noting details in DebugInfo* at 0x10024CEA10 --4384-- di_notify_mmap-6: no dinfo loaded /usr/lib/x86_64-linux-gnu/qt5/plugins/platforms/libqeglfs.so (no rx or no rw mapping) --> [pre-success] Success(0x4027000) SYSCALL[4384,1](3) sys_close ( 3 )[sync] --> Success(0x0) SYSCALL[4384,1](11) sys_munmap ( 0x4027000, 10520 )[sync] --> Success(0x0) ^^^^ the above munmap has not cleaned up or removed anything in DebugInfo* at 0x10024CEA10 Later on, /usr/lib/x86_64-linux-gnu/qt5/plugins/platforms/libqxcb.so is mapped overlapping the memory where libqeglfs.so was mapped ro. Now, this cleans up the (useless) di that never had have_dinfo true, e.g. ------ start ELF OBJECT ------------------------------------------------------- ------ name = /usr/lib/x86_64-linux-gnu/qt5/plugins/platforms/libqxcb.so ... --4384-- Discarding syms at 0x0-0x0 in /usr/lib/x86_64-linux-gnu/qt5/plugins/platforms/libqeglfs.so (have_dinfo 0) (the 0x0-0x0 in the trace is because there was never any text mapping for libqeglfs.so). Diff: --- NEWS | 1 + coregrind/m_debuginfo/debuginfo.c | 100 +++++++++++++++++++------------------- 2 files changed, 52 insertions(+), 49 deletions(-) diff --git a/NEWS b/NEWS index e14e44c..bd3c61d 100644 --- a/NEWS +++ b/NEWS @@ -136,6 +136,7 @@ where XXXXXX is the bug number as listed below. 393023 callgrind_control risks using the wrong vgdb 393062 build-id ELF phdrs read causes "debuginfo reader: ensure_valid failed" 393099 posix_memalign() invalid write if alignment == 0 +393146 failing assert "is_DebugInfo_active(di)" 395709 PPC64 is missing support for the xvnegsp instruction 395682 Accept read-only PT_LOAD segments and .rodata by ld -z separate-code == 384727 diff --git a/coregrind/m_debuginfo/debuginfo.c b/coregrind/m_debuginfo/debuginfo.c index a30c7b4..0fc54bf 100644 --- a/coregrind/m_debuginfo/debuginfo.c +++ b/coregrind/m_debuginfo/debuginfo.c @@ -34,6 +34,7 @@ #include "pub_core_vki.h" #include "pub_core_threadstate.h" #include "pub_core_debuginfo.h" /* self */ +#include "pub_core_debuglog.h" #include "pub_core_demangle.h" #include "pub_core_libcbase.h" #include "pub_core_libcassert.h" @@ -68,10 +69,6 @@ #endif -/* Set this to 1 to enable debug printing for the - should-we-load-debuginfo-now? finite state machine. */ -#define DEBUG_FSM 0 - /* Set this to 1 to enable somewhat minimal debug printing for the debuginfo-epoch machinery. */ #define DEBUG_EPOCHS 0 @@ -443,27 +440,31 @@ static void free_DebugInfo ( DebugInfo* di ) */ static void discard_or_archive_DebugInfo ( DebugInfo* di ) { - const HChar* reason = "munmap"; - const Bool archive = VG_(clo_keep_debuginfo); + /* di->have_dinfo can be False when an object is mapped "ro" + and then unmapped before the debug info is loaded. + In other words, debugInfo_list might contain many di that have + no OS mappings, even if their fsm.maps still contain mappings. + Such (left over) mappings can overlap with real mappings. + Search for FSMMAPSNOTCLEANEDUP: below for more details. */ + /* If a di has no dinfo, we can discard even if VG_(clo_keep_debuginfo). */ + const Bool archive = VG_(clo_keep_debuginfo) && di->have_dinfo; DebugInfo** prev_next_ptr = &debugInfo_list; DebugInfo* curr = debugInfo_list; - /* It must be active! */ - vg_assert(is_DebugInfo_active(di)); + /* If di->have_dinfo, then it must be active! */ + vg_assert(!di->have_dinfo || is_DebugInfo_active(di)); while (curr) { if (curr == di) { /* Found it; (remove from list and free it), or archive it. */ - if (curr->have_dinfo - && (VG_(clo_verbosity) > 1 || VG_(clo_trace_redir))) - VG_(message)(Vg_DebugMsg, - "%s syms at %#lx-%#lx in %s due to %s()\n", - archive ? "Archiving" : "Discarding", - di->text_avma, - di->text_avma + di->text_size, - curr->fsm.filename ? curr->fsm.filename - : "???", - reason); + if (VG_(clo_verbosity) > 1 || VG_(clo_trace_redir)) + VG_(dmsg)("%s syms at %#lx-%#lx in %s (have_dinfo %d)\n", + archive ? "Archiving" : "Discarding", + di->text_avma, + di->text_avma + di->text_size, + curr->fsm.filename ? curr->fsm.filename + : "???", + curr->have_dinfo); vg_assert(*prev_next_ptr == curr); if (!archive) { *prev_next_ptr = curr->next; @@ -1021,7 +1022,7 @@ ULong VG_(di_notify_mmap)( Addr a, Bool allow_SkFileV, Int use_fd ) Int actual_fd, oflags; SysRes preadres; HChar buf1k[1024]; - Bool debug = (DEBUG_FSM != 0); + const Bool debug = VG_(debugLog_getLevel)() >= 3; SysRes statres; struct vg_stat statbuf; @@ -1034,11 +1035,11 @@ ULong VG_(di_notify_mmap)( Addr a, Bool allow_SkFileV, Int use_fd ) vg_assert(seg); if (debug) { - VG_(printf)("di_notify_mmap-0:\n"); - VG_(printf)("di_notify_mmap-1: %#lx-%#lx %c%c%c\n", - seg->start, seg->end, - seg->hasR ? 'r' : '-', - seg->hasW ? 'w' : '-',seg->hasX ? 'x' : '-' ); + VG_(dmsg)("di_notify_mmap-0:\n"); + VG_(dmsg)("di_notify_mmap-1: %#lx-%#lx %c%c%c\n", + seg->start, seg->end, + seg->hasR ? 'r' : '-', + seg->hasW ? 'w' : '-',seg->hasX ? 'x' : '-' ); } /* guaranteed by aspacemgr-linux.c, sane_NSegment() */ @@ -1064,7 +1065,7 @@ ULong VG_(di_notify_mmap)( Addr a, Bool allow_SkFileV, Int use_fd ) return 0; if (debug) - VG_(printf)("di_notify_mmap-2: %s\n", filename); + VG_(dmsg)("di_notify_mmap-2: %s\n", filename); /* Only try to read debug information from regular files. */ statres = VG_(stat)(filename, &statbuf); @@ -1167,9 +1168,9 @@ ULong VG_(di_notify_mmap)( Addr a, Bool allow_SkFileV, Int use_fd ) # endif if (debug) - VG_(printf)("di_notify_mmap-3: " - "is_rx_map %d, is_rw_map %d, is_ro_map %d\n", - (Int)is_rx_map, (Int)is_rw_map, (Int)is_ro_map); + VG_(dmsg)("di_notify_mmap-3: " + "is_rx_map %d, is_rw_map %d, is_ro_map %d\n", + (Int)is_rx_map, (Int)is_rw_map, (Int)is_ro_map); /* Ignore mappings with permissions we can't possibly be interested in. */ if (!(is_rx_map || is_rw_map || is_ro_map)) @@ -1253,15 +1254,15 @@ ULong VG_(di_notify_mmap)( Addr a, Bool allow_SkFileV, Int use_fd ) mjw/thh. */ if (di->have_dinfo) { if (debug) - VG_(printf)("di_notify_mmap-4x: " - "ignoring mapping because we already read debuginfo " - "for DebugInfo* %p\n", di); + VG_(dmsg)("di_notify_mmap-4x: " + "ignoring mapping because we already read debuginfo " + "for DebugInfo* %p\n", di); return 0; } if (debug) - VG_(printf)("di_notify_mmap-4: " - "noting details in DebugInfo* at %p\n", di); + VG_(dmsg)("di_notify_mmap-4: " + "noting details in DebugInfo* at %p\n", di); /* Note the details about the mapping. */ DebugInfoMapping map; @@ -1285,13 +1286,14 @@ ULong VG_(di_notify_mmap)( Addr a, Bool allow_SkFileV, Int use_fd ) already read debuginfo for this object. So let's do so now. Yee-ha! */ if (debug) - VG_(printf)("di_notify_mmap-5: " - "achieved accept state for %s\n", filename); + VG_(dmsg)("di_notify_mmap-5: " + "achieved accept state for %s\n", filename); return di_notify_ACHIEVE_ACCEPT_STATE ( di ); } else { - /* If we don't have an rx and rw mapping, or if we already have - debuginfo for this mapping for whatever reason, go no - further. */ + /* If we don't have an rx and rw mapping, go no further. */ + if (debug) + VG_(dmsg)("di_notify_mmap-6: " + "no dinfo loaded %s (no rx or no rw mapping)\n", filename); return 0; } } @@ -1336,16 +1338,16 @@ void VG_(di_notify_mprotect)( Addr a, SizeT len, UInt prot ) declaration of struct _DebugInfoFSM for details. */ void VG_(di_notify_vm_protect)( Addr a, SizeT len, UInt prot ) { - Bool debug = (DEBUG_FSM != 0); + const Bool debug = VG_(debugLog_getLevel)() >= 3; Bool r_ok = toBool(prot & VKI_PROT_READ); Bool w_ok = toBool(prot & VKI_PROT_WRITE); Bool x_ok = toBool(prot & VKI_PROT_EXEC); if (debug) { - VG_(printf)("di_notify_vm_protect-0:\n"); - VG_(printf)("di_notify_vm_protect-1: %#lx-%#lx %c%c%c\n", - a, a + len - 1, - r_ok ? 'r' : '-', w_ok ? 'w' : '-', x_ok ? 'x' : '-' ); + VG_(dmsg)("di_notify_vm_protect-0:\n"); + VG_(dmsg)("di_notify_vm_protect-1: %#lx-%#lx %c%c%c\n", + a, a + len - 1, + r_ok ? 'r' : '-', w_ok ? 'w' : '-', x_ok ? 'x' : '-' ); } Bool do_nothing = True; @@ -1354,8 +1356,8 @@ void VG_(di_notify_vm_protect)( Addr a, SizeT len, UInt prot ) # endif if (do_nothing /* wrong platform */) { if (debug) - VG_(printf)("di_notify_vm_protect-2: wrong platform, " - "doing nothing.\n"); + VG_(dmsg)("di_notify_vm_protect-2: wrong platform, " + "doing nothing.\n"); return; } @@ -1367,7 +1369,7 @@ void VG_(di_notify_vm_protect)( Addr a, SizeT len, UInt prot ) is found, conclude we're in an accept state and read debuginfo accordingly. */ if (debug) - VG_(printf)("di_notify_vm_protect-3: looking for existing DebugInfo*\n"); + VG_(dmsg)("di_notify_vm_protect-3: looking for existing DebugInfo*\n"); DebugInfo* di; DebugInfoMapping *map = NULL; Word i; @@ -1397,8 +1399,8 @@ void VG_(di_notify_vm_protect)( Addr a, SizeT len, UInt prot ) return; /* didn't find anything */ if (debug) - VG_(printf)("di_notify_vm_protect-4: found existing DebugInfo* at %p\n", - di); + VG_(dmsg)("di_notify_vm_protect-4: found existing DebugInfo* at %p\n", + di); /* Do the upgrade. Simply update the flags of the mapping and pretend we never saw the RO map at all. */ @@ -1419,7 +1421,7 @@ void VG_(di_notify_vm_protect)( Addr a, SizeT len, UInt prot ) /* Check if we're now in an accept state and read debuginfo. Finally. */ if (di->fsm.have_rx_map && di->fsm.have_rw_map && !di->have_dinfo) { if (debug) - VG_(printf)("di_notify_vm_protect-5: " + VG_(dmsg)("di_notify_vm_protect-5: " "achieved accept state for %s\n", di->fsm.filename); ULong di_handle __attribute__((unused)) = di_notify_ACHIEVE_ACCEPT_STATE( di ); |
|
From: Philippe W. <phi...@so...> - 2018-09-01 16:53:18
|
https://sourceware.org/git/gitweb.cgi?p=valgrind.git;h=a214595daed7830a091dcd0f52c5b8073bfd04dd commit a214595daed7830a091dcd0f52c5b8073bfd04dd Author: Philippe Waroquiers <phi...@sk...> Date: Sat Sep 1 18:51:21 2018 +0200 Change filter_memcheck_monitor as glibc 2.27 seems to keep some more memory There is no real need to verify how much memory is still in use at exit, so filter this in filter_memcheck_monitor. Analysis by Dimitrije Nikolic Diff: --- gdbserver_tests/filter_memcheck_monitor | 1 + gdbserver_tests/mcclean_after_fork.stderr.exp | 2 +- gdbserver_tests/mcmain_pic.stderr.exp | 2 +- gdbserver_tests/mcsignopass.stderr.exp | 2 +- gdbserver_tests/mcsigpass.stderr.exp | 2 +- gdbserver_tests/mcwatchpoints.stderr.exp | 2 +- 6 files changed, 6 insertions(+), 5 deletions(-) diff --git a/gdbserver_tests/filter_memcheck_monitor b/gdbserver_tests/filter_memcheck_monitor index 431352b..f5a2e51 100755 --- a/gdbserver_tests/filter_memcheck_monitor +++ b/gdbserver_tests/filter_memcheck_monitor @@ -31,4 +31,5 @@ sed -e '/Cannot access memory at address 0x......../d' \ -e '/^Missing separate debuginfo/d' \ -e '/^Try: zypper install -C/d' \ -e 's/Test 3: FAIL: expected si_code==2, not 128/Test 3: PASS/' \ + -e 's/in use at exit: [0-9][0-9]* bytes in [0-9][0-9]* blocks/in use at exit: ... bytes in ... blocks/' \ -e '/^ total heap usage: /d' diff --git a/gdbserver_tests/mcclean_after_fork.stderr.exp b/gdbserver_tests/mcclean_after_fork.stderr.exp index 3bb7944..9107182 100644 --- a/gdbserver_tests/mcclean_after_fork.stderr.exp +++ b/gdbserver_tests/mcclean_after_fork.stderr.exp @@ -1,6 +1,6 @@ (action at startup) vgdb me ... HEAP SUMMARY: - in use at exit: 0 bytes in 0 blocks + in use at exit: ... bytes in ... blocks For a detailed leak analysis, rerun with: --leak-check=full For counts of detected and suppressed errors, rerun with: -v ERROR SUMMARY: 0 errors from 0 contexts (suppressed: 0 from 0) diff --git a/gdbserver_tests/mcmain_pic.stderr.exp b/gdbserver_tests/mcmain_pic.stderr.exp index d82a7ee..546bc37 100644 --- a/gdbserver_tests/mcmain_pic.stderr.exp +++ b/gdbserver_tests/mcmain_pic.stderr.exp @@ -1,6 +1,6 @@ (action at startup) vgdb me ... HEAP SUMMARY: - in use at exit: 16 bytes in 1 blocks + in use at exit: ... bytes in ... blocks For a detailed leak analysis, rerun with: --leak-check=full For counts of detected and suppressed errors, rerun with: -v ERROR SUMMARY: 0 errors from 0 contexts (suppressed: 0 from 0) diff --git a/gdbserver_tests/mcsignopass.stderr.exp b/gdbserver_tests/mcsignopass.stderr.exp index 7dbc9ee..4055b97 100644 --- a/gdbserver_tests/mcsignopass.stderr.exp +++ b/gdbserver_tests/mcsignopass.stderr.exp @@ -8,7 +8,7 @@ Test 2: PASS Test 3: PASS Test 4: PASS HEAP SUMMARY: - in use at exit: 0 bytes in 0 blocks + in use at exit: ... bytes in ... blocks For a detailed leak analysis, rerun with: --leak-check=full For counts of detected and suppressed errors, rerun with: -v ERROR SUMMARY: 11 errors from 1 contexts (suppressed: 0 from 0) diff --git a/gdbserver_tests/mcsigpass.stderr.exp b/gdbserver_tests/mcsigpass.stderr.exp index 7a754fd..e35e38a 100644 --- a/gdbserver_tests/mcsigpass.stderr.exp +++ b/gdbserver_tests/mcsigpass.stderr.exp @@ -8,7 +8,7 @@ Test 2: PASS Test 3: PASS Test 4: PASS HEAP SUMMARY: - in use at exit: 0 bytes in 0 blocks + in use at exit: ... bytes in ... blocks For a detailed leak analysis, rerun with: --leak-check=full For counts of detected and suppressed errors, rerun with: -v ERROR SUMMARY: 1 errors from 1 contexts (suppressed: 0 from 0) diff --git a/gdbserver_tests/mcwatchpoints.stderr.exp b/gdbserver_tests/mcwatchpoints.stderr.exp index 319547c..8d04da0 100644 --- a/gdbserver_tests/mcwatchpoints.stderr.exp +++ b/gdbserver_tests/mcwatchpoints.stderr.exp @@ -15,7 +15,7 @@ before rewriting 8 value 0nde4ine8 value of k50[1000] p HEAP SUMMARY: - in use at exit: 0 bytes in 0 blocks + in use at exit: ... bytes in ... blocks For a detailed leak analysis, rerun with: --leak-check=full For counts of detected and suppressed errors, rerun with: -v ERROR SUMMARY: 0 errors from 0 contexts (suppressed: 0 from 0) |