- linaro-toolchain - lists.linaro.org

Vector-alignment patch performance regressions

by Ulrich Weigand

Hello, I've had a look at the mp3player performance regressions (just with *some* data sets) with the vector-alignment patch. Interestingly it turns out that the patch basically does not change the generated code for the hot spot (inv_mdct routine) at all. (The *only* change is which bits of the incoming pointer the run-time alignment check generated by the vectorizer tests for. But this has no practical consequences, since the check itself is not hot, and the *decision* made by the check is the same anyway -- everything is in fact properly aligned at runtime.) The other difference, outside of code, introduced by the vector-alignment patch is that some global arrays used to be forcibly aligned to 16 bytes by the vectorizer, and they are now only aligned to 8 bytes. To check whether this makes a difference, I've modified the compiler as a hack to always force all global arrays to be 16 byte aligned. And interestingly enough, this appears to fix this particular performance regression ... Any thoughts as to why this might be the case? What are the recommendations on the ARM hardware side as to what alignment is prefered? Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzende des Aufsichtsrats: Martina Koederitz | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

13 years, 11 months

3
3
0 0

Currently open tasks for GCC wiki page.

by Ramana Radhakrishnan

Hi Uli, The currently open tasks wiki page has now been moved out of my Sandbox and in here. https://wiki.linaro.org/WorkingGroups/ToolChain/GCCPerfConnectQ212Notes Updated for status as of today . Please let me know if I've missed something . regards, Ramana

13 years, 11 months

1
0
0 0

Agenda for Performance call 7th August 2012.

by Ramana Radhakrishnan

https://wiki.linaro.org/WorkingGroups/ToolChain/Meetings/2012-08-07 Any updates please let me know or add to the wiki page as appropriate ? Ramana

13 years, 11 months

1
0
0 0

AND vs UXTB

by Mans Rullgard

I have noticed gcc has a preference for generating UXTB instructions when an AND with #255 would do the same thing. This is bad, because on A9 UXTB has two cycles latency compared to one cycle for AND. On A8 both instructions have one cycle latency. -- Mans Rullgard / mru

13 years, 11 months

4
4
0 0

[ACTIVITY] Jul 30 - Aug 3

by Ulrich Weigand

== GCC == * Checked in patch to change vector alignment to 8 to GCC mainline. * Started investigating benchmark regressions with Linaro GCC 4.7 backport of vector alignment patch. == GDB == * Checked in patch to fix hardware breakpoints on non-4-byte aligned (Thumb) instructions. * Checked in patch to properly report unsupported watchpoint address/length combinations in gdbserver. * Checked in patch to fix regression accessing /proc files on older Linux kernels. * Checked in 5 more patches to fix miscellaneous test suite regressions. * Re-tested GDB 7.5 pre-release on multiple platforms. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

13 years, 11 months

1
0
0 0

Distinguishing SF/HF ABI binaries, take two

by Steve McIntyre

[ Also posted to debian-arm; not cross-posted to avoid subscription complaints... ] Hi folks, We're currently carrying patches in glibc in Debian (and Ubuntu) that I wrote which are used to work out whether an ELF binary is hard-float or soft-float. We're using these to allow us to do the right thing on a multi-arch system, which is to pick a consistent set of binaries (programs and libraries) at runtime; if you try to mix binaries using different ABIs, you're prone to all kinds of weird and wonderful results but generally badness occurs. Upstream glibc have generally not been welcoming of these patches, and I understand this; the approach taken (reading ARM-specific build attributes) is far from clean and doesn't fit well in the design of ld.so in particular. So, I've been looking into alternative methods for achieving the goal of identifying ABI. After a couple of false starts and discussion with some of the helpful toolchain and ABI folks in ARM, I think we have a solution that will work well in the long term. I just wish we'd thought about this *way* back when we first started the armhf port, as it would have been much easier to work on and standardise this back then. Modulo availability of time machines, there's not much we can do on that front... :-) What I'm proposing is to use two new values in the OSABI field in the ELF header: #define ELFOSABI_LINUX_ARM_AEABI_SF 65 #define ELFOSABI_LINUX_ARM_AEABI_HF 66 and use these values in the future for soft- and hard-float binaries so that can unambiguously identify them. There's already precedent for binaries using different values in this field, with support in glibc for parsing and understanding them. Adding more possible values is quite easy, assuming that the maintainers are amenable. I'm about to post a similar message there. I have a plan of attack for how to make a staged switch over, deliberately to minimise any potential compatibility problems. See the attached doc for that. It's deliberately not very specific in terms of timeline, as that's something I'm hoping to get feedback about. Comments very welcome; please point out if you think there are problems with this approach, or if there are any more implementations of toolchain / linker that will need to be addressed. Cheers, -- Steve McIntyre steve.mcintyre(a)linaro.org <http://www.linaro.org/> Linaro.org | Open source software for ARM SoCs

13 years, 11 months

5
13
0 0

[ACTIVITY] report week 31

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-20 || 2012-07-20 || ||clean-up-kvm-patches || || || || ||track-kvm-abi-changes || || || || ||fake-trustzone || || || || Overall KVM plan for 'do by end August': QEMU parts of this are a mix of clean-up-kvm-patches and track-kvm-abi-changes blueprints, mostly. http://cards.linaro.org/browse/CARD-167 == other == * cleaned up qemu benchmarking setup into something reproducible * upstream patch review KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&…

13 years, 11 months

1
0
0 0

Seeing __dso_handle link errors when building Android?

by Michael Hope

For reference, if you see link time errors about a missing '__dso_handle' symbol when building Android, then check if you're using any global class instances in your multimedia libraries. Each shared library has a __dso_handle symbol which is filled in on load by the dynamic loader. Global class instances use this unique value to make sure the destructor is called when the library is unloaded. The symbol itself is defined in crtbegin_so.o, but the multimedia rules forbid using this for an unknown reason. Either create your global instances in a different way or change the multimedia rules :) -- Michael

13 years, 11 months

1
0
0 0

Remaining release steps

by Michael Hope

Hi Ramana. These are covered by the release process documentation but I thought I'd fill them out. The builds are completing. You can see the finished grid at: http://ex.seabright.co.nz/helpers/buildlog/gcc-linaro-4.7-2012 Click on 'Compare' for each machine to see the results like: http://ex.seabright.co.nz/helpers/testcompare/gcc-linaro-4.7-2012.07/logs/a… The test compare picks a close version but falls back to something ancient. Add the correct previous version like: http://ex.seabright.co.nz/helpers/testcompare/gcc-linaro-4.7-2012.07/logs/a… Check for any differences by searching for 'Just in'. A is the previous release, B is this. There's one regression in http://ex.seabright.co.nz/helpers/testcompare/gcc-linaro-4.7-2012.07/logs/a… which is: gcc.target/arm/pr42172-1.c scan-assembler-times ldr 1 I'd normally check our upstream builds: http://ex.seabright.co.nz/helpers/buildlog/gcc-4.7+svn but this is a ARMv5 fault and we only track Cortex-A9. Checking gcc-testresults shows: http://gcc.gnu.org/ml/gcc-testresults/2012-07/msg00171.html so the fault is upstream. I've spawned the test-oecore-gcc-linaro-4.7-2012.07 / x86_64-heavy and ubutest-gcc-linaro-4.7-2012.07 / i686,x86_64 jobs. The results will pop up similar to the 4.6 ones in the buildlog. -- Michael

13 years, 11 months

2
3
0 0

[Activity ] Week 30

by Ramana Radhakrishnan

== Progress == * Fixed PR54051 * Improved neon intrinsics testsuite. While still not an execution based testsuite atleast we get compile time tests that are sensible C. Exposed issues - wrote patches. that improve vabal , vaba intrinsics. Fix an issue with costs, fixed an issue with splitters for large mode moves for Neon with hardfp port etc. * Some upstream patch and bug review. * Fixed a minor testism for vld1q_s64 tests. == Plans == * Write a patch to check md5sums between local tarball and uploaded tarball in the release script. * Look at auto-inc-dec patches more and investigate benchmark results. * Submit intrinsics work upstream and sheperd it through. * Finish looking at PR53664 and clean up testsuite further. * Follow-up on my intrinsics patches upstream. == Absences == * 17th Sept - 5th Oct - Vacation approved.

13 years, 11 months

1
0
0 0

[ACTIVITY] Jul 23 - Jul 27

by Ulrich Weigand

== GCC == * Checked in fix fix for incorrect pool placement with -O0 by splitting all insns in machine-dependent reorg. * Created blueprint to investigate -funroll-loops and -fvariable-expansion-in-unroller. * Took over patch to change vector alignment to 8 from Richard; reworked according to review comments; found and fixed two vectorizer bugs triggered by the change; submitted for mainline approval. * Continued investigation of reload bug reported by ARM. Posted potential fix to gcc-patches for discussion. == GDB == * Worked on fixing HW breakpoint/watchpoint regressions. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

13 years, 11 months

1
0
0 0

[ACTIVITY] report week 30

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-20 || 2012-07-20 || ||clean-up-kvm-patches || || || || ||track-kvm-abi-changes || || || || ||fake-trustzone || || || || Overall KVM plan for 'do by end August': QEMU parts of this are a mix of clean-up-kvm-patches and track-kvm-abi-changes blueprints, mostly. http://cards.linaro.org/browse/CARD-167 == clean-up-kvm-patches == * sent patch series to try to clean up some QEMU kvm x86isms that block cleanup of some of the ARM KVM support code; dealt with review comments and sent v2 == other == * started on cleaning up the QEMU benchmarking setup so we can put it on a server machine somewhere * fixed a crash in the QEMU ARMv7M models which was introduced by one of my earlier GIC/NVIC refactoring series * upstream review/maintainer duties KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&… -- PMM

13 years, 11 months

1
0
0 0

Fwd: [cbuild] gcc-4.8~svn189808 armv7l failed

by Michael Hope

FYI GCC trunk r189808 fails to build with a bootstrap comparison error: Comparing stages 2 and 3 warning: gcc/cc1-checksum.o differs warning: gcc/cc1plus-checksum.o differs warning: gcc/cc1obj-checksum.o differs warning: gcc/cc1objplus-checksum.o differs Bootstrap comparison failure! arm-linux-gnueabi/libgcc/unwind-arm.o differs arm-linux-gnueabi/libgcc/unwind-arm_s.o differs 189575 was fine on hard float. 189745 is fine on softfp. -- Michael ---------- Forwarded message ---------- From: Linaro Toolchain Builder <michael.hope+cbuild(a)linaro.org> Date: 25 July 2012 15:59 Subject: [cbuild] gcc-4.8~svn189808 armv7l failed To: "michael.hope+notify(a)linaro.org" <michael.hope+notify(a)linaro.org> ursa3 finished running job gcc-4.8~svn189808 on armv7l-precise-cbuild348-ursa3-cortexa9hfr1. The results are here: http://builds.linaro.org/toolchain/gcc-4.8~svn189808 This email is sent from a cbuild (https://launchpad.net/cbuild) based bot which is administered by Michael Hope <michael.hope(a)linaro.org>.

13 years, 11 months

3
3
0 0

Re: Agenda for tomorrow's call.

by Steven Bosscher

Hello Ramana, For your PGO list: * please note that I've been working on PGO for switch code, and also for chains of if-statements with a common condition variable (with Tom de Vries) * turning conditional execution off will not make a difference, your profile information will be exactly the same. Profile instrumentation happens very early in the pipe line (on purpose, PGO is more accurately "coverage guided optimization", not profiling in the prof/gprof/oprofile sense). And the parts of the CFG that have profile instrumentation cannot be if-converted anyway. * you can use the script "analyze_brprob" in contrib/ to measure the accuracy of the branch predictors. The script needs some TLC, fixing it is on my TODO list but let me know if linaro folks are going to take care of that. You'll find that the predictors are heavily tuned towards the original Opteron, I'm not aware of much tuning for other architectures. * The heuristics for profile-guided optimizations are also not tuned for arm. In the past we found that some params have more influence than others (the TRACER* parameters for example). Hope this helps, What do you mean with "Only conditionalise those parts that benefit"? Ciao! Steven

13 years, 11 months

2
1
0 0

Agenda for tomorrow's call.

by Ramana Radhakrishnan

https://wiki.linaro.org/WorkingGroups/ToolChain/Meetings/2012-07-24 is now online. If folks have anything they'd like to add can they do so ? Ramana

13 years, 11 months

1
0
0 0

[Activity] Week 28

by Ramana Radhakrishnan

== Progress == * Looking at auto-inc-dec patches. * sched-pressure now on by default in FSF 4.8 * Background look into neon costs and vdup improvements. * Some upstream patch review. * Discovered http://gcc.gnu.org/PR54051 while testing a neon intrinsics patch and wrote a patch to fix it. == Plans == * Write a patch to check md5sums between local tarball and uploaded tarball in the release script. * Look at auto-inc-dec patches more and investigate benchmark results. * Finish submitting PR54051 patch upstream. * Finish vdup folding patch.

13 years, 11 months

1
0
0 0

[ANNOUNCE] Linaro Toolchain Binaries 2012.07 released

by Zhenqiang Chen

The Linaro Toolchain Working Group is pleased to announce the 2012.07 release of the Linaro Toolchain Binaries, a pre-built version of Linaro GCC and Linaro GDB that runs on generic Linux or Windows and targets the glibc Linaro Evaluation Build. Uses include: * Cross compiling ARM applications from your laptop * Remote debugging * Build the Linux kernel for your board What's included: * Linaro GCC 4.7 2012.07 * Linaro GDB 7.4 2012.06 * A statically linked gdbserver * A system root * Manuals under share/doc/ The system root contains the basic header files and libraries to link your programs against. Interesting changes include: * Change c++, gcc and ld to symlinks in Linux package The Linux version is supported on Ubuntu 10.04.3 and 12.04, Debian 6.0.2, Fedora 16, openSUSE 12.1, Red Hat Enterprise Linux Workstation 5.7 and later, and should run on any Linux Standard Base 3.0 compatible distribution. Please see the README about running on x86_64 hosts. The Windows version is supported on Windows XP Pro SP3, Windows Vista Business SP2, and Windows 7 Pro SP1. The binaries and build scripts are available from: https://launchpad.net/linaro-toolchain-binaries/trunk/2012.07 Need help? Ask a question on https://ask.linaro.org/ Already on Launchpad? Submit a bug at https://bugs.launchpad.net/linaro-toolchain-binaries On IRC? See us on #linaro on Freenode. Other ways that you can contact us or get involved are listed at https://wiki.linaro.org/GettingInvolved.

13 years, 11 months

1
0
0 0

Ongoing benchmark graphs

by Michael Hope

We've just started running a weekly benchmark of GCC trunk and Linaro GCC tip. I've written a short script that compares against a baseline and spits out a graph: http://ex.seabright.co.nz/benchmarks/gcc-4.8~svn.png http://ex.seabright.co.nz/benchmarks/gcc-linaro-4.7%2bbzr.png I'll switch the baseline to GCC 4.7.0 once the build and benchmark run completes. The gcc-linaro results need more data before they'll make sense. Part way there. An automatic email would be next. We should check the graphs before each performance call. -- Michael, who needs to get moving on LAVA

13 years, 11 months

3
5
0 0

[ACTIVITY] Jul 16 - Jul 20

by Ulrich Weigand

== GCC == * Checked in fix to LP bug 1020601 (missed optimization with multiple __builtin_unreachable calls) to Linaro GCC 4.7. * Implemented and tested alternative fix for incorrect pool placement with -O0 by splitting all insns in machine- dependent reorg. * Continued investigation of reload bug reported by ARM. == GDB == * Tested GDB 7.5 branch on ARM, found a couple of regressions. Worked on fixing HW breakpoint/watchpoint regressions. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

13 years, 12 months

1
0
0 0

[ACTIVITY] report week 29

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-20 || 2012-07-20 || ||clean-up-kvm-patches || || || || ||track-kvm-abi-changes || || || || ||fake-trustzone || || || || Overall KVM plan for 'do by end August': QEMU parts of this are a mix of clean-up-kvm-patches and track-kvm-abi-changes blueprints, mostly. http://cards.linaro.org/browse/CARD-167 == a15-lpae-support == * LPAE patches now merged upstream * v2 of vexpress-large-ram-size sent upstream, code reviewed and put into arm-devs pullreq. Hasn't hit master yet but I expect that to happen over the next week. == clean-up-kvm-patches == * squashed together some kvm patches in the qemu-linaro tree * sent upstream a few patches where we can avoid an ARM-KVM specific change by instead generalising the upstream code not to have an explicit list of KVM supporting architectures * started looking at how best to clean up some working-but-ugly code handling interrupts in the QEMU KVM-ARM patchset. Among other problems, this is messy to fix because at the moment upstream is overloading "is there an in kernel irqchip?" to mean both "should we use QEMU's irqchip model or not?" and "is the interrupt injection model synchronous or asynchronous?" because on x86 they are (for historical reasons) the same. For ARM we only want to decide which irqchip model to use, not anything else... == other == * upstream review (various exynos patches, mostly) * some patches fixing problems with compiler warnings in configure test fragments * arm-devs pullreq KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&… -- PMM

13 years, 12 months

1
0
0 0

Help with gcov-7.c aborting

by Michael Hope

Hi Ramana, Ulrich. Could I have some help with an unexpected testsuite failure while backporting Carrot's adddi patch? testsuite/gcc.misc-tests/gcov-7.c builds and runs but aborts during leave() due to unexpected results. The merge request is here: https://code.launchpad.net/~michaelh1/gcc-linaro/core-adddi/+merge/113111 The testsuite diff is here: http://ex.seabright.co.nz/build/gcc-linaro-4.7+bzr115001~michaelh1~core-add… The build tree is at: cbuild@tcpanda02.v:/scratch/cbuild/slave/slaves/tcpanda02/gcc-linaro-4.7+bzr115001~michaelh1~core-adddi/gcc/default/build The failing and working versions are on tcpanda02 as ~/gcov-7.exe and ~/gcov-7-ok. Here's the details: * The test is fine when built from the command line * The test is fine on the hard float Precise build * The failing binary works fine when run on Precise * The disassembled body (not libraries) is identical modulo changes in addresses * The fault goes away with a static linking via adding "--tool_opts '-static'" * The fault persists with binutils 2.22 * The fault persists with the eglibc 2.15 loader I assume the testsuite picks up a different libgcc and libgcov somehow which gives a different executable. It's strange that the static linked version is fine, and that the failing binary works fine on a different host. Could you have a poke in the build tree? -- Michael

13 years, 12 months

2
5
0 0

Libav benchmarks

by Mans Rullgard

I ran my usual set of benchmarks of libav compiled with the current gcc releases (hand-written assembly disabled). The results are in this spreadsheet: https://docs.google.com/spreadsheet/ccc?key=0AguHvNGaLXy9dHExeWZ1YWZ1c0s2Vn… First the good news, almost everything is faster with 4.6+ than with linaro-4.5. The bad news is that some things have regressed since 4.6, even if not all the way back to 4.5 levels. A few especially problematic pieces stand out: - The mp3 test performs 5-15% worse. This regression is (mostly) attributable to the ff_mpadsp_apply_window_fixed [1] function. We have looked at this one before. - FLAC is 9% slower in upstream 4.7/4.8 compared to Linaro releases. Here flac_lpc_16_c [2] and flac_decorrelate_indep_c_16 [3] are mainly to blame. - MPEG2/MPEG4 decoding is ~10% slower with vectorisation turned on. The culprit here is ff_simple_idct_8_c [4] function. - H.264 and DTS seem 1-2% slower, although this could be just noise. - Code size has increased by ~10% in all post-4.6 releases. In all cases, compiled with -O3 -mcpu=cortex-a9. The vectorised builds all use -fvect-cost-model. Without this flag the results are much worse. [1] http://git.libav.org/?p=libav.git;a=blob;f=libavcodec/mpegaudiodsp_template… [2] http://git.libav.org/?p=libav.git;a=blob;f=libavcodec/flacdsp.c;h=a2e335b4d… [3] http://git.libav.org/?p=libav.git;a=blob;f=libavcodec/flacdsp_template.c;h=… [4] http://git.libav.org/?p=libav.git;a=blob;f=libavcodec/simple_idct_template.… -- Mans Rullgard / mru

14 years

2
3
0 0

[ACTIVITY] Jul 9 - Jul 13

by Ulrich Weigand

== GCC == * Tom de Vries fixed root cause of LP bug 1020601 (missed optimization with multiple __builtin_unreachable calls) on mainline. Backported to Linaro GCC 4.7 and tested. Fixed bug exposed by backport (latent in mainline). * Continued investigation of reload bug reported by ARM. == Misc == * Attended GNU Tools Cauldron in Prague. Presented on GDB remote/native feature parity work. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years

1
0
0 0

[ACTIVITY] report week 27

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-20 || || ||clean-up-kvm-patches || || || || ||track-kvm-abi-changes || || || || ||fake-trustzone || || || || Overall KVM plan for 'do by end August': QEMU parts of this are a mix of clean-up-kvm-patches and track-kvm-abi-changes blueprints, mostly. http://cards.linaro.org/browse/CARD-167 == a15-lpae-support == * LPAE patchset in latest target-arm pullreq sent upstream * Kernel patch to get it not to throw away high bits of RAM size Acked by Will and sent to RMK's patch system * vexpress patchset for large RAM sizes had a few review issues which I think I've sorted; need to roll a v2 * push back estimate date a week to account for: large-ram-size work wasn't in my original list of work here; code review wait times [ie not much real work remaining, but some time delay] == other == * updated to new fast model and kernel and rechecked that my local setup still works OK * qemu-linaro 2012.07 released * usual upstream patch review * finally bit the bullet and upgraded my ancient Ubuntu desktop KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&…

14 years

1
0
0 0

[ANNOUNCE] Linaro GCC 4.7 and 4.6 2012.07 released.

by Ramana Radhakrishnan

The Linaro Toolchain Working Group is pleased to announce the 2012.07 release of both Linaro GCC 4.7 and Linaro GCC 4.6. Linaro GCC 4.7 2012.07 is the fourth release in the 4.7 series. Based off the latest GCC 4.7.0+svn189098 release, it includes performance improvements around choice of auto-increment based addressing modes for floating point values. Interesting changes include: Updates to GCC 4.7.0+svn189098 Implements improvements to ivopts selection of addressing modes of floating point values. Fixes: LP: #1010826 - Invalid unaligned loads in vectorized code. Linaro GCC 4.6 2012.07 is the seventeenth release in the 4.6 series. Based off the latest GCC 4.6.3+svn189058 release, this is the fourth release after entering maintenance. Interesting changes include: Updates to 4.6.3+svn189058 Fixes: LP: #1010826 - Invalid unaligned loads in vectorized code. LP: #1013209 - Internal compiler error when building neon intrinsics. The source tarballs are available from: https://launchpad.net/gcc-linaro/+milestone/4.7-2012.07 https://launchpad.net/gcc-linaro/+milestone/4.6-2012.07 Downloads are available from the Linaro GCC page on Launchpad: https://launchpad.net/gcc-linaro More information on the features and issues are available from the release page: https://launchpad.net/gcc-linaro/4.7/4.7-2012.07 https://launchpad.net/gcc-linaro/4.6/4.6-2012.07 Mailing list: http://lists.linaro.org/mailman/listinfo/linaro-toolchain Bugs: https://bugs.launchpad.net/gcc-linaro/ Questions? https://ask.linaro.org/ Interested in commercial support? Inquire at support(a)linaro.org

14 years

1
0
0 0

[ANNOUNCE] Linaro QEMU 2012.07 released

by Peter Maydell

The Linaro Toolchain Working Group is pleased to announce the release of Linaro QEMU 2012.07. Linaro QEMU 2012.07 is the latest monthly release of qemu-linaro. Based off upstream (trunk) QEMU, it includes a number of ARM-focused bug fixes and enhancements. There are no major changes in this month's release, though it has been updated to track the latest upstream QEMU changes. Known issues: - Graphics do not work for OMAP3 based models (beagle, overo) with 11.10 Linaro images. - Audio may not work on Versatile Express models with the latest Linaro kernel/hardware packs (LP:977610). The source tarball is available at: https://launchpad.net/qemu-linaro/+milestone/2012.07 More information on Linaro QEMU is available at: https://launchpad.net/qemu-linaro

14 years

1
0
0 0

[ACTIVITY] Jul 2 - Jul 6

by Ulrich Weigand

== GCC == * Investigated bootstrap comparison failure with neon-shifts branch; tracked down root cause to pre-existing bug in GCC common code. Fix checked in to FSF mainline and 4.7 branch. * Investigated di-sync-multithread test case failure with neon-shifts branch; root cause was missing length attributes for sync.md insn&split patterns. Implemented fix and restarted tests. * Investigated LP bug 1020601, missed optimization with multiple __builtin_unreachable calls. Tracked down root cause and started discussion of possible fixes on gcc-patches. * Investigated potential reload bug reported by ARM. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years

1
0
0 0

[Activity] Week 27

by Ramana Radhakrishnan

RAG Amber: 4.7 2012.07 source release for reasons described below. Green : 4.6 2012.07 source release done. == Progress == * Worked on auto-inc-dec scheduler changes.First cut patch looking reasonable. * Committed the neon permute intrinsics upstream. * Release week : release tarballs prepared for 4.6 . The 4.6 release is GREEN. I will upload the release on Thursday morning after I am back in the office. The 4.7 release had some issues - I had to rerun the release script because the merge contained some artifacts which were a result of merge conflicts. Having respun the release it turned out that the rsync from my machine to cbuild failed, which meant that I ended up testing the same snapshot twice.Given that the 2 tarballs only differ in the .rej and the .orig files and nothing more I'm not too worried about this because it should ideally just work. The good news is that ubutest and everything else went through ok. The bad news is that the oe build appears to be borked. We need to investigate that further. Having looked inside the tarballs and seen that the .rej and .orig files were the only things different between the 2 tarballs I don't think it's a huge problem for the release. I;ve spawned off another set of builds to be absolutely sure . * Looked at neon costs and vdup improvements . The neon cost changes could cause regressions with 64 bit arithmetic and hence need to be looked at carefully. The vdup improvements cause carnage in gcc.target/arm/neon and tests for intrinsics have to be improved. == Plans == * GNU Tools cauldron next week. * Deal with release week fall-out. * Write a patch to check md5sums between local tarball and uploaded tarball in the release script. * Look at auto-inc-dec patches more. * Background look into improving some of the tests that now fail with the vdup patches. == Absences == * 8th - 11th July - GNU Tools Cauldron. * 17th Sept - 5th Oct - Vacation planned, yet to be approved.

14 years

1
0
0 0

[ACTIVITY] report week 27

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-13 || || ||clean-up-kvm-patches || || || || ||track-kvm-abi-changes || || || || ||fake-trustzone || || || || Overall KVM plan for 'do by end August': QEMU parts of this are a mix of clean-up-kvm-patches and track-kvm-abi-changes blueprints, mostly. http://cards.linaro.org/browse/CARD-167 == a15-lpae-support == * did the basic benchmarking of the LPAE series; using 64 bits for guest physical addresses has between 0 and 0.5% hit to performance, which IMHO is sufficiently minimal that it is not a problem. * wrote a set of follow-up patches which allow the vexpress-a15 model to accept large RAM sizes (mostly turning off the "too big" user-error message, fixing some over-small types in the QEMU boot loader and adding support for handling device tree blobs with 64 bit address/size fields). * discovered that Linux will happily throw away the top 32 bits of a device tree memory node's size field. Wrote a patch for this, which works but needs redoing to fix in a cleaner way. == other == * qemu-linaro 2012.07 release prep: bug triage, investigation, rolling tarball, testing * arm-devs pullreq KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&… -- PMM

14 years

2
2
0 0

Draft release notes for 2012.07

by Ramana Radhakrishnan

Draft release notes are here https://wiki.linaro.org/RamanaRadhakrishnan/Sandbox/GCC201207DraftReleaseNo… Can folks have a quick look to see if I've missed something ? Ramana

14 years

2
1
0 0

broken fsf gcc-4.7 merge

by Matthias Klose

Hi, I didn't look if the files were correctly merged or not. but the .orig and .rej files don't belong here. It might be worth to update the merge to r189186, reverting the c++98/c++11 ABI incompatibility in std::list. Matthias revno: 115001 [merge] committer: Michael Hope <michael.hope(a)linaro.org> branch nick: 4.7 timestamp: Tue 2012-07-03 20:16:55 +1200 message: Merge from FSF (GCC SVN branches/gcc-4_7-branch:189098) added: gcc/config.gcc.rej gcc/config/arm/arm.c.orig gcc/config/arm/arm.c.rej gcc/config/avr/avr-stdint.h gcc/configure.ac.rej gcc/configure.rej [...]

14 years

2
1
0 0

[Activity] Week 26

by Ramana Radhakrishnan

== Progress == * Testing costs changes for Neon intrinsics. * Fixed the regression I added to the Linaro 4.6 tree - committed there. Looked at a few vagaries around testresults. * Started looking at auto-inc-dec scheduler changes. * 1/2 a day lost to visa application process * Usual 1:1s . * Upstream patch review. == Plans == * Work on auto-inc-dec scheduler changes. * Ping current neon intrinsics patches and get them in. * Release week dry-run to be done next week - and finish creating the release tarballs by 6th of July * Upstream patch review. * Collect passport on Tuesday / Wed afternoon. == Absences == * 8th - 12th July - GNU Tools Cauldron. * 17th Sept - 5th Oct - Vacation planned, yet to be approved.

14 years

1
0
0 0

Agenda for tomorrow's performance meeting.

by Ramana Radhakrishnan

https://wiki.linaro.org/WorkingGroups/ToolChain/Meetings/2012-07-03 Ramana

14 years

1
0
0 0

Auto builder failures

by Michael Hope

We've had a few testsuite failures recently which were due to the auto builder itself. I've started a log at: https://wiki.linaro.org/WorkingGroups/ToolChain/CBuild/FailureLog so we can track the incident rate and see if there's a pattern. Zhenqiang, if you see an unexpected failure could you respawn the build and notify me? -- Michael

14 years

4
11
0 0

How to do a manual bzr merge when "bzr merge" fails

by Andrew Stubbs

Hi all, Right now, it's impossible to merge from lp:gcc/4.7 to lp:gcc-linaro/4.7. This is due to a BZR bug of some kind, so hopefully we won't have to work around it for too much longer. According to the nice folks at #bzr, here's how to do the same merge manually: bzr branch lp:gcc-linaro/4.7 cd gcc-linaro bzr log | less # find the last merge revision (it should be clear from the message) # grab the *SVN* revision number bzr log --show-ids lp:gcc/4.7 | less # search for the *SVN* revision number # (it should appear on the end of a "revision-id" line, not "parent") # grab the corresponding *BZR* revision number ("revno") bzr diff -r <bzr-revno> lp:gcc/4.7 > ../patch patch -p0 -i ../patch # resolve conflicts, rejected hunks, etc. bzr add --file-ids-from lp:gcc/4.7 # if it's doing the right thing you'll get messages like: # "adding <file> w/ file id from <file>" # if it just says "adding file" then you got something wrong # edit Changelog.linaro, as usual bzr ci bzr push lp:~.........gcc-linaro/merge-from.... After all that, a future "bzr merge" should just work (once the bug has been fixed). Anyway, I doubt there's anybody else needs to know this: I've just posted it in case I get hit by a bus before next month. Andrew

14 years

3
2
0 0

[ACTIVITY] Jun 25 - Jun 29

by Ulrich Weigand

== GCC == * GCC PR 53636 fix caused regression on powerpc64 and sparc64; committed fix upstream and to Linaro GCC 4.7. * Backported GCC PR 53636 fix --including regression fix-- to Linaro GCC 4.6. * Reworked Andrew's neon-shifts branch to reliably use NEON for "left shift by register"; fix typo in "left shift by 1"; overall simplification of implementation. Tests restarted. == GDB == * Investigated remaining GDB/Android work; reviewed card. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years

1
0
0 0

[ACTIVITY] report week 26

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-13 || || ||clean-up-kvm-patches || || || || ||track-kvm-abi-changes || || || || ||fake-trustzone || || || || The blueprints clean-up-kvm-patches and track-kvm-abi-changes include dependencies on kernel side work which makes it hard to set a date; however I'm hoping to get them either done or mostly done within the next two months. == cp15-rework == * patches were committed to master, blueprint complete == a15-lpae-support == * worked on a set of patches to lay groundwork for this: mostly this is extending the size of QEMU's 'target physical address' type to 64 bits for ARM (potentially a small perf hit for the 32 bit only ARM cores; benchmarking still to be done) * wrote patches to implement all the various pieces of LPAE, confirmed that Linux with LPAE enabled boots, sent patches to list * started looking into whether there are any bits of LAVA that make sense to use for QEMU benchmarking == other == * fixed a missing Makefile line that meant qemu-linaro wouldn't build on ARM targets with KVM enabled * reviewed a pile of outstanding patches (including SDHCI, i.MX31) and am now caught up with the post-holiday backlog KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&… -- PMM

14 years

1
0
0 0

which toolchain version supports sdiv and udiv instructions?

by Xiao Jiang

Hello, I tried codesourcy arm-2012.03-57-arm-none-linux-gnueabi-i686-pc-linux-gnu.tar.bz2, and get below err infos. Error: selected processor does not support ARM mode `sdiv R2,R0,R1' Error: selected processor does not support ARM mode `udiv R2,R0,R1' Does it mean this toolchain version don't support both instructions? and which toolchain can support them? Thanks a lot! Xiao

14 years

2
4
0 0

[ACTIVITY] Jun 18 - Jun 22

by Ulrich Weigand

== GCC == * GCC PR 53636 fix caused regression on powerpc64 and sparc64; investigated, determined root cause, and implemented fix. == GDB == * Took over remaining GDB/Android work from Thiago. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years

1
0
0 0

[ANNOUNCE] Linaro Toolchain Binaries 2012.06 released

by Zhenqiang Chen

The Linaro Toolchain Working Group is pleased to announce the 2012.06 release of the Linaro Toolchain Binaries, a pre-built version of Linaro GCC and Linaro GDB that runs on generic Linux or Windows and targets the glibc Linaro Evaluation Build. Uses include: * Cross compiling ARM applications from your laptop * Remote debugging * Build the Linux kernel for your board What's included: * Linaro GCC 4.7 2012.06 * Linaro GDB 7.4 2012.06 * A statically linked gdbserver * A system root * Manuals under share/doc/ The system root contains the basic header files and libraries to link your programs against. Interesting changes include: * Refine the system root The Linux version is supported on Ubuntu 10.04.3 and 12.04, Debian 6.0.2, Fedora 16, openSUSE 12.1, Red Hat Enterprise Linux Workstation 5.7 and later, and should run on any Linux Standard Base 3.0 compatible distribution. Please see the README about running on x86_64 hosts. The Windows version is supported on Windows XP Pro SP3, Windows Vista Business SP2, and Windows 7 Pro SP1. The binaries and build scripts are available from: https://launchpad.net/linaro-toolchain-binaries/trunk/2012.06 Need help? Ask a question on https://ask.linaro.org/ Already on Launchpad? Submit a bug at https://bugs.launchpad.net/linaro-toolchain-binaries On IRC? See us on #linaro on Freenode. Other ways that you can contact us or get involved are listed at https://wiki.linaro.org/GettingInvolved.

14 years

1
0
0 0

[ACTIVITY] report week 23

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || || ||clean-up-kvm-patches || || || || ||track-kvm-abi-changes || || || || ||fake-trustzone || || || || ||a15-lpae-support || || || || (dates to come next week) == cp15-rework == * sent out pull request including these patches, so it should get committed to master in the next few days == a15-lpae-support == * started on getting ARM qemu to work with 64 bit physaddrs (first stage mostly a tedious code audit) == other == * email catchup following holiday * rebased various trees, sent out pullreqs for outstanding ARM QEMU patches Michael H has set up a web page which tracks progress on KVM related blueprints here: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&… This includes QEMU blueprints related to KVM. -- PMM

14 years

1
0
0 0

Summary of the 64 bit NEON improvements

by Michael Hope

I've gone through and checked the 64 bit operation improvements that Andrew has made to GCC. For everything but the Cortex-A8, GCC uses the NEON unit for 64 bit operations and Andrew's improvements mean we can stay on NEON for longer without having an expensive transfer back and forth to the core registers. The results are here: https://wiki.linaro.org/MichaelHope/Sandbox/64BitOperations Once we've fixed the shift-left-by-n pattern I'll turn this into an Outputs[1] page. Benchmark results have been sent to the linaro-toolchain-benchmarks list. -- Michael

14 years

1
0
0 0

[ACTIVITY] weekly status

by Ken Werner

Hi, OpenEmbedded-Core/meta-linaro: * updated OE-Core cbuild to pick up a recent snapshot of meta-linaro * verified the release candidate of the Linaro binary toolchain 12.06 * prepared meta linaro for the upcoming release of our binary toolchain * started on a linaro-qemu recipe but didn't finish it misc: * boot Linaro Android using QEMU: https://wiki.linaro.org/KenWerner/Sandbox/AndroidQEMU Regards, Ken

14 years

1
0
0 0

[Activity] Week 24

by Ramana Radhakrishnan

== Progress == * Tried a number of testcases for the shuffles . Needed to add support to the C++ frontend for the __builtin_shuffle support. Fortunately there existed a patch - I tested it and it looked good. Committed upstream. However the original author had some concerns whether it would work in C++ or not but we shall see. The OP is concerned that it might break C++11 and constexpr which need to be looked at . * Briefly investigated a regression with Linaro GCC 4.6 with Neon intrinsics. It looks like my patch to allow LTO to proceed has had some fall out . We really need some good tests in the GCC testsuite for intrinsics. * Looked at the Android documents and commented. * Some upstream patch review. == Plans == * Follow on the C++11 issues with the __builtin_shuffle patch if any. * Commit the __builtin_shuffle variation of the neon intrinsics patch into FSF 4.8. The improvements obtained are real and nice atleast for the testcases that we could see after finishing up the testcases. * There is some follow-up work which should tie in nicely with costs rework - lower-subreg ends up splitting things a bit badly in some cases with vld4 style intrinsics and for V4SF copies. So it's better we try to get the costs right. I suspect this might be harming us in a few cases with auto-vectorized code as well. Especially where we vectorize with the large vldn instructions. * Investigate the 4.6 regression with Neon intrinsics. * Auto-inc-dec scheduler work.

14 years

1
0
0 0

Linaro Android toolchain linking problem

by Marius Cetateanu

Hi, I'm trying to build some shared libraries with the Linaro Android toolchain. For all of my libraries I get the following errors from the linker: |BlaBla.cpp.o: requires unsupported dynamic reloc R_ARM_REL32; recompile with -fPIC /home/dev/android/android_linaro_toolchain/libexec/gcc/arm-linux-androideabi/4.7.1/real-ld: error: hidden symbol '__dso_handle' is not defined locally | I'm using -fPIC in the compiler's flags so I'm not sure why the linker is complaining. The |__dso_handle| error is supposed to have been fixed in the NDKr6. I tried the Linaro 4.7.1(2012.05) toolchain, the one available for download, one of the daily builds from Linaro of the same toolchain(the one from Friday last week) and I also rebuilt entirely the toolchain from source but with the same results. I found a bug report in the launchpad(https://bugs.launchpad.net/igloocommunity/+bug/1000200) which pretty much describes exactly the same problem but unfortunately none of the observations made there helped(I do have -fPIC in the compilation flags, I do not have any assembly source and I rebuilt the toolchain from source). Does anyone have any hints on how to fix or overcome the problem? Thanks, Marius

14 years

2
2
0 0

[ACTIVITY] Jun 11 - Jun 14

by Ulrich Weigand

== GCC == * Fixed vectorizer bug causing unaligned memory accesses (LP 1010826 / GCC PR 53636); checked in to GCC mainline and Linaro GCC 4.7. Backports to FSF 4.7 and Linaro GCC 4.6 are under way. * Investigated vectorizer performance regression reported by Mans; main problem seems to be lack of use of the vectorizer cost model by default on ARM, but other aspects of the vectorized code could be improved as well. * Created blueprint to tune vectorizer cost mode on ARM and enable it by default. * Ongoing work on reassociation pass. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years

1
0
0 0

[ANNOUNCE] Linaro QEMU 2012-06 released

by Rusty Russell

The Linaro Toolchain Working Group is pleased to announce the release of Linaro QEMU 2012-06. Linaro QEMU 2012.06 is the latest release of qemu-linaro. Based off upstream qemu, it includes a number of ARM-focused bug fixes and enhancements. There are no major changes with this release, though it has been updated to the latest (1.1.0) qemu. The source tarball is available at: https://launchpad.net/qemu-linaro/+milestone/2012.06 More information on Linaro QEMU is available at: https://launchpad.net/qemu-linaro

14 years

1
0
0 0

String routines writeup with benchmarks

by Michael Hope

We talked at Connect about finishing up the cortex-strings work by upstreaming them into Bionic, Newlib, and GLIBC. I've written up one of our standard 'Output' pages: https://wiki.linaro.org/WorkingGroups/ToolChain/Outputs/CortexStrings with a summary of what we did, what else exists, benchmark results, and next steps. This can be used to justify the routines to the different upstreams. The Android guys are going to upstream these to Bionic. I need a volunteer to do Newlib and GLIBC. One surprise was that the Newlib plain C routines are very good on strings - probably due to a good end of string detector. -- Michael

14 years, 1 month

2
3
0 0

[ACTIVITY] weekly status

by Ken Werner

Hi, OpenEmbedded-Core/meta-linaro: * worked on building oe-core+meta-linaro using the 2012.05 release of the binary toolchain * minimal sysroot contains libraries that reference the old ld-linux.so.3 loader * created #1011671 * otherwise works fine for oe-core+meta-linaro * setup the build env on tcserver01 * verified the 2012.06 RC of linaro GCC 4.7 and 4.6 * 4.7 looks good * 4.6 has ICE when building Qt -mfpu=neon * reduced testcase available at bug #1013209 * updated meta-linaro (master) to pull in version 2012.06 of Linaro GCC 4.6/4.7 Regards, Ken

14 years, 1 month

1
0
0 0

gettext support

by Tom Deblauwe

Hello, I am wondering if there is support for gettext in the linaro toolchain? How can I check it if it should work or not? I can compile and link the "setlocale()" and "bindtextdomain()" and "textdomain()" functions, however, the translation doesn't work. Best regards Tom, -- *Tom Deblauwe* *R&D Engineer* Traficon International N.V. Vlamingstraat 19 B-8560 Wevelgem Belgium Tel.: +32 (0)56 37.22.00 Fax: +32 (0)56 37.21.96 URL: www.traficon.com <http://www.traficon.com>

14 years, 1 month

2
2
0 0

C++11 and C++98 incompatibility

by Ramana Radhakrishnan

I noticed this bug upstream about C++11 and C++98 ABI incompatibilities , in case someone is using the C++11 features, please be aware that there is an ABI bug lurking. http://gcc.gnu.org/bugzilla/show_bug.cgi?id=53646 Ramana

14 years, 1 month

2
1
0 0

Linaro GDB 7.4 2012.06 released

by Thiago Jung Bauermann

The Linaro Toolchain Working Group is pleased to announce the release of Linaro GDB 7.4 2012.06. Linaro GDB 7.4 2012.06 is the third release in the 7.4 series. Based off the latest GDB 7.4.1, it includes a number of bug fixes. Interesting changes include: * GDB now expands tildes in solib-search-path entries. * Updated to the GDB 7.4.1 code base. https://launchpad.net/gdb-linaro/+milestone/7.4-2012.06 More information on Linaro GDB is available at: https://launchpad.net/gdb-linaro -- []'s Thiago Jung Bauermann Linaro Toolchain Working Group

14 years, 1 month

1
0
0 0

[ANNOUNCE] Linaro GCC 4.7 and 4.6 2012.06 released

by Michael Hope

The Linaro Toolchain Working Group is pleased to announce the 2012.06 release of both Linaro GCC 4.7 and Linaro GCC 4.6. Linaro GCC 4.7 2012.06 is the third release in the 4.7 series. Based off the latest GCC 4.7.0+svn188038 release, it includes performance improvements especially around 64 bit operations. Interesting changes include: * Updates to GCC 4.7.0+svn188038 * Adds multilib support for use in the binary builds * Improves performance of 64 bit shifts in core registers Fixes: * LP: #949805 GCC doesn't by default use %gnu_unique_object * LP: #990530 internal compiler error: in convert, at lto/lto-lang.c:1292 * An off-by-one error in vrev Linaro GCC 4.6 2012.06 is the sixteenth release in the 4.6 series. Based off the latest GCC 4.6.3+svn188320 release, this is the third release after entering maintenance. Interesting changes include: * Updates to 4.6.3+svn188320 * Uses the new /lib/ld-linux-armhf.so.3 loader for hard float binaries Fixes: * LP: #949805 GCC doesn't by default use %gnu_unique_object * LP: #990530 internal compiler error: in convert, at lto/lto-lang.c:1292 The source tarballs are available from: https://launchpad.net/gcc-linaro/+milestone/4.7-2012.06 https://launchpad.net/gcc-linaro/+milestone/4.6-2012.06 Downloads are available from the Linaro GCC page on Launchpad: https://launchpad.net/gcc-linaro More information on the features and issues are available from the release page: https://launchpad.net/gcc-linaro/4.7/4.7-2012.06 Mailing list: http://lists.linaro.org/mailman/listinfo/linaro-toolchain Bugs: https://bugs.launchpad.net/gcc-linaro/ Questions? https://ask.linaro.org/ Interested in commercial support? Inquire at support(a)linaro.org -- Michael

14 years, 1 month

1
0
0 0

Re: Regarding Linking my code using Linaro's GNU-GCC Toolchain 4.6.2

by Michael Hope

On 12 June 2012 18:53, Akash D <akashd(a)renuelectronics.com> wrote: > Hello Michael, > > Thanks for reply. > > The required information is mentioned below. > > Compiler Used ---> > > http://launchpad.net/gcc-arm-embedded > > Version number ----> > > arm-none-eabi-gcc (GNU Tools for ARM Embedded Processors) 4.6.2 20110921 > (release) [ARM/embedded-4_6-branch revision 182083] Yip, this is ARM's Cortex-R & M bare metal toolchain. It doesn't come directly from Linaro but we've got a good relationship with them. I'll ping them and see the best place to ask this question. > The link file is attached with this mail. I only had a quick read, but you're missing a capture for the '.text.startup' section in the linker script. You might need something like: *(.text.startup) before the one.o(.text) line or to change the *(.text) capture to *(.text*). The startup section might need to be at a fixed address. Please check your chip and toolchain documentation to confirm. -- Michael

14 years, 1 month

1
0
0 0

Vectoriser performance regression in 4.7

by Mans Rullgard

While benchmarking the auto-vectoriser on Libav, I noticed a performance regression in gcc 4.7 (both FSF and Linaro) compared to gcc 4.6 in the AAC decoder. I narrowed it down to this function: static void ps_hybrid_analysis_ileave_c(float (*out)[32][2], float L[2][38][64], int i, int len) { int j; for (; i < 64; i++) { for (j = 0; j < len; j++) { out[i][j][0] = L[0][j][i]; out[i][j][1] = L[1][j][i]; } } } While gcc 4.6 does not attempt to vectorise this at all, 4.7 goes crazy with a massive slowdown, about 20x slower than non-vectorised with Linaro 4.7 and much worse with FSF 4.7. Let me know if you need more information. -- Mans Rullgard / mru

14 years, 1 month

2
3
0 0

Agenda for tomorrow's performance call.

by Ramana Radhakrishnan

https://wiki.linaro.org/WorkingGroups/ToolChain/Meetings/2012-06-12 Rather late but it's just been effectively a week since Connect. The only additional thing I've added is the vectorizer cost model and the libav regression that Mans discovered . regards, Ramana

14 years, 1 month

1
0
0 0

[Activity] Week 22 / 23

by Ramana Radhakrishnan

== Progress == * Connect last week. * Worked through the open issues and open work items related to performance and we've got a clear list of things that are currently in flight. Now to keep track of this better. https://wiki.linaro.org/RamanaRadhakrishnan/Sandbox//RRQ212ConnectNotes and move this away from the wiki page in a form that we can use to talk during our regular performance meetings. * Created blueprints, closed down old issues and reprioritized issues with Ulrich and others. * A number of interesting conversations during Connect for a number of compiler related issues. * Other sessions that I attended included the Android optimizations sessions - while there was quite a bit about toolchain performance it is important that we keep looking out for the performance profiles and find areas where the toolchain can be improved. However this can't be done without getting more testcases from other groups. There were a couple of interesting comments made that skia is CPU bound which would indicate that the paint function is CPU bound. But why and how ? Someone should look at reproducing these numbers and see where we get to in this area. Pointed out that cortex-strings might be good to make it into bionic ? * Fixed the vrev off by one error and committed to FSF trunk . However it couldn't make it in time for FSF 4.7.1 as the merge window had closed by then. * Set up my panda board to be identical to what runs on our validation labs etc. * This week * Worked through the merge requests and moved some patches upstream away from the "toreview" state. * Landed a few merge requests that were approved but hadn't been done so. Took care of merging the upstream 4.7 branch. * Given I only had a few hours back in the office this week I worked on regenerating arm_neon.h to use __builtin_shuffle with vrev64, vrev32, vtrn , vzip and vuzp. A follow up patch needs to do the same for vext but that needs generic support also in vec_perm_const_ok .Once that is done I think we can safely start rewriting . It still needs some more testing and polishing up but the initial results on the testcase from PR48941 is kind of neat. The result for some of the other testcases that I've looked at also looks much better than where we were a few weeks back. So all in all nice progress on that front. However we have to also find a way of getting these generated at O0 which they don't appear to do so cleanly enough with this approach. for one example it does look like this below: Notice those spills beginning to disappear .... :) New : sqrlen4D_16u8: @ args = 0, pretend = 0, frame = 0 @ frame_needed = 0, uses_anonymous_args = 0 @ link register save eliminated. vabd.u8 q1, q0, q1 vmull.u8 q0, d2, d2 vmull.u8 q8, d3, d3 vuzp.32 q0, q8 vpaddl.u16 q0, q0 vpadal.u16 q0, q8 bx lr Old : sqrlen4D_16u8: @ args = 0, pretend = 0, frame = 0 @ frame_needed = 1, uses_anonymous_args = 0 @ link register save eliminated. vabd.u8 q1, q0, q1 stmfd sp!, {r4, fp} add fp, sp, #4 sub sp, sp, #48 add r3, sp, #15 vmull.u8 q0, d2, d2 bic r3, r3, #15 vmull.u8 q8, d3, d3 vuzp.32 q0, q8 vstmia r3, {d0-d1} vstr d16, [r3, #16] vstr d17, [r3, #24] vpaddl.u16 q0, q0 vpadal.u16 q0, q8 sub sp, fp, #4 ldmfd sp!, {r4, fp} bx lr * Attended platform / WG sync-up. == Plans == * Cleanup the ml bits of rewiring the intrinsics and try some proper testcases. * Work on the auto-inc-dec scheduler patches. * Rework the sched-pressure patch upstream . * Review the Android benchmarking writeups.

14 years, 1 month

1
0
0 0

[Activity ] Week 23

by Zhenqiang Chen

Summary: * Bug fixes. * Tune ivopt for code size. Details: 1. Reproduce lp:1007353 "kernel build fails with 12.04 and 12.05 toolchain released" and workout a patch to fix it; reopen the related binutils/gas bug http://sourceware.org/bugzilla/show_bug.cgi?id=12698 and propose the patch to it; push the patch to linaro crosstool-ng to make sure lp:1007353 is fixed for next binary toolchain release. 2. Setup the SPEC build env and reproduce lp: 886124 "using LDR from literal pool rather than MOVW/MOVT". After cprop1 replaces lo_sum (high: symbol_ref bloc) (symbol_ref (block)) with a (symbol_ref (block)), no later optimization can split it. The solution in linaro 4.5 is to add a split (porting from codesourcery) in arm.md. Then split1 can split the (symbol_ref (block)). The split is: (define_split [(set (match_operand:SI 0 "arm_general_register_operand" "") (match_operand:SI 1 "general_operand" ""))] "TARGET_32BIT && TARGET_USE_MOVT && GET_CODE (operands[1]) == SYMBOL_REF && !flag_pic && !target_word_relocations && !arm_tls_referenced_p (operands[1])" [(clobber (const_int 0))] { arm_emit_movpair (operands[0], operands[1]); DONE; }) 3. Tune ivopt for code size. Try to set avg_loop_niter to 1 since loop iterator number does not impact code size. But test shows there is no improvement. Need more tuning. Plans: * Analyze the failed cases in arm-linux-gnueabihf regression test. * Tune code size for M0. Best regards! -Zhenqiang

14 years, 1 month

1
0
0 0

Regarding Linking my code using Linaro's GNU-GCC Toolchain 4.6.2

by Akash D

Hello Sir/Madam, I am using MK60FN1M0VLQ12 (COTREX-M4) processor for my development. I am using float and double data types in my code. When I perform any mathematical operation on these variables, the processor goes to Hard Fault Exception. Earlier I have used GCC 4.5.2 compiler for my compilation So now I am using Linaro's GNU-GCC Toolchain 4.6.2 for compiling my code with following command. arm-none-eabi-gcc -Wall -mfpu=fpv4-sp-d16 -mfloat-abi=softfp -mcpu=cortex-m4 -mthumb -Qn -Os -mlong-calls -c main.c -o main.o But I am getting following error while linking my code ld: section .text.startup loaded at [00032258,000331cb] overlaps section .InitializedVariables loaded at [00032258,00032787] The link file is attached with this mail. Can you please suggest me some solution for this problem. Can you also suggest some compiler commands to support float and double data type using software. Awaiting for your reply, Thanks & Regards, Akash

14 years, 1 month

2
1
0 0

[ACTIVITY] Jun 4 - Jun 8

by Ulrich Weigand

== GCC == * Worked on reimplementing reassociation pass based on review comments I had received. * Identified root cause and worked on fix for vectorizer bug causing unaligned memory accesses (reported by Mans). Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years, 1 month

1
0
0 0

[ACTIVITY] weekly status

by Ken Werner

Hi, OpenEmbedded-Core/meta-linaro: * fixed the binary toolchain support on master (still 2012.03) * fixed armhf support for Linaro GCC 4.6 on master * backport of Linaro GCC 4.7 r114985 * tested the images using QEMU - no failures * now the master branch supports building images for ARM, MIPS, PPC, X86 and X86_64 using the latest (2012.05) releases of Linaro GCC 4.6 or 4.7 * add tags on meta-linaro to easily find the revision for a particular Linaro GCC * changed cbuild to pull in the master branches of OE-Core and meta-linaro * merged the branch that allows to build OpenEmbedded-Core using cbuild http://bazaar.launchpad.net/~kwerner/cbuild/oecore/changes/ * updated docs on the wiki Misc: * public holiday on Thu, vacation on Fri * I'll be back on Monday : ) Regards, Ken

14 years, 1 month

1
0
0 0

[ACTIVITY] May 28 - June 1

by Thiago Jung Bauermann

Hi, GDB for Android: * Submitted and committed trivial patch to gdbserver which made it compile again on Android. A patch had been added which made gdbserver use a MIPS-related constant which Android doesn't provide. * Compared testsuite results of GDB on Android vs regular Linux. Unfortunately there's a lot of noise because the GCC 4.4 used by the Android SDK generates bad debuginfo which confuses GDB and breaks a lot of tests. Overall, it seems GDB on Android is in a generally good shape. Still need to run the testsuite again with an Android based on a newer compiler to have a better comparison. * Mozilla has a GDB patch to call gdbarch_addr_bits_remove before comparing PCs in breakpoint handling which seems like a sensible thing to do. Still, running the testsuite with and without this patch didn't make a difference on Android or regular Linux. * Remotely attended the GDB for Android session at Connect. Prepared the following page to go with it: https://wiki.linaro.org/ThiagoBauermann/Sandbox/AndroidGDBConnectSession -- []'s Thiago Jung Bauermann Linaro Toolchain Working Group

14 years, 1 month

1
0
0 0

[ACTIVITY] May 21 - May 25

by Thiago Jung Bauermann

Hi, GDB for Android: * Created patch to expand the ~ in "set solib-search-path". Despite doing the right thing in other commands, GDB doesn't understand ~ in solib-search-path, which made me lose some time in a debugging session trying to figure out what was going on. Committed upstream. * Looked into AOSP patch which hardcodes use of fork tracing instead of thread events. Found out that gdbserver actually already prefers fork tracing on both Linux and Android (tested on ICS and Linaro 12.04). This must have been a problem in some earlier version, and the patch is unnecessary now. * Set up a QEMU instance with Linaro Android 12.04. Got dropbear ssh on it and ran the GDB testsuite remotely on the VM. -- []'s Thiago Jung Bauermann Linaro Toolchain Working Group

14 years, 1 month

1
0
0 0

[ACTIVITY] weekly status

by Ken Werner

Hi, OpenEmbedded-Core/meta-linaro: * added a default xorg.conf for the qemuarmv7a MACHINE * necessary because OE-Core master switched from Xfbdev to Xorg * noticed that hard float with Linaro GCC 4.6 works on denzil but is broken on master due to differences on the requested/provided interpreter * it used to (accidentally?) work when /lib/ld-linux.so.3 was used even for armhf * need to check out what loader name OE-Core really wants to use * worked on getting OE-Core to build with Linaro GCC 4.7 * verified that the recipes for Linaro GCC 4.7 are working for ARM, MIPS, PPC, X86, X86_64 * all images are working! * updated the wiki pages Regards, Ken

14 years, 1 month

2
2
0 0

No meetings today

by Michael Hope

I've cancelled today's meeting due to the UK and NZ holidays. I'll see you all at the Thursday standup. -- Michael

14 years, 1 month

1
0
0 0

[ACTIVITY] report week 21

by Peter Maydell

Linaro Connect edition... RAG: GREEN: productive Connect, hammered out a KVM TODO list * As usual, most sessions don't really intersect with KVM/QEMU work, so the bulk of the benefit of the week was in informal discussions and hacking sessions. Useful outcomes there: * Dragged Rusty through some of the more obscure corners of the ARM architecture, in the course of doing a review of all the A15 cp15 registers and how KVM should handle them * Thrashed out a todo list for getting to "initial upstreamable patchset" for KVM: https://docs.google.com/document/d/1TSpDKQZ-6u-HH_2BNY_85jDStI2YDhENf5-z8Nb… * Nailed down a few decisions we'd left hanging for a bit * A few sessions that seem worth mentioning: * Enterprise bootloaders Jon M definitely pushing the idea that servers will want ACPI, UEFI, etc all to look as consistent and like x86 as possible. This includes a desire for UEFI in the virtual environment provided by QEMU/KVM. We've been aware we might want to do that, but there is definitely some work to do to get UEFI running (probably a combo of QEMU bugfixes/feature work and patching UEFI). Total work required hard to estimate because you just have to keep fixing bugs until it works... (The push for UEFI was repeated in a couple of other sessions too.) * v8 discussion The question of whether there will be a v8 QEMU was raised (again). There do seem to be enough people interested that we should be able to collaborate on a user-mode emulator, which I think is a good outcome. This will obviously depend on release of enough public info on the architecture. * KVM performance Bit of a null session, as it turns out that we aren't really ready to think about performance. We believe there aren't any obvious areas requiring optimisation in the current KVM patchset. Virtio is the only thing to be added later, and this is really just missing QEMU side rather than needing specific kernel support. We did take the opportunity to go through our TODO list for KVM functionality; nobody raised anything we'd missed, so that's good. -- PMM

14 years, 1 month

1
0
0 0

Fwd: linaro kernel fails to build with gcc4.7

by Fathi Boudra

Hi, It seems bug 947111 affects the binary toolchain. ---------- Forwarded message ---------- linaro-kernel seems to fail to build with the GCC4.7 [4.7.1 20120402 prerelease ] picked up from http://releases.linaro.org/12.04/components/toolchain/binaries/gcc-linaro-a…. Here is the link to the job which failed https://ci.linaro.org/jenkins/job/linux-linaro-tracking_panda-omap2plus_san… This issue had been recorded previously with bug https://bugs.launchpad.net/ubuntu/+source/armel-cross-toolchain-base/+bug/9…. This appeared to be fixed already according to the bug report, but seem to have regressed again.

14 years, 1 month

2
1
0 0

Support for building OpenEmbedded-Core using Linaro GCC 4.7

by Ken Werner

Hello, The OE-layer 'meta-linaro' now employs an updated recipe for building OpenEmbedded using the Linaro GCC 4.7 2012.05. The following configuration has been tested: OE-sources: * OpenEmbedded-Core: - git://git.openembedded.org/openembedded-core - rev 363424c * BitBake: - git://git.openembedded.org/bitbake - rev f8bf449 * meta-linaro: - git://git.linaro.org/people/kwerner/meta-linaro.git - rev 323a982 compiler: * Linaro GCC 4.7 2012.05 https://launchpad.net/gcc-linaro/4.7/4.7-2012.05/+download/gcc-linaro-4.7-2… images: * core-image-minimal (just enough to get a shell) * core-image-sato (Xorg, gtk+2) * qt4e-demo-image (Qt 4.8 embedded) targets: * ARM: - qemuarm (vesatilepb, ARMv5, arm926ej-s) - qemuarmv7a (vexpress, ARMv7, -march=armv7-a, -mthumb, -mfloat-abi=hard, -mfpu=neon) * MIPS: - qemumips (malta, -march=mips32) * PPC: - qemuppc (mac99, -mcpu=603e) * X86 - qemux86 * X86_64 - qemux86-64 build/host system: * x86_64 Ubuntu 11.10 (Oneiric) The easiest way to reproduce: wget http://people.linaro.org/~kwerner/oe-core/script/build-oe-core-linaro.sh bash ~/build-oe-core-linaro.sh --workdir workdir --dldir /home/ken/data/downloads --gcctype "linaro-4.7" --mlbranch 323a982 --oebranch 363424c --bbbranch f8bf449 --oepatches "http://people.linaro.org/~kwerner/oe-core/patches/armv7a-tree-vectorize.pat…" More information about the meta-linaro layer can be found at: https://wiki.linaro.org/KenWerner/Sandbox/OpenEmbedded-Core Regards Ken

14 years, 1 month

1
0
0 0

[ANNOUNCE] Linaro Toolchain Binaries 2012.05 released

by Zhenqiang Chen

The Linaro Toolchain Working Group is pleased to announce the 2012.05 release of the Linaro Toolchain Binaries, a pre-built version of Linaro GCC and Linaro GDB that runs on generic Linux or Windows and targets the glibc Linaro Evaluation Build. Uses include: * Cross compiling ARM applications from your laptop * Remote debugging * Build the Linux kernel for your board What's included: * Linaro GCC 2012.05 * Linaro GDB 2012.04 * A statically linked gdbserver * A system root * Manuals under share/doc/ The system root contains the basic header files and libraries to link your programs against. Interesting changes include: * Updates the system root to Ubuntu Precise * Switches to the arm-linux-gnueabihf triplet * Compiles programs for hard float by default * Includes soft float support for ARMv4T and later systems * Includes debug symbols for debugging and backtracing the C library The Linux version is supported on Ubuntu 10.04.3 and 12.04, Debian 6.0.2, Fedora 16, openSUSE 12.1, Red Hat Enterprise Linux Workstation 5.7 and later, and should run on any Linux Standard Base 3.0 compatible distribution. Please see the README about running on x86_64 hosts. The Windows version is supported on Windows XP Pro SP3, Windows Vista Business SP2, and Windows 7 Pro SP1. The binaries and build scripts are available from: https://launchpad.net/linaro-toolchain-binaries/trunk/2012.05 Need help? Ask a question on https://ask.linaro.org/ Already on Launchpad? Submit a bug at https://bugs.launchpad.net/linaro-toolchain-binaries On IRC? See us on #linaro on Freenode. Other ways that you can contact us or get involved are listed at https://wiki.linaro.org/GettingInvolved.

14 years, 1 month

1
0
0 0

GCC performance meeting.

by Ramana Radhakrishnan

Thanks to the change in the schedule the agenda is here. https://wiki.linaro.org/WorkingGroups/ToolChain/Meetings/2012-05-28 If there are any topics folks would like to add to this for today please feel free to do so now given we have a session in under 2 hours. regards, Ramana

14 years, 1 month

1
0
0 0

[Activity ] Week 21

by Ramana Radhakrishnan

Progress * Fixed PR53334 upstream - something that broke eembc builds. * Usual meetings. * Work through some of the speed tickets and upstream bugzilla perf tickets in preparation for connect. * Prepared for connect. Looked through some open issues and investigating PR48941 patch. Uli and I had some discussions around the patches for this and I had an idea later this evening to try out something with __builtin_shuffle which certainly looks interesting and is effectively what we came up with . It's probably better to use __builtin_shuffle rather than inventing something on our own. In the process found a bug with automatic rev generation from vec_perm expressions and that should now be fixed. * Worked through the auto-inc-dec stuff. Still needs some work and looks unlikely to complete before connect and that's something I need to keep working through. * Prepared for connect. Plans * Connect next week ! Absences: 28 May - 1 June : Linaro Connect

14 years, 1 month

1
0
0 0

[ACTIVITY] 21st - 25th May

by Andrew Stubbs

Committed my core-shifts patch into Linaro GCC. Checked and posted my (newly rebased) neon-shifts patch upstream for review. Continued work on my brain-dump of work in progress. Cleaned up, tested and posted example testcases and before/after compiler output for all my work-in-progress patches. Looked at LaunchPad bug #851258. It's a miss-optimization bug that would take some effort to fix. Discovered that my lower-subreg build had failed due to Werror. Fixed the warning, reuploaded the sources, and relaunched the build. Prepared for travel to Connect.

14 years, 1 month

1
0
0 0

[ACTIVITY] May 21 - May 25

by Ulrich Weigand

== GCC == * Followed up on review comments on reassociation pass. * Analyzed performance headroom of Linaro GCC 4.7 compared to various other compilers and identified several missing optimisations. == Misc == * Prepared for Linaro Connect Hong Kong. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years, 1 month

1
0
0 0

[ACTIVITY] report week 21

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || || == other == * preparation for Connect * wrote up and sent out proposal about handling TrustZone for KVM * investigated some issues Riku found when testing his packaged version of KVM (one model issue, one kernel-too-old issue) * usual upstream maintainer duties -- PMM

14 years, 1 month

1
0
0 0

[ACTIVITY] weekly status

by Ken Werner

Hi, OpenEmbedded-Core/meta-linaro: * cbuild enhancements: * debugged failures till I noticed cbuild was pulling in the wrong branch of meta-linaro (now fixed) * added support for checking the oe-core build prerequisites * the images are now automatically bootet using qemu * sizes of the images and package sizes are now recorded * update to Linaro GCC 4.6 2012.05 (denzil) and Linaro GCC 4.7 2012.05 (master) * debugged build failure when using Linaro GCC 4.6 in a hard float configuration * turns out that OE expects the GCC to respect the ARCH_FLAGS_FOR_TARGET env variable to build libgcc and friends properly for the given target (another missing patch to build the GCC the OE-Core way) * fix tested and checked in (denzil) * created/updated wiki pages: https://wiki.linaro.org/WorkingGroups/ToolChain/Outputs/OpenEmbedded-Core https://wiki.linaro.org/KenWerner/Sandbox/OpenEmbedded-Core Regards, Ken

14 years, 1 month

1
0
0 0

KVM integration output page

by Michael Hope

Hi Peter, Riku. I've written up a page covering the KVM integration work done this quarter at: https://wiki.linaro.org/WorkingGroups/ToolChain/Outputs/KVMIntegration Could you review it please, including the instructions at: https://wiki.linaro.org/WorkingGroups/ToolChain/Outputs/KVMIntegration/Quic… It overlaps with the howtos that you both have but is supposed to be both short and a snapshot in time. If it looks good then I'll use this to closeout this quarter's KVM card. -- Michael

14 years, 1 month

4
8
0 0

My topics for Connect

by Michael Hope

Here's my list of things I'd like to knock off during Connect: https://wiki.linaro.org/MichaelHope/Sandbox/Q2.12Plans Have a think about specific things you'd like to achieve as I'll be asking on Monday. -- Michael

14 years, 1 month

1
0
0 0

[ACTIVITY] May 14 - May 18

by Thiago Jung Bauermann

Hi, GDB for Android: * Fixed the PC offset in jmp_buf but the patch still wasn't working. It turns out that GDB wasn't loading the libc6.so symbols even though I set both sysroot *and* solib-search-path. Copied libc6.so to GDB's cwd and the patch worked (will investigate this next week). Submitted upstream, currently under review. -- []'s Thiago Jung Bauermann Linaro Toolchain Working Group

14 years, 1 month

1
0
0 0

[ACTIVITY] May 7 - May 11

by Thiago Jung Bauermann

Hi, GDB for Android: * Worked on patch which uses the correct offset for finding the PC value inside the jmp_buf on Android binaries. Things weren't working though, and in the end it turns out that the value used in AOSP's patch is wrong. -- []'s Thiago Jung Bauermann Linaro Toolchain Working Group

14 years, 1 month

1
0
0 0

Testsuite differences with a hard float shift

by Michael Hope

Hi Zhenqiang. I've had a look at the difference between testsuite results on our current softfp Natty builders and the new hard float Precise builders. The diff and notes is at: http://people.linaro.org/~michaelh/incoming/hard-float-builder-diff.txt There's a lot of commonality: /usr/bin/ld: cannot find {S,g}crt1.o: builder fault. I've fixed this. sorry, unimplemented: Thumb-1 hard-float VFP ABI errors: tests where they set the architecture to ARMv5T and use our default Thumb mode. This causes the compiler to fail as it doesn't support Thumb-1 with hard float. arm_iwmmxt_ok5222.c:1:0: sorry, unimplemented: iWMMXt and hardware floating point Some are real: +FAIL: gcc.c-torture/compile/sync-3.c -O0 (test for excess errors) /tmp/cc3ufndj.s:436: Error: co-processor offset out of range +FAIL: gcc.dg/pr48335-2.c (test for excess errors) pr48335-2.c:19:30: internal compiler error: in expand_expr_addr_expr_1, at expr.c:7527 +FAIL: gcc.dg/pr48335-5.c (test for excess errors) pr48335-5.c:17:1: error: unrecognizable insn: (insn 11 10 12 3 (set (reg:DI 141) (unspec:DI [ (mem/c:DI (plus:SI (reg/f:SI 129 virtual-stack-vars) (const_int -8 [0xfffffffffffffff8])) [2 S8 A32]) ] UNSPEC_MISALIGNED_ACCESS)) /cbuild/slaves/ursa2/gcc-linaro-4.7+bzr114988~zhenqiang-chen~gnueabihf/gcc/gcc-linaro-4.7/gcc/testsuite/gcc.dg/pr48335-5.c:16 -1 (nil)) +FAIL: gcc.dg/torture/stackalign/builtin-apply-2.c -O0 execution test Some are marked as unsupported but shouldn't be: +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-11a.c +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-11b.c +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-11.c +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-11c.c +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-25.c +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-26.c +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-28.c +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-2.c +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-32.c Could you look into the unsupported ones please? I'll fix the crt1 problems and respin the build. -- Michael

14 years, 1 month

2
2
0 0

Changes to the auto builders

by Michael Hope

The Precise based hard float auto builders are now online. Every merge request and commit to gcc-linaro will now be built build both on a Natty softfp system and a Precise hard float. Let's run this in parallel for a while before updating the validation lab. I've also updated the x86 cloud builders from Natty to Precise. A quick test showed no regressions but I want to run them in parallel for a bit to be sure. -- Michael

14 years, 1 month

1
0
0 0

[Activity] Week 20

by Ramana Radhakrishnan

Progress * Proposed backport for vfp addressing modes patch. * Investigated the build issue with EEMBC and have a candidate patch for upstream trunk. (PR53334) * Investigated auto-inc-dec sched changes. * Some upstream patch review. Plans * Work on auto-inc-dec sched changes. * Finish PR53334 patch upstream. * Work through some of the speed tickets and upstream bugzilla perf tickets in preparation for connect.

14 years, 1 month

1
0
0 0

[ACTIVITY] 14th -18th May

by Andrew Stubbs

Remerged the GCC 4.7 branch from upstream. I had previously misunderstood how to resolve a conflict where Uli had committed a different version of the same patch upstream. Spun the GCC 4.6 and 4.7 release tarballs and passed them to Michael for testing. Continued work on improving code generation for 64-bit and/or/not/xor. I now have this working to the point where it would be ready to post upstream .... except that it depends on my other patches that are not yet committed (or even reviewed) upstream. Rebased and modified my core-shifts patch following Ramana's code review. Then regression tested it - no regressions - and committed the patch upstream. I've also updated the launchpad branch and resubmitted the merge request with the finalized upstream patch. Rebased the neon-shifts patch. I'll repost this upstream as soon as I'm happy it still works correctly. Worked on a brain-dump of all I have been working on recently. This will hopefully help others take over my tasks after the contract expires. I still need to put together all the test-cases and examples that Ramana requested.

14 years, 1 month

1
0
0 0

[Activity] Week 20

by Zhenqiang Chen

Summary: * Linaro binary toolchain 2012.05 release. * Code size benchmark analysis. Details: 1. Linaro binary toolchain 2012.05 release * Check-in the patches to support multilib and arm-linux-gnueabihf in linaro crosstool. * Update config to 2012.05 release, which will build multilib toolchain: default option: -mthumb -march=armv7-a -mfloat-api=hard -mtune=cortex-a9 -mfpu=vfpv3-d16 armv4t option: -marm -march=armv4t -mfloat-api=soft * Try u-boot build with the armv4t option. * Add arm-linux-gnueabihf.mpi for windows installer. * Tests and regression analysis. 2. During code size regression analysis, we find postreload can not optimize some cases when spilling happens, reassociation for PHI note might lead to spilling, expand generates inefficient codes which can not be optimized by later passes and poor code layout introduces more branch instructions. Plans: * Linaro binary toolchain 2012.05 release. * Investigate other code size regressions in 4.7. Best regards! -Zhenqiang

14 years, 1 month

1
0
0 0

[ACTIVITY] May 14 - May 18

by Ulrich Weigand

== GCC == * Completed implementation of new optimization sub-pass to improve re-association of plus/minus chains for types with undefined overflow (to improve end-of-loop value computation); posted to gcc-patches for review. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years, 1 month

1
0
0 0

[ACTIVITY] report week 20

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || ||cp15-rework || 2012-01-06 || 2012-06-23 || || Historical Milestones: ||initial-a15-system-model || 2012-01-27 || 2012-01-27 || 2012-01-17 || ||qemu-kvm-getting-started || 2012-03-04?|| 2012-03-04 || 2012-02-01 || == cp15-rework == * fixed various issues, sent out v2 series, looks good to me == other == * qemu-linaro 2012.05 released * thinking about how to handle TrustZone in the context of QEMU/KVM (we're not going to try to do a full emulation, but we need to define a coherent line for how we support running guests that are expecting to run as either S or NS PL1/0 kernels) * had a play with booting UEFI on QEMU -- fails early on trying to use the TrustZone-only VBAR register * usual upstream maintainer duties -- PMM

14 years, 1 month

1
0
0 0

Re: Testsuite differences with a hard float shift

by Michael Hope

On 17 May 2012 18:23, Zhenqiang Chen <zhenqiang.chen(a)linaro.org> wrote: >> Some are marked as unsupported but shouldn't be: >> >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-11a.c >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-11b.c >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-11.c >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-11c.c >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-25.c >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-26.c >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-28.c >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-2.c >> +UNSUPPORTED: gcc.dg/tree-ssa/gen-vect-32.c > > The root cause is "target vect_cmdline_needed". For those cases, they > have notes as: > > /* { dg-do run { target vect_cmdline_needed } } */ > > In function "check_effective_target_vect_cmdline_needed" of > lib/target-supports.exp, it check_effective_target_arm_neon. > > For our build, it is arm neon, > check_effective_target_vect_cmdline_needed return 0. > > A quick fix is to add another dg-do run like: > /* { dg-do run { target arm*-*-*eabihf } } */ I've looked into this further and the tests make no sense. The test themselves are turned off unless the compiler needs extra command line arguments to enable some type of SIMD. See PR21292. Let's discuss this on Monday. I've put an updated list at: http://people.linaro.org/~michaelh/incoming/hard-float-builder-diff-2.txt The interesting ones below. They're a mix of assembler faults, ICEs, and testisims. None are due to the change in triplet so please propose your patch upstream. -- Michael +FAIL: gcc.c-torture/compile/sync-1.c -O0 (test for excess errors) +FAIL: gcc.c-torture/compile/sync-3.c -O0 (test for excess errors) /tmp/ccGuCO1R.s:463: Error: co-processor offset out of range ** Doesn't happen with a natty sysroot. Assembler fault? +FAIL: gcc.dg/builtin-apply2.c execution test ** Testism. Skips if an explicit float-abi=hard is passed. +FAIL: gcc.dg/pr48335-5.c (test for excess errors) (insn 11 10 12 3 (set (reg:DI 141) (unspec:DI [ (mem/c:DI (plus:SI (reg/f:SI 129 virtual-stack-vars) (const_int -8 [0xfffffffffffffff8])) [2 S8 A32]) ] UNSPEC_MISALIGNED_ACCESS)) /cbuild/slaves/ursa2/gcc-linaro-4.7+bzr114985~michaelh1~hard-builder-test/gcc/gcc-linaro-4.7/gcc/testsuite/gcc.dg/pr48335-5.c:16 -1 (nil)) ** The unaligned access support doesn't include an unaligned DI pattern? +FAIL: gcc.dg/torture/stackalign/builtin-apply-2.c -Os execution test ** Testism. Assumes doubles are passed in core registers. +UNSUPPORTED: gcc.target/arm/mmx-1.c /cbuild/slaves/ursa2/gcc-linaro-4.7+bzr114985~michaelh1~hard-builder-test/gcc/gcc-linaro-4.7/gcc/testsuite/gcc.target/arm/g2.c:12:1: sorry, unimplemented: Thumb-1 hard-float VFP ABI ** Various forms. Needs thought.

14 years, 2 months

1
0
0 0

Branches unfrozen

by Andrew Stubbs

The releases have been made, so the branches have been updated and returned to their normal state. Andrew

14 years, 2 months

1
0
0 0

[ANNOUNCE] Linaro QEMU 2012.05 released

by Peter Maydell

The Linaro Toolchain Working Group is pleased to announce the release of Linaro QEMU 2012.05. Linaro QEMU 2012.05 is the latest monthly release of qemu-linaro. Based off upstream (trunk) QEMU, it includes a number of ARM-focused bug fixes and enhancements. New in this month's release: - Beagle bootrom emulation now correctly handles FAT12/FAT16 images (thanks to Peter Chubb for the bug report and patch). - We now support running ARM BE8 userspace binaries (ie byte-invariant big-endian data and little-endian code). Known issues: - Graphics do not work for OMAP3 based models (beagle, overo) with 11.10 Linaro images. - Audio may not work on Versatile Express models with the latest Linaro kernel/hardware packs (LP:977610). The source tarball is available at: https://launchpad.net/qemu-linaro/+milestone/2012.05 More information on Linaro QEMU is available at: https://launchpad.net/qemu-linaro

14 years, 2 months

1
0
0 0

[ANNOUNCE] No release of Linaro GDB this month

by Michael Hope

There will be no release of Linaro GDB this month. We're busy working on upstreaming Android support and will backport them as they come ready. -- Michael

14 years, 2 months

1
0
0 0

[ANNOUNCE] Linaro GCC 4.7 and 4.6 2012.05 released

by Michael Hope

The Linaro Toolchain Working Group is pleased to announce the 2012.05 release of both Linaro GCC 4.7 and Linaro GCC 4.6. Linaro GCC 4.7 2012.05 is the second release in the 4.7 series. Based off the latest GCC 4.7.0+svn187448 release, it includes performance improvements especially around 64 bit operations. Interesting changes include: * Updates to GCC 4.7.0+svn187448 * Uses the new /lib/ld-linux-armhf.so.3 loader for hard float binaries * Adds support for negating 64 bit values in NEON * Improves loading of 64 bit immediate values in NEON Fixes: * LP: #959242 ICE: in vect_is_simple_use_1, at tree-vect-stmts.c * LP: #968766 GCC 4.6.3 (cc1) crashes when compiling MPFR 3.1.0 Linaro GCC 4.6 2012.05 is the fifteenth release in the 4.6 series. Based off the latest GCC 4.6.3+svn187273 release, this is the second release after entering maintenance. Interesting changes include: * Updates to 4.6.3+svn187273 Fixes: * LP: #959242 ICE: in vect_is_simple_use_1, at tree-vect-stmts.c * LP: #968766 GCC 4.6.3 (cc1) crashes when compiling MPFR 3.1.0 * LP: #972648 ICE (segfault) in gsi_for_stmt The source tarballs are available from: https://launchpad.net/gcc-linaro/+milestone/4.7-2012.05 https://launchpad.net/gcc-linaro/+milestone/4.6-2012.05 Downloads are available from the Linaro GCC page on Launchpad: https://launchpad.net/gcc-linaro More information on the features and issues are available from the release page: https://launchpad.net/gcc-linaro/4.7/4.7-2012.05 Mailing list: http://lists.linaro.org/mailman/listinfo/linaro-toolchain Bugs: https://bugs.launchpad.net/gcc-linaro/ Questions? https://ask.linaro.org/ Interested in commercial support? Inquire at support(a)linaro.org -- Michael

14 years, 2 months

1
0
0 0

[ACTIVITY] weekly status

by Ken Werner

Hi, OpenEmbedded-Core/meta-linaro: * reverted the gcc 4.7 support from the denzil branch as it's causing too much trouble * instead we'll use a oe-core master snaphsot for 4.7 * committed a fix to our kernel bbappend * started to look into cbuild * added configurations to support building the images for all oe-core targets * created lp:~kwerner/cbuild/oecore * kicked off a build for ARM, MIPS, PPC, X86, X86_64 using Linaro GCC 4.6 2012.04 Misc: * IBM internal meetings * public holiday on Thu, vacation on Fri I'll be back on monday Regards, Ken

14 years, 2 months

1
0
0 0

GCC trunk fails to build

by Michael Hope

Hi Ramana. FYI, gcc trunk fails to bootstrap with: ../../../../gcc-4.8~/libgcc/libgcc2.c: In function '__mulvdi3': ../../../../gcc-4.8~/libgcc/libgcc2.c:397:1: internal compiler error: in df_uses_record, at df-scan.c:3179 A cross compiler fails when building EEMBC with: (insn 1166 1165 1167 155 (set (reg:CC 24 cc) (compare:CC (reg:SI 2148 [ D.6766 ]) (const_int 5000 [0x1388]))) iirflt01/bmark.c:501 -1 (nil)) iirflt01/bmark.c:1138:1: internal compiler error: in extract_insn, at recog.c:2131 The last revision that bootstrapped was 187203. 187223 and 187275 failed. -- Michael

14 years, 2 months

3
4
0 0

Branches Frozen

by Andrew Stubbs

The GCC 4.7 merge testing is currently in progress. We're a little late with it, so I'm spinning the release speculatively. This being the case I've made the lp:gcc-linaro branch read-only, just in case. This shouldn't prevent anybody from reading the branch with "lp:gcc-linaro", but the "lp:~linaro-toolchain-dev/gcc-linaro/4.7" name will be broken for a while, so you may find "bzr pull" broken. (The reason being that the only way to make a bzr branch read-only is to change its owner.) I will put the branch back to its normal state as soon as the release is done. Andrew

14 years, 2 months

1
0
0 0

State of Fast Model in the lab

by Michael Hope

Hi there. We'd like to run a Fast Model in the validation lab for KVM testing. Is there a blueprint for this? What's the status? Paul and I discussed a rough plan a few months ago. It was along the lines of: * A x86 machine as the Fast Model host * An emulated vexpress-a15 as the KVM host * A vexpress-a15 as the KVM guest * LAVA treats the Fast Model as a board * Jobs are spawned into the LAVA scheduler * Once the KVM host is running, everything else is toolchain specific and done via shell scripts The dispatcher would: * Grab the hwpack * Grab the nano rootfs * Build the rootfs with separate kernel, initrd, and dtb using linaro-media-create * Start the Fast Model with the boot wrapper, kernel, and rootfs * Use the console to run the test script There's more information on the steps required at: https://wiki.linaro.org/MichaelHope/Sandbox/KVMUseCase -- Michael

14 years, 2 months

3
5
0 0

[ACTIVITY] May 07 - May 11

by Ulrich Weigand

== GCC == * Checked in patch to fix LP #959242 (GCC PR tree-optimization/52633) to Linaro GCC 4.7 and 4.6. * Completed design of new optimization sub-pass to improve re-association of plus/minus chains for types with undefined overflow (to improve end-of-loop value computation); started implementation. * Investigated GCC PR target/44141. * Started investigation of TSVC vectorizer test kernels. Mit freundlichen Gruessen / Best Regards Ulrich Weigand -- Dr. Ulrich Weigand | Phone: +49-7031/16-3727 STSM, GNU compiler and toolchain for Linux on System z and Cell/B.E. IBM Deutschland Research & Development GmbH Vorsitzender des Aufsichtsrats: Martin Jetter | Geschäftsführung: Dirk Wittkopp Sitz der Gesellschaft: Böblingen | Registergericht: Amtsgericht Stuttgart, HRB 243294

14 years, 2 months

1
0
0 0

Agenda for tomorrow's performance call.

by Ramana Radhakrishnan

https://wiki.linaro.org/WorkingGroups/ToolChain/Meetings/2012-05-15 I've put together an initial version of the blueprints we could consider . Are there any other topics that folks are interested in adding ? If so, could you add it to the wiki page. Thanks, Ramana

14 years, 2 months

1
0
0 0

[ACTIVITY] 7th - 11th May

by Andrew Stubbs

* Linaro GCC Did the merges from upstream ahead of the Linaro releases next week. Unfortunately, with the Linaro office move the test system is running slowly, and it took a long while for Uli's concerns about the 4.7 merge to be confirmed, so this might cause a bit of delay while I remerge, and retest. Begun looking at a solution for GCC Bugzilla pr53189. I've rewritten the anddi3, iordi3 and xordi3 patterns to avoid the problems when NEON is not available, and also improved the situation when NEON is enabled. There are still a few kinks that need to be ironed out with poorly optimized extend-and-operate sequences, and then I'm done, I hope. * Other Public holiday on Monday.

14 years, 2 months

1
0
0 0

[Activity] Week 19

by Zhenqiang Chen

Summary: * arm-linux-gnueabihf and multilib support for linaro toolchain. Details: 1. Make arm-linux-gnueabihf and multilib work together for linaro toolchain * Tuning the include and link path and order. * The build requires a sysroot with both soft and hard float support (Refer precise-sysroot-armhf-r0c.tar.bz2 at http://people.linaro.org/~michaelh/incoming/). With the sysroot, a reference multilib toolchain build is at http://people.linaro.org/~zhenqiangchen/ * Update the Makefiles in tests to support armv4t build. * Setup a pandaboard and run some tests. Plans: * Investigate other code size regressions in 4.7. * Prepare for linaro binary toolchain 2012.05 release. Best regards! -Zhenqiang

14 years, 2 months

1
0
0 0

[Activity] Week 19

by Ramana Radhakrishnan

<Short week given bank holiday> Progress * Committed the VFP addressing modes patch. * Investigated PR48941 patch a bit more - looks like an issue with the register allocator around vzip and vuzp patterns and not sure what the easiest way of sorting this really is. I wonder if we should be looking at some of the issues around secondary reloads or friends for this particular patch - we generate too many vmov's for my liking and with more complex code this ends up as spills ! * Backported gnu_unique_objects patch. Need approval to commit in Linaro tree. Plans * Backport VFP addressing patch to Linaro tree. * Finish smin-umin idiom patch in the backend. * smin - umin idiom patch in middle-end - investigate further. Absences: * May 28- June 3 : Away to Linaro Connect.

14 years, 2 months

1
0
0 0

2026

2025

2024

2023

2022

2021

2020

2019

2018

2017

2016

2015

2014

2013

2012

2011

2010

linaro-toolchain