- linaro-toolchain - lists.linaro.org

by Christophe Lyon

== Progress == * PGO/hot-cold partitioning/Spec2k: * Debugging why 254.gap is causing an ICE. * Connect preparation: Configuring a temporary laptop == Next == * Continue with PGO/hot-cold partitioning

12 years, 10 months

1
0
0 0

[ACTIVITY] 15 - 19 October

by Matthew Gretton-Dann

== Progress == * HOT/COLD partitioning for PGO * Submitted merge request for current changes so that we can benchmark and see how much benefit we can actually expect * Patch Tracking & Backporting * Backported Uli's fix for insn splitting at -O0 to 4.7 * Started backporting Doko's configury changes for arm-none-linux-gnueabihf support * Connect Prep * Started investigating LRA * Admin * Interviewing == Next Week == * Prepare for Connect * Investigate zero/sign extension * Investigate LRA * Investigate Conditional Comparison benefits * AArch64 * Document processes == Future == * Attend Connect * HOT/COLD partitioning for PGO: * Get two current patches accepted upstream * Post question upstream about register allocation 'mistakes' I am seeing -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

12 years, 11 months

1
0
0 0

Add dwarf/unwind info in epilogue

by Zhenqiang Chen

Hi Ramana, The attached file is a reference patch to add more dwarf/unwind info in epilogue. Please help to review. Without the patch, dwarf check fail for the following cases when enabling shrink-wrap: tst ... L1 //simple_return push ... ... pop ... //.cfa_offset is not 0 L1: bx lr //common simple_return Thanks! -Zhenqiang

12 years, 11 months

3
6
0 0

[ACTIVITY] report weeks 40,41

by Peter Maydell

== other == * upstream patch review * target-arm pull request * reviewed/committed some boot wrapper patches from Tixy to init the CCI * rebased various qemu kvm-related patches on current upstream master, sent out RFC v2 for review (matching kernel -v12 patches); this is getting some useful review feedback * added check for 'does KVM support vfp-d32' rather than just assuming it on the QEMU side * discussed API for userspace to tell KVM the base address of the VGIC with Avi, Christoffer [todo: write QEMU patches to go with C's proposed kernel patches] KVM blueprint progress tracker: http://ex.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&pr… -- PMM

12 years, 11 months

1
0
0 0

[Activity] Week 41

by Zhenqiang Chen

Summary: * Test shrink-wrap. * Identify the root cause of dwarf check fail when enabling shrink-wrap. Details: 1. Test shrink-wrap on PandaBoard with Precise * Bootstrap is OK * No make check regression * No performance change for SPEC2000 INT. 2. Identify the root case for dwarf check fail on ARM, while they are OK on X86 and MIPS when enabling shrink-wrap. * "push" related INSNs are set as RTX_FRAME_RELATED_P in prologue; but not all "pop" related INSNs are set as RTX_FRAME_RELATED_P. * Prologue uses REG_FRAME_RELATED_EXPR notes to tell the dwarf backend SP is adjusted; but no such kind of notes in epilogue. * In addition, dwarf info for INSNs to adjust SP are not handled correctly in epilogue. Plans: * Verify shrink-wrap related bugs * Prepare Linaro binary toolchain 2012.10 release Best regards! -Zhenqiang

12 years, 11 months

1
0
0 0

[ANNOUNCE] Linaro GCC 4.7 and Linaro GCC 4.6 2012.10 released

by Matthew Gretton-Dann

The Linaro Toolchain Working Group is pleased to announce the 2012.10 release of both Linaro GCC 4.7 and Linaro GCC 4.6. Linaro GCC 4.7 2012.10 is the seventh release in the 4.7 series. Based off the latest GCC 4.7.2+svn191881 release, it includes ARM-focused performance improvements and bug fixes. Interesting changes include: * Updates to GCC 4.7.2+svn191881 * Backport changes to use VLD1 for Neon quad loads. Fixes: * LP 1053348: Missing binary files Linaro GCC 4.6 2012.10 is the twentieth release in the 4.6 series. Based off the latest GCC 4.6.3+svn191880 release, this is the seventh release after entering maintenance. Interesting changes include: * Updates to 4.6.3+svn191880 * A fix to LP #1029454 The source tarballs are available from: https://launchpad.net/gcc-linaro/+milestone/4.7-2012.10 https://launchpad.net/gcc-linaro/+milestone/4.6-2012.10 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 pages: https://launchpad.net/gcc-linaro/4.7/4.7-2012.10 https://launchpad.net/gcc-linaro/4.6/4.6-2012.10 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 -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

12 years, 11 months

2
1
0 0

[ACTIVITY] 8 - 12 October 2012

by Yvan Roux

== Progress == * Completed Linaro ramp up process. * Obtained my SSH security exception * Crosstool-ng : - Repoduced the aarch64 builds (bare and linux) - Updated gcc to Linaro 2012.10 and submitted the merge request. * Cbuild autobuilder : - Not able to spawn a job on seabright (lack of permission) == Misc == * One day off.

12 years, 11 months

2
1
0 0

[ACTIVITY] 8 - 12 October 2012

by Christophe Lyon

== Progress == * builtin_bswap16: * Backported missing patch from thunk to Linaro/4.7. One test still failing in the hard-float + thumb configuration because it forces armv6 and results in a unsupported configuration: vfp-1 + hard-float. Resumed discussion about a fix I proposed 3 weeks ago. * PGO/hot-cold partitioning/Spec2k: * read doc about spec2k * started looking at 254.gap causing an ICE. * started studying qemu traces about 175.vpr crashing when compiled using profiling info. Cold code returns from a function using a clobbered lr value. == Next == * builtin_bswap16: * complete backport to linaro-gcc 4.7. * PGO/hot-cold partitioning/Spec2k: * investigate compiler crash and runtime failures.

12 years, 11 months

1
1
0 0

[ACTIVITY] 8 - 12 October 2012

by Matthew Gretton-Dann

== Progress == * Deputising for Michael * 4.6 and 4.7 2012.10 releases * Included extra AArch64 merge into gcc-lianro/4.7 * AArch64 support * Did another merge * Starting another one. * HOT/COLD partitioning for PGO * PINGed If/Then/Else block conversion patch * Started reworking postreload-gcse.c patch * Ran into issues with vanilla gcc-linaro/4.7 not being able to build for 'arm-none-linux-gnueabihf' without some configury magic * Admin * Interviewing == Next Week == * Do another AArch64 merge. * HOT/COLD partitioning for PGO: * Get two current patches accepted upstream * Post question upstream about register allocation 'mistakes' I am seeing * symbol_ref splitting * Test code alignment hypothesis * Test v2 patch. == Future == * Look at Cards for Vectorization, PGO and LTO with Michael. -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

12 years, 11 months

1
0
0 0

Query: What happens in case of char array overflow?

by Viresh Kumar

Hi Guys, I just found an issue in kernel code and thought we must have a compilation warning for such cases. Submitted a bug here: https://bugs.launchpad.net/gcc-linaro/+bug/1064218 Problem description: ------------------------- When we have following declaration: struct foo { char array[5]; .... }; And have a definition like: struct foo foo_abc = { .array = "12345", }; Problem here is: size of array is 5 bytes and so we can actually add a string with four characters only to it, as '\0' will take an additional space. But with my definition of foo_abc.. i had 5 characters + '\0'... that will make it 6 and that will overflow the array.. What will actually happen here? - compiler will not add '\0' at all? -or it will go outside of boundaries of array? -- viresh

12 years, 11 months

4
7
0 0

Re: alignment faults in 3.6

by Michael Hope

On 5 October 2012 12:10, Rob Herring <robherring2(a)gmail.com> wrote: > I've been scratching my head with a "scheduling while atomic" bug I > started seeing on 3.6. I can easily reproduce this problem when doing a > wget on my system. It ultimately seems to be a combination of factors. > The "scheduling while atomic" bug is triggered in do_alignment which > gets triggered by this code in net/ipv4/af_inet.c, line 1356: > > id = ntohl(*(__be32 *)&iph->id); > flush = (u16)((ntohl(*(__be32 *)iph) ^ skb_gro_len(skb)) | (id ^ IP_DF)); > id >>= 16; > > This code compiles into this using "gcc version 4.6.3 (Ubuntu/Linaro > 4.6.3-1ubuntu5)": > > c02ac020: e8920840 ldm r2, {r6, fp} > c02ac024: e6bfbf3b rev fp, fp > c02ac028: e6bf6f36 rev r6, r6 > c02ac02c: e22bc901 eor ip, fp, #16384 ; 0x4000 > c02ac030: e0266008 eor r6, r6, r8 > c02ac034: e18c6006 orr r6, ip, r6 > > which generates alignment faults on the ldm. These are silent until this > commit is applied: Hi Rob. I assume that iph is something like: struct foo { u32 x; char id[8]; }; struct foo *iph; GCC merged the two adjacent loads of x and id into one ldm. This is an ARM specific optimisation done in load_multiple_sequence() and enabled with -fpeephole2. I think the assembly is correct - GCC knows that iph is aligned and knows the offsets of both x and id. Happy to be corrected if I'm wrong, but I think the assembly is valid given the C code. -- Michael

12 years, 11 months

8
28
0 0

[ACTIVITY] Oct-1-Oct-5

by Christophe Lyon

== Progress == * builtin_bswap16: * backporting of builtin_bswap16 for ARM to Linaro/4.7: one of the tests fails. Waiting for Ramana's return to see if he can help me identify the patch needed from trunk. * Useless zero extensions: despite Ulrich support I didn't succeed to rewrite the bswap16 pattern in a way that would avoid generating useless zero extension. Asking for help on gcc list shows that it would actually need a complete new optimization pass, which has already been discussed several times. * PGO/hot-cold partitioning/Spec2k: * looking at spec2k build & run system * Branch reviews: approved Matt's october merges for Linaro-gcc 4.6 and 4.7. Briefly looked at aarch64-4.7 merge request. == Next == * builtin_bswap16: * try to complete backport to linaro-gcc 4.7. * PGO/hot-cold partitioning/Spec2k: * investigate compiler crash and runtime failures. * setup Snowball

12 years, 11 months

1
0
0 0

[ACTIVITY] 1 - 5 October 2012

by Yvan Roux

== Progress == * Started Linaro ramp up process. * Started to look at Crosstool-ng and CBuild * Fighting against proxy and bazaar configuration == Next Week == * Continue the started tasks.

12 years, 11 months

1
0
0 0

[ACTIVITY] 1 - 5 October 2012

by Matthew Gretton-Dann

== Progress == * 4.6 and 4.7 start of month merges * Fixed missing binary files issues whilst doing this. * 4.7 AArch64 merge into gcc-linaro/4.7 * Completed initial merge * Admin * Interviewing == Next Week == * Deputise for Michael * Do GCC-Linaro releases * Fix up any issues with aarch64 merge. * HOT/COLD partitioning for PGO: * Get two current patches accepted upstream * Post question upstream about register allocation 'mistakes' I am seeing * symbol_ref splitting * Test code alignment hypothesis * Test v2 patch. == Future == * Look at Cards for Vectorization, PGO and LTO with Michael. -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

12 years, 11 months

1
0
0 0

Re: Kernel 3.6 build bug with Linaro 4.7 toolchains

by Loïc Minier

Adding linaro-toolchain On Tue, Oct 02, 2012, Khem Raj wrote: > On Tue, Oct 2, 2012 at 4:59 PM, Tim Bird <tim.bird(a)am.sony.com> wrote: > > When I try to build the Linux kernel version 3.6 with the gcc-4.7 > > nightly build Linaro toolchains, > > linaro binutils needs to back port > > http://sourceware.org/git/?p=binutils.git;a=commit;h=3fd1fadc205bc69410080a… > > > > > $ arm-eabi-gcc --version > > arm-eabi-gcc (Linaro GCC 4.7-2012.09-1~dev) 4.7.2 20120910 (prerelease) > > $ arm-eabi-as --version > > GNU assembler (Linux/GNU Binutils) 2.23.51.0.3.20120918 > > > > I get a compiler error (actually, assembler error): > > > > AS arch/arm/lib/copy_from_user.o > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S: Assembler messages: > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:100: Error: selected processor does not support ARM mode `ldralt r3,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:100: Error: selected processor does not support ARM mode `ldralt r4,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:100: Error: selected processor does not support ARM mode `ldralt r5,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:100: Error: selected processor does not support ARM mode `ldralt r6,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:100: Error: selected processor does not support ARM mode `ldralt r7,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:100: Error: selected processor does not support ARM mode `ldralt r8,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:100: Error: selected processor does not support ARM mode `ldralt ip,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:100: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:118: Error: selected processor does not support ARM mode `ldralt r3,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:119: Error: selected processor does not support ARM mode `ldralt r4,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:120: Error: selected processor does not support ARM mode `ldralt r5,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:121: Error: selected processor does not support ARM mode `ldralt r6,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:122: Error: selected processor does not support ARM mode `ldralt r7,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:123: Error: selected processor does not support ARM mode `ldralt r8,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:124: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:173: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt r4,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt r5,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt r6,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt r7,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt r8,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt r9,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt ip,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:243: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt r4,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt r5,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt r6,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt r7,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt r8,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt r9,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt ip,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:245: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt r4,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt r5,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt r6,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt r7,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt r8,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt r9,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt ip,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > /a/home/tbird/work/auto-reduce/lto-test/linux-3/arch/arm/lib/copy_template.S:247: Error: selected processor does not support ARM mode `ldralt lr,[r1],#4' > > make[2]: *** [arch/arm/lib/copy_from_user.o] Error 1 > > make[1]: *** [arch/arm/lib] Error 2 > > make[1]: *** Waiting for unfinished jobs.... > > > > > > This appears to be related to the following bug report for binutils: > > http://sourceware.org/ml/binutils/2012-09/msg00128.html > > > > I'm compiling the kernel for PandaBoard > > > > Any ideas for work-arounds or fixes for this? Note that the ldralt instruction > > doesn't actually appear in copy_template.S (maybe it's coming from a macro?) > > -- Tim > > > > ============================= > > Tim Bird > > Architecture Group Chair, CE Workgroup of the Linux Foundation > > Senior Staff Engineer, Sony Network Entertainment > > ============================= > > _______________________________________________ > linaro-dev mailing list > linaro-dev(a)lists.linaro.org > http://lists.linaro.org/mailman/listinfo/linaro-dev -- Loïc Minier

12 years, 11 months

2
1
0 0

[ACTIVITY] Sep 24 - Sep 28

by Ulrich Weigand

== GCC == * Implemented patch to prevent lower-subreg pass from splitting pseudo register moves during first pass. Committed to mainline. * Updated patch to perform 64-bit integer shifts in NEON registers to avoid NEON single to NEON double register hazard. Re-started testing via Launchpad branch neon-shifts-4.7-v3. * Rebased patch to improve 32-to-64-bit extended from core into NEON registers, added backport of lower-subreg mainline fix. New Launchpad branch neon-extendsidi-4.7-v3. * Tested reload patch to fix aarch64 find_reloads_subreg_address bug on multiple platforms to prepare for mainline. 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

12 years, 11 months

1
0
0 0

[ACTIVITY] Sep 24-Sep 28

by Christophe Lyon

== Progress == * builtin_bswap16: * patch to catch (x<<8)|<x>>8) committed upstream after confirmation it was OK by PowerPC guys. * backporting of builtin_bswap16 for ARM to Linaro/4.7: one of the tests fails. Trying to isolate the trunk change that would make is pass. * useful discussions with Ulrich to investigate if we could avoid generating useless zero-extensions after rev16. I still need to experiment. * PGO/hot-cold partitioning: * applied info from Matt, I have now a usable Spec2000 setup based on qemu. == Next == * builtin_bswap16: * try to avoid useless zero-extensions. * PGO/hot-cold partitioning: * investigate runtime failures. * run on a Snowball board.

12 years, 11 months

2
1
0 0

[ACTIVITY] 24 - 28 September 2012

by Matthew Gretton-Dann

== Progress == * 4.7 AArch64 merge into gcc-linaro/4.7 * Got Foundation model working * Ran testsuite - results OK - some obvious infrastructure issues though * Hot/Cold partitioning in PGO: * Posted second patch upstream * Had basic flaw with it pointed out (shame was the flaw fixed the issue) * Admin * Interviewing == Next Week == * Start of month branch merges. * HOT/COLD partitioning for PGO: * Get two current patches accepted upstream * Post question upstream about register allocation 'mistakes' I am seeing * ARM/aarch64-4.7-branch merge into gcc-linaro/4.7. * Investigate failure in testsuite run * Check that I am merging the svn branches correctly. * Participate in sprint * symbol_ref splitting * Test code alignment hypothesis * Test v2 patch. == Future == * Look at Cards for Vectorization, PGO and LTO with Michael. -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

12 years, 11 months

2
1
0 0

[ACTIVITY] report week 38,39

by Peter Maydell

(two week rollup report since week 38 was a short week for me) Current Milestones: || || Planned || Estimate || Actual || || clean up kvm-qemu cp i/f || 2012-09-20 || 2012-09-20 || || || fake-trustzone || 2012-10-15 || 2012-10-15 || || Also planned: general keeping up with kernel changes; upstream patch review; qemu-linaro releases. May change dates to align with overall KVM plan for the quarter when that is finalised. Previous Milestones: ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-20 || 2012-07-20 || == other == * looked briefly at the result of running the clang static analyzer over QEMU * wrote some fixes to totally broken code in the ds1338 model as result * reviewed some nice TCG optimisation patches from Aurelien which bump up performance for ARM guests by 10-15% * reviewed, bugfixed and committed some patches for the bootwrapper from Dave Martin * removed obsolete SMC API support from bootwrapper (lets us knock the final item off a blueprint) * implemented the new movcond TCG IR insn in the ARM backend KVM blueprint progress tracker: http://ex.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&pr… -- PMM

12 years, 11 months

1
0
0 0

[Activity] Week 39

by Zhenqiang Chen

Summary: * Validate and release Linaro binary toolchain 2012.09 * Identify the root cause of dwarf check fail in native build when enabling shrink-wrap. Details: 1. Validate and release Linaro binary toolchain 2012.09. 2. Analyze the dwarf check fail in native build when enabling shrink-wrap: * Root cause: tail calls from simple-return path and normal return path are optimized as one common tail call. * To fix it, use simple-return to indicate the one from simple-return path, which will block the optimization to mix them. Plans: * Test shrink-wrap performance. Planed leaves: * Sept. 30 - Oct. 7: Mid-Autumn Festival and National Day of China's holiday. Best regards! -Zhenqiang

12 years, 11 months

1
0
0 0

Getting Alignment Fault with linaro toolchain

by Shivamurthy Shastri

Hi, I am using Linaro Toolchain for compiling UEFI and I am getting alignment fault as exception while running UEFI on Origen Board. When I was using other cross compilers the issue was not there. The crash report is as follows: Data Abort Exception PC at 0x4F84DCDC CPSR 0x60000133 nZCveAifT_svc /home/shiva/workspace/armserver/uefi_origen/edk2/Build/OrigenBoard-Exynos/DEBUG_ARMLINUXGCC/ARM/FatPkg/EnhancedFatDxe/Fat/DEBUG/Fat.dll loaded at 0x4F84D000 (PE/COFF offset) 0xCDC (ELF or Mach-O offset) 0xA9C 0xF8BD6037 LDRH r6, [sp, #0x37] R0 0x0000000B R1 0x0000000A R2 0x4FCEEAD8 R3 0x80000000 R4 0x4F836010 R5 0x4F863619 R6 0x00000000 R7 0x4F837F10 R8 0xFFFFFFFF R9 0x00000000 R10 0x00000001 R11 0x00000000 R12 0x00000000 SP 0x4FCEEA20 LR 0x4F84DCDD PC 0x4F84DCDC DFSR 0x00000001 DFAR 0x4FCEEB17 IFSR 0x0000140B IFAR 0x00910883 Alignment fault: read from 0x4FCEEB17 Instruction Domain fault on Page at 0x00910883 ASSERT /home/shiva/workspace/armserver/uefi_origen/edk2/ArmPkg/Library/DefaultExceptionHandlerLib/DefaultExceptionHandler.c(304): ((BOOLEAN)(0==1)) -- Thanks and Regards, Shiva.

12 years, 11 months

3
5
0 0

Linaro is hiring!

by Michael Hope

Interested in working with us on improving the performance of Linux on ARM? We’re looking for motivated engineers to work in our toolchain team on compiler technology, developer tools, and low level performance libraries. You will use your specialised knowledge to work in the open, work upstream, and make ARM flavoured improvements to a range of tools that are fundamental to making the latest mobile and server products. We’re currently looking for: * GCC developers * Developer tools engineers, especially on the GNU tools like binutils and GDB * ARM performance engineers, to work on a range of low level libraries We’re a distributed team. Working from the home office is an option. Please see the careers page on our website for more information and how to contact us. -- Michael

12 years, 11 months

1
0
0 0

[ACTIVITY] Sep 17 - Sep 21

by Ulrich Weigand

== GCC == * Committed patch to use vld1.64/vst1.64 instead of vldm/vstm to GCC mainline and Linaro GCC 4.7 * Committed patch to use vld1/vst1 to implement vec_set/vec_extract to GCC mainline and Linaro GCC 4.7 * Posted patch to perform 64-bit integer shifts in NEON registers for mainline inclusion. Started to address review comments. * Rebased patch to improve 32-to-64-bit extends from core into NEON registers; ran into lower-subreg regression. * Worked on implementing fix for lower-subreg regression. * Handed over (Richard's) auto-inc-dec patches to Matt. 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

12 years, 11 months

1
0
0 0

[ANNOUNCE] Linaro Toolchain Binaries 2012.09 released

by Zhenqiang Chen

The Linaro Toolchain Working Group is pleased to announce the 2012.09 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.09 * Linaro GDB 7.5 2012.09 * 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: * gdbserver is stripped. * gdbtui is replaced by "gdb --tui" 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.09 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.

12 years, 11 months

1
0
0 0

[Activity] Week 38

by Zhenqiang Chen

Summary * Prepare Linaro binary toolchain 2012.09 release * Fix lp:1036170/pr50970 Details: 1. Prepare Linaro binary toolchain 2012.09 release * Update linaro gcc and gdb to 2012.09 release * Workaround gdb lsb build issue. * Strip gdbserver. * Smoke tests. 2. Merge shrink-wrap patch to lp:gcc for cbuild test. But dwarf checks fail when building fortan related codes at stage 2. 3. Identify the root cause of lp:1036170/pr50970 and work out a patch to fix it. Plans: * Linaro binary toolchain 2012.09 release. * Fix shrink-wrap build fail issues. Planed leaves: * Sept. 30 - Oct. 7: Mid-Autumn Festival and National Day of China's holiday. Best regards! -Zhenqiang

12 years, 11 months

1
0
0 0

[ACTIVITY] Sep 17-Sep 21

by Christophe Lyon

== Progress == * Discussed big-endian patches for vext tests: careful review of the specification is required and this patch might actually expose GCC bugs in big-endian/Neon. * builtin_bswap16: * Posted 2 implementations of the generic patch for (x<<8)|(x>>8). The 2nd one looks OK, but I was asked to make some checks on powerPC, which are on-going. * backporting it to Linaro/4.7. On-going: merged obvious patches but one test does not produce the same code as on trunk. * validations in cbuild in with GCC configured for thumb and hard FP showed that some bswap16 tests fail because they force armv6, which leads to unsupported thumb1 configuration. Proposed testsuite modification to make this easier, under discussion with Matt & Richard. == Next == * builtin_bswap16: * check powerPC results and have the patch accepted upstream. * measure probable regression in libav when using the builtin instead of an asm(). * complete backport in Linaro/4.7. * PGO/hot-cold partitioning: start working on this blueprint.

12 years, 11 months

2
1
0 0

[ACTIVITY] 17 - 21 September

by Matthew Gretton-Dann

== Progress == * Fixed https://bugs.launchpad.net/ubuntu/+source/gcc-4.6/+bug/1029454 * After investigating further found that this was actually an issue already fixed in FSF upstream * 4.7 AArch64 merge into gcc-linaro/4.7 * Did an initial merge of upstream ARM/aarch64-4.7-branch into gcc-linaro/4.7 * So far it hasn't broken other platforms * Investigated getting FastModels working for me * Hot/Cold partitioning in PGO: * Tidied up current patches ready for reposting upstream * Handed current status to Christophe == Next Week == * HOT/COLD partitioning for PGO: * Complete hand-over to Christophe * Get two current patches accepted upstream * Post question upstream about register allocation 'mistakes' I am seeing * ARM/aarch64-4.7-branch merge into gcc-linaro/4.7. * Get a test run of aarch64 targetted compiler complete * Confirm no code generation changes for other back-ends * symbol_ref splitting * Test code alignment hypothesis * Test v2 patch. * Admin * Several interviews == Future == * Look at Cards for Vectorization, PGO and LTO with Michael. -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

12 years, 11 months

1
0
0 0

[ACTIVITY] report week 37

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || || clean up kvm-qemu cp i/f || 2012-09-20 || 2012-09-20 || || || fake-trustzone || 2012-10-15 || 2012-10-15 || || Also planned: general keeping up with kernel changes; upstream patch review; qemu-linaro releases. May change dates to align with overall KVM plan for the quarter when that is finalised. Previous Milestones: ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-20 || 2012-07-20 || == track-kvm-abi-changes == * folded in Christoffer's interrupt ABI changes * updated to new ONE_REG ABI for register accesses * QEMU now in sync with the kernel patchset Christoffer has just sent to alkml == other == * qemu-linaro 2012.09 released * various meetings/status calls KVM blueprint progress tracker: http://ex.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&pr…

12 years, 12 months

2
2
0 0

[Activity] Week 37

by Zhenqiang Chen

Summary * Workaround the unwind issue for shrink-wrap * Verify Linaro tickets. Details: 1. Debugging the failed cases for shrink-wrap. To workaround the unwind issue, update arm_expand_epilogue to generate return not simple_return when sp is changed. 2. Setup Linaro toolchain and verify 8 tickets: *Linaro gcc: lp:1036170: Function pointer dereferenced twice. It is ARM special bug which is confirmed in 4.6, 4.7 and FSF trunk only on ARM. lp:1048709: wrong assembler, out of range vldr instruction. Confirmed in Linaro 4.6. Can not reproduce it in 4.7 or FSF 4.6. lp:1014658: It is c++11 related issue in 4.6. lp:944572: It is a gcc general issue. lp:972503 and lp:1039401 can not be reproduced. * Linaro binary toolchain: lp:1046718: confirmed and fixed it. lP:1049498: invalid Plans: * Prepare Linaro binary toolchain 2012.09 release. * Performance test for shrink-wrap. * Follow-up the tickets. Best regards! -Zhenqiang

12 years, 12 months

2
2
0 0

[ACTIVITY] Sep 10-Sep 14

by Christophe Lyon

== Progress == * Committed patch to fix 3 testcases in big-endian after upstream comments. * Updated patch to make vext tests support big-endian after upstream comments. * builtin_bswap16: * Committed implementation for ARM. * Investigating testsuite regressions caused by my patch to catch (x<<8)|(x>>8) == Next == * Continue with bswap16 support.

12 years, 12 months

1
0
0 0

[ACTIVITY] 10 - 14 September

by Matthew Gretton-Dann

== Progress == * Started looking at https://bugs.launchpad.net/ubuntu/+source/gcc-4.6/+bug/1029454 * Confirmed the failure * Unfortunately the git bisect I thought would find the fix didn't * Hot/Cold partitioning in PGO: * Some further investigations * Talked to Uli about one failure - he gave me some further pointers * Admin * Some interviewing == Next Week == * Continue looking at 1029454: cselim tree optimizer generates incorrect code * Start looking at merging the ARM public 4.7 GCC branch into gcc-linaro/4.7 * Hot/Cold Partitioning: * Investigate remaining silent code-gen faults and non-termination issue in SPEC * If failures are fixed start profiledbootstraps and tests on the central boards. * symbol_ref splitting * Test code alignment hypothesis * Test v2 patch. == Future == * Look at Cards for Vectorization, PGO and LTO with Michael. -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

12 years, 12 months

1
0
0 0

[ACTIVITY] Sep 13 - Sep 14

by Ulrich Weigand

== GDB == * Created and published Linaro GDB 7.5 release. == GCC == * Posted patch to use vld1.64/vst1.64 instead of vldm/vstm for mainline inclusion. * Posted patch to use vld1/vst1 to implement vec_set/vec_extract with scalar operand residing in memory. 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

12 years, 12 months

1
0
0 0

[ANNOUNCE] Linaro GDB 7.5 2012.09 released

by Ulrich Weigand

The Linaro Toolchain Working Group is pleased to announce the release of Linaro GDB 7.5. Linaro GDB 7.5 2012.09 is the first release in the 7.5 series. ***NOTE*** Linaro GDB 7.5 2012.09 is identical to the FSF GDB 7.5 release, except for the change in version number and Linaro branding, since all Linaro GDB features were already accepted upstream and are included in the FSF release as-is. Future releases in the Linaro GDB 7.5 series may include additional ARM-focused bug fixes and enhancements. The source tarball is available at: https://launchpad.net/gdb-linaro/+milestone/7.5-2012.09 More information on Linaro GDB is available at: https://launchpad.net/gdb-linaro

13 years

1
0
0 0

[ANNOUNCE] Linaro QEMU 2012.09 released

by Peter Maydell

The Linaro Toolchain Working Group is pleased to announce the release of Linaro QEMU 2012.09. Linaro QEMU 2012.09 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, but it has been updated to be based on upstream's recent 1.2.0 release. The source tarball is available at: https://launchpad.net/qemu-linaro/+milestone/2012.09 More information on Linaro QEMU is available at: https://launchpad.net/qemu-linaro

13 years

1
0
0 0

[ANNOUNCE] Linaro GCC 4.7 and Linaro GCC 4.6 2012.09 released

by Michael Hope

The Linaro Toolchain Working Group is pleased to announce the 2012.09 release of both Linaro GCC 4.7 and Linaro GCC 4.6. Linaro GCC 4.7 2012.09 is the sixth release in the 4.7 series. Based off the latest GCC 4.7.1+svn191123 release, it includes ARM-focused performance improvements and bug fixes. Interesting changes include: * Updates to GCC 4.7.1+svn191123 * Adds support for the NEON vext instruction when shuffling * Backports improvements to scheduling transfers between VFP and core registers * Backports support for the UBFX instruction on certain bit extract idioms Fixes: * PR54252 ICE with too wide alignment assertion on vectorised code * PR54212 ICE due to generating a predicated NEON vdup instruction Linaro GCC 4.6 2012.09 is the nineteenth release in the 4.6 series. Based off the latest GCC 4.6.3+svn191000 release, this is the sixth release after entering maintenance. Interesting changes include: * Updates to 4.6.3+svn191000 The source tarballs are available from: https://launchpad.net/gcc-linaro/+milestone/4.7-2012.09 https://launchpad.net/gcc-linaro/+milestone/4.6-2012.09 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.09 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

13 years

1
0
0 0

GCC 4.6.x miscompiling arm-linux (including Linaro GCC)

by Nicolas Pitre

Hello folks, FYI There is a thread on the arm-linux-kernel mailing list about a GCC bug, and the Linaro version appears to be affected as well. Here's the thread: http://news.gmane.org/group/gmane.linux.ports.arm.kernel/thread=186563 Nicolas

13 years

2
1
0 0

[Activity] Week 36

by Zhenqiang Chen

Summary: * Test shrink-wrap code Details: 1. Add simple_return support in function thumb2_expand_return for shrink-wrap. Here is the make check status * One new fail is due to code size increase. We'd disable it when optimizing function for size on THUMB2. * Other new fails is due to dwarf info. Root cause is ICE at function maybe_record_trace_start gcc_checking_assert (cfi_row_equal_p (cur_row, ti->beg_row)); Here is the failed code segment: tst ... L1 push {r4} ... ldr r4, ... L1: bx lr // common simple return from two branches. Here are the results for cur_row and ti->beg_row of trace starting at L1: {cfa = {offset = 0, base_offset = 0, reg = 13, indirect = 0, in_use = 0}, cfa_cfi = 0x0, reg_save = 0x0} {cfa = {offset = 4, base_offset = 0, reg = 13, indirect = 0, in_use = 0}, cfa_cfi = 0x0, reg_save = 0x7ffff726ab70} Try gcc-linaro-4.5-2011.03. It does not generate the common bx lr. test L1 push {r4} ... pop {r4} bx lr L1: bx lr There is similar bug about it. But the fix is useless for us: http://gcc.gnu.org/bugzilla/show_bug.cgi?id=50833 Plans: * Continue shrink-wrap task. Best regards! -Zhenqiang

13 years

2
3
0 0

[ACTIVITY] Sep 3-Sep 7

by Christophe Lyon

== Progress == * Neon vext support for builtin_shuffle: * Committed vext patch upstream, as well as a small cleanup patch. * Merged vext support into gcc-linaro/4.7 branch. * Posted upstream a follow-up patch to make vext tests support big-endian. Filed PR 54517: wrong code generation in big-endian with inline in these tests. * Updated patch to fix 3 testcases in big-endian after upstream comments. * Implement builtin_bswap16: * Posted upstream a patch to implement bswap16. Discussion on-going, to have less duplication between arm and thumb patterns. * Investigating how to make GCC catch the (x<<8)|(x>>8) construct (where x is unsigned short) and map it to rev16, like builtin_bswap16. == Next == * Continue with bswap16 support.

13 years

2
1
0 0

[ACTIVITY] report week 36

by Peter Maydell

Current Milestones: || || Planned || Estimate || Actual || || clean up kvm-qemu cp i/f || 2012-09-20 || 2012-09-20 || || || fake-trustzone || 2012-10-15 || 2012-10-15 || || Also planned: general keeping up with kernel changes; upstream patch review; qemu-linaro releases. May change dates to align with overall KVM plan for the quarter when that is finalised. Previous Milestones: ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-20 || 2012-07-20 || == track-kvm-abi-changes == * merged in Christoffer's patches altering the IRQ delivery ABI == other == * resent some patches as qemu trunk has reopened after 1.2 release * misc upstream review work * prep for qemu-linaro 2012.09 release * AFDS (annual review) season again KVM blueprint progress tracker: http://ex.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&pr… -- PMM

13 years

1
0
0 0

[ACTIVITY] Week 3 - 7 September

by Matthew Gretton-Dann

== Progress == * Started looking at symbol_ref splitting benchmark results * One big regression ~18% * Started to investigate whether code alignment was the problem as before * Hot/Cold partitioning in PGO: * https://blueprints.launchpad.net/gcc-linaro/+spec/hot-cold-partitioning-in-… * Sent fixes so far upstream * Spent most of the week looking at a Silent Code Gen fault in reload. * Admin * Some interviewing == Next Week == * symbol_ref splitting * Test code alignment hypothesis * Test v2 patch. * Hot/Cold Partitioning: * Investigate remaining silent code-gen faults and non-termination issue in SPEC * If failures are fixed start profiledbootstraps and tests on the central boards. == Future == * Look at Cards for Vectorization, PGO and LTO with Michael. -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years

1
0
0 0

Issue with reload and indirect branches

by Matthew Gretton-Dann

All, I have run into a(nother) problem with reload with -freorder-blocks-and-partition. Attached is my WIP patch (some of this has been sent up to gcc-patches for review), and also the profile information (tarred up) I have gathered in the train session I get a segfault when executing crafty, which seems to come from incorrect code generation in iterate.c. The following shows some of the RTL dump after IRA (insn 3087 1471 3088 163 (clobber (reg:DI 682 [ D.7985 ])) -1 (nil)) (insn 3088 3087 3085 163 (set (subreg:SI (reg:DI 682 [ D.7985 ]) 0) (sign_extend:SI (mem/c:QI (reg/f:SI 1417) [0 transposition_id+0 S1 A8]))) 735 {*thumb2_extendqisi_v6} (expr_list:REG_DEAD (reg/f:SI 1417) (nil))) ... (insn 3089 1477 1478 163 (set (subreg:SI (reg:DI 682 [ D.7985 ]) 4) (ashiftrt:SI (subreg:SI (reg:DI 682 [ D.7985 ]) 0) (const_int 31 [0x1f]))) 130 {*arm_shiftsi3} (nil)) ... (insn 2898 2622 2899 203 (set (reg:SI 1677) (mem/u/c:SI (symbol_ref/u:SI ("*.LC60") [flags 0x2]) [2 S4 A32])) 635 {*thumb2_movsi_vfp} (insn_list:REG_LABEL_OPERAND 1525 (expr_list:REG_EQUIV (label_ref:SI 1525) (nil)))) (insn 2899 2898 3491 203 (set (reg:SI 1678) (ior:SI (reg:SI 1677) (const_int 1 [0x1]))) 98 {*iorsi3_insn} (expr_list:REG_DEAD (reg:SI 1677) (nil))) (insn 3491 2899 3492 203 (set (reg:DI 1734 [orig:682 D.7985 ] [682]) (reg:DI 682 [ D.7985 ])) 636 {*movdi_vfp} (nil)) ... (jump_insn 2900 3499 2625 203 (set (pc) (reg:SI 1678)) 727 {*thumb2_indirect_jump} (expr_list:REG_DEAD (reg:SI 1678) (expr_list:REG_CROSSING_JUMP (nil) (nil)))) ... Insns 2898, 2899, and 2900 form the standard Thumb-2 indirect jump sequence. Insn 3491 is a move that has been generated as part of emit_moves in IRA for the loop it belongs to (effectively copying r682 into r1734). Now despite thinking that r1678 is live throughout insn 3491 after reload this part of the RTL dump looks like (insn 2898 2622 2899 212 (set (reg:SI 4 r4 [1677]) (mem/u/c:SI (symbol_ref/u:SI ("*.LC60") [flags 0x2]) [2 S4 A32])) 635 {*thumb2_movsi_vfp} (insn_list:REG_LABEL_OPERAND 1525 (expr_list:REG_EQUIV (label_ref:SI 1525) (nil)))) (insn 2899 2898 3491 212 (set (reg:SI 4 r4 [1678]) (ior:SI (reg:SI 4 r4 [1677]) (const_int 1 [0x1]))) 98 {*iorsi3_insn} (nil)) (insn 3491 2899 3493 212 (set (reg:DI 4 r4 [orig:682 D.7985 ] [682]) (mem/c:DI (plus:SI (reg/f:SI 13 sp) (const_int 24 [0x18])) [9 %sfp+-672 S8 A64])) 636 {*movdi_vfp} (nil)) ... (jump_insn 2900 3497 2625 212 (set (pc) (reg:SI 4 r4 [1678])) 727 {*thumb2_indirect_jump} (expr_list:REG_CROSSING_JUMP (nil) (nil))) That is all of r682, r1678, and r1734 have been assigned to hard register r4. This is incorrect - as insn 2900 wants to be using r1678 from insn 2899. Looking at the logs it seems to me that r1734 because its original is r682 and that is assigned r4. The reload dump says the following about the liveness of the registers for various insns: insn=3087, live_throughout: ..., dead_or_set: 682 insn=3088, live_throughout: ..., dead_or_set: 682 insn=3089, live_throughout: ..., dead_or_set: 682 insn=2898, live_throughout: ..., 682, ..., dead_or_set: 1677 insn=2899, live_throughout: ..., 682, ..., dead_or_set: 1677, 1678 insn=3491, live_throughout: ..., 682, 1678, ..., dead_or_set: 1734 insn=2900, live_throughout: ..., 682, 1734, ..., dead_or_set: 1678 This suggests to me that the compiler should know assigning the same hard-register to r682 and r1678 is incorrect as they have overlapping live-ranges, and are not duplicates of each other. The compiler is configured as follows: Target: arm-none-linux-gnueabi Configured with: /work/sources/gcc-fsf-enable-hot-cold-partitioning/configure --target=arm-none-linux-gnueabi --prefix=/work/builds/gcc-fsf-enable-hot-cold-partitioning-arm-none-linux-gnueabi/tools --with-sysroot=/work/builds/gcc-fsf-enable-hot-cold-partitioning-arm-none-linux-gnueabi/sysroot --disable-libssp --disable-libgomp --disable-libmudflap --enable-languages=c,c++,fortran --with-cpu=cortex-a9 --with-fpu=neon --with-float=softfp --enable-build-with-cxx : (reconfigured) /work/sources/gcc-fsf-enable-hot-cold-partitioning/configure --target=arm-none-linux-gnueabi --prefix=/work/builds/gcc-fsf-enable-hot-cold-partitioning-arm-none-linux-gnueabi/tools --with-sysroot=/work/builds/gcc-fsf-enable-hot-cold-partitioning-arm-none-linux-gnueabi/sysroot --disable-libssp --disable-libgomp --disable-libmudflap --enable-languages=c,c++,fortran --with-cpu=cortex-a9 --with-fpu=neon --with-float=softfp --enable-build-with-cxx Thread model: posix gcc version 4.8.0 20120821 (experimental) (GCC) The gcc command line looks like: ./xgcc -B`pwd` -march=armv7-a -mtune=cortex-a9 -mthumb -mfpu=neon -mvectorize-with-neon-quad -mfloat-abi=softfp -fprofile-use=.../186.crafty -freorder-blocks-and-partition -fno-common -fdump-noaddr -O3 -dp -save-temps iterate.c -o iterate.o Does anyone have any hints as to where I should go looking? Thanks, Matt -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years

1
0
0 0

Cross Compile LKM for Pandaboard ES

by Beni

First I am trying to learn and am in no way an expert. I have searched and searched for a walkthrough on how to compile LKMs for my pandaboard ES. My target is the pandaboard running Linaro 12.08. I am using Linaro toolchain binary 12.08. My confusion comes from me not knowing where the kernel sources are (really how to get them) and the target libraries. I guess what I expect is the target's rootfs with kernel source to be somewhere on my Ubuntu Host so I can link to them. I have tried the following make file configs. But obviously, I don't have the correct path for KERNDIR as I don't know if it even exists on my host. And the second make file seems like a native compile. My previous experience with buildroot: KERNDIR=/opt/buildroot/build_arm/linux-2.6.20.7/ export CROSS_COMPILE=arm-linux- export ARCH=arm obj-m += pwr_led.o all: make -C $(KERNDIR) M=$(PWD) modules clean: make -C $(KERNDIR) M=$(PWD) clean Web examples: obj-m = foo.o KVERSION = $(shell uname -r) all: make -C /lib/modules/$(KVERSION)/build M=$(PWD) modules clean: make -C /lib/modules/$(KVERSION)/build M=$(PWD) clean Could you please set my head straight by pointing me to a webpage or briefly walking through the steps? Thanks, Todd

13 years

1
0
0 0

Re: [Linaro-toolchain-dev] Linaro tool chain manuals

by Matthew Gretton-Dann

Assaf, Just to let you know that linaro-toolchain-dev(a)lists.launchpad.net is a closed list, a better place for this question is linaro-toolchain(a)lists.linaro.org. On 3 September 2012 11:41, Assaf Hoffman <hoffman(a)marvell.com> wrote: > Hi, > > Where can I find Linaro toolchain manuals? The manuals are distributed as *.info files, as per FSF GCC. These are found in .../share/info/ under wherever you installed your toolchain. One way to view these is to run info as follows: info -f .../share/info/gcc.info > I’m looking for Linaro supported optimization flag list. > > Is it a super set of FSF GCC? Linaro GCC 4.X supports all the options of FSF GCC 4.X, it may also support options that were added in later versions of FSF GCC if the appropriate functionality has been backported. The info files will document these new options. Unfortunately, I do not have an easy to read list of these options (if indeed there are any), so I can't provide you with any further pointers at the moment. Thanks, Matt -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years

2
1
0 0

[Activity] Week 35

by Zhenqiang Chen

Summary: * Release Linaro binary toolchain 2012.08 * Start shrink-wrap task Details: 1. Validate and release Linaro binary toolchain 2012.08. 2. Start shrink-wrap task https://launchpad.net/gcc-linaro/+spec/shrink-wrapping: * Learn the background from the mail-list discussion: http://old.nabble.com/Shrink-wrapping%3A-Introduction-to31220423.html * Build X86/MIPS trunk toolchain to check the changes. * Try to apply ARM backend related patches. It can get correct result for several small cases. But lots of new fails in gcc make-check. "pop_multiple_with_writeback_and_return" is not handled correctly. Plans: * Continue the shrink-warp work. Best regards! -Zhenqiang

13 years

1
0
0 0

[ACTIVITY] report week 35

by Peter Maydell

(Short week: 4 days, bank holiday) Current Milestones: || || Planned || Estimate || Actual || || clean up kvm-qemu cp i/f || 2012-09-20 || 2012-09-20 || || || fake-trustzone || 2012-10-15 || 2012-10-15 || || Also planned: general keeping up with kernel changes; upstream patch review; qemu-linaro releases. May change dates to align with overall KVM plan for the quarter when that is finalised. Previous Milestones: ||cp15-rework || 2012-01-06 || 2012-06-23 || 2012-06-24 || ||a15-lpae-support || 2012-07-13 || 2012-07-20 || 2012-07-20 || == track-kvm-abi-changes == * working through design of how we do sync of register state between QEMU and the kernel and how we handle migration (the two turn out to be related and I now have a nice looking design that resolves both of these at once) * both the interrupt injection ABI and the coprocessor access ABI are changing (again!) == other == * fixed an embarrassing bug which made qemu-system-arm segfault on 32 bit hosts; luckily spotted just in time for QEMU 1.2 release * AFDS (annual review) season again KVM blueprint progress tracker: http://ex.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&pr… -- PMM

13 years

1
0
0 0

[ACTIVITY] Week of 27 - 31 August

by Matthew Gretton-Dann

== Progress == * Bank Holiday on Monday * Got symbol_ref split benchmarking going * Hot/Cold partitioning in PGO: * https://blueprints.launchpad.net/gcc-linaro/+spec/hot-cold-partitioning-in-… * Investigated and fixed all compile-time failures in SPEC * Investigated and fixed a silent code-gen fault in SPEC == Next Week == * Look at symbol_ref split benchmarking results * Hot/Cold Partitioning: * Investigate remaining silent code-gen faults and non-termination issue in SPEC * If failures are fixed start profiledbootstraps and tests on the central boards. == Future == * Look at Cards for Vectorization, PGO and LTO with Michael. -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years

1
0
0 0

[ACTIVITY] Aug 27-Aug 31

by Christophe Lyon

== Progress == * Validation of my vext patch in big-endian mode proved that proper support would be non-trivial. Spent a lot of time writing a self-testing executable test, which works in both big and little endian modes. Posted an updated patch which makes no optimization in big-endian. After discussion with Ramana, I will post a 2nd patch which improves the testing in big-endian mode. * In the process, wrote a patch to fix 3 other testcases which used to fail in big-endian mode. * Received no answer from the original contributor of bswap16 support patch. == Next == * Have my vext patch accepted on trunk. * Continue with bswap16 support.

13 years

2
1
0 0

[ACTIVITY] report week 34

by Peter Maydell

(Short week: 3 days) Current Milestones: || || Planned || Estimate || Actual || || clean up kvm-qemu cp i/f || 2012-09-20 || 2012-09-20 || || || fake-trustzone || 2012-10-15 || 2012-10-15 || || Also planned: general keeping up with kernel changes; upstream patch review; qemu-linaro releases. May change dates to align with overall KVM plan for the quarter when that is finalised. Previous Milestones: ||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 == * patches as they stand look good; currently blocked waiting for changes to go into kernel side == track-kvm-abi-changes == * thinking about some interesting corner cases in accessing cp15 state via KVM, notably how userspace should get at the cache ID registers, which are exposed by hardware as a "select" and "read value of selected register" cp15 register pair. Consensus seems to be that the kernel should deal with converting this into a simple interface that userspace can use to just read all the ID register state at once. == other == * fixed breakage in ARM TCG host support (recent changes had failed to account for the ABI requirement that 64 bit arguments to functions must be passed in even-odd register pairs) * KVM bootwrapper: pushed 64-bit-addresses-in-dtb patch to main repo; reviewed patch from Guodong Xu adding uInitrd support KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&… -- PMM

13 years

1
0
0 0

[ANNOUNCE] Linaro Toolchain Binaries 2012.08 released

by Zhenqiang Chen

The Linaro Toolchain Working Group is pleased to announce the 2012.08 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.08 * 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: * Enable threaded gold linker 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.08 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

1
0
0 0

[Activity] Week 34

by Zhenqiang Chen

Summary: * Identify the root cause of performance regression for the "split2" patch. * Validate Linaro binary toolchain prerelease. Details: 1. Identify the root cause of performance regression for the "split2" patch. * Code alignment is the root cause for the performance regression (Michael reproduced it with "__attribute__ ((aligned(16)))"). * "build-id" section is the root cause of result difference from cbuild test (the additional section makes the function address different). * Workout a small case to show the impact of code alignment on performance. 2. Linaro binary toolchain 2012.08 prerelease validation. All tests pass. Absence: * Annual leave: Aug. 24. Plans: * Linaro binary toolchain 2012.08 release. * Start shink-wrap work. Best regards! -Zhenqiang

13 years

1
0
0 0

LTO for the kernel

by Christian Robottom Reis

In case nobody here caught it: https://lwn.net/Articles/512548/ Interesting? Worth talking to Andi about it for ARM? -- Christian Robottom Reis | [+55 16] 3376 0125 | http://async.com.br/~kiko Async Open Source | [+55 16] 9112 6430 | http://launchpad.net/~kiko

13 years

1
0
0 0

[ACTIVITY] Aug 21-Aug 24

by Christophe Lyon

== Progress == * Fixed problems with my patch for "constant vec permute operation for the vext instruction" blue-print, validated in cbuild. * Ported it to trunk and submitted for review. R.Earnshaw requested validation on big-endian. I need to upgrade my qemu to have it supported. * Compiled my Neon intrinsics testsuite with LLVM (version 3.2 trunk 160543). It compiles at O0/O1/O2/O3, but only O0 produces the expected results. Errors include: vset_lane, vld3, and vld4. * Started looking a bswap16 support == Next == * Have my "constant vec permute operation for the vext instruction" patch accepted on trunk * Continue with bswap16 support.

13 years

1
0
0 0

[ACTIVITY] 20 August - 24 August

by Matthew Gretton-Dann

== Progress == * Follow up from 2012.08 Toolchain release * Updated Wiki pages * Start working on symbol_ref split benchmarking. * Backport to PR54212 done upstream to 4.6 and 4.7 * Started picking up Hot/Cold partitioning in PGO blueprint: * https://blueprints.launchpad.net/gcc-linaro/+spec/hot-cold-partitioning-in-… * Got SPEC running locally and I think I have reproduced Ramana's failures. == Next Week == * Bank Holiday on Monday * Investiagte SPEC failures in Hot/Cold PGO * Get symbol_ref benchmarking going properly == Future == * Look at Cards for Vectorization, PGO and LTO with Michael. -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years

1
0
0 0

Testing builds via cbuild

by Michael Hope

(cc'd to linaro-toolchain to archive) Hi Matt. I've had a look at the manual builds you tried to spawn. Here's what I did to run cbuild locally to test it: * cd linaro * bzr branch lp:cbuild * cd cbuild/slaves * cp -a example `hostname` * cd `hostname` * make -f ../../lib/build.mk final/gcc-4.8+svn190558.stamp I'm not proud of the whole 'slaves/$hostname' setup, but it is what it is. Results are in $version, such as gcc-4.8+svn190558. The build tree is in $version/gcc/default/build. Nuke using rm -rf final results $version. See lib/common.mk and override the email address etc in local.mk to stop build results going out You should put a proxy in $http_proxy or ~/.wgetrc to reduce the download cost. Please add to the cbuild README. A nit: we use the Debian versioning scheme so the version should be 4.8~svn190558, i.e. a SVN checkout leading up to 4.8. Compare with 4.7+svn1234, which is a SVN checkout of the 4.7 branch. The tarballs look generally good. I've spawned them into the a9hf queue as that's what we benchmark on. Note that they're low priority due to not having 'linaro' in the name. -- Michael

13 years

1
0
0 0

Function alignment and benchmark results

by Michael Hope

Zhenqiang's been working on the later split 2 patch which causes more constants to be built using a movw/movt instead of a constant pool load. There was an unexpected ~10 % regression in one benchmark which seems to be due to function alignment. I think we've tracked down the reason but not the action. Compared to the baseline, the split2 branch took 113 % of the time to run, i.e. 13 % longer. Adding an explicit 16 byte alignment to the function changed this to 97 % of the time, i.e. 3 % faster. The reason Zhenqiang and I got different results was the build-id. He used the binary build scripts to make the cross compiler, which turn on the build ID, which added an extra 20 bytes ahead of .text, which happened to align the function to 16 bytes. cbuild doesn't use the build-id (although it should) which happened to align the function to an 8 byte boundary. The disassembly is identical so I assume the regression is cache or fast loop related. I'm not sure what to do, so let's talk about this at the next performance call. -- Michael

13 years

3
2
0 0

Actions from Toolchain Performance Call 21 August 2012

by Matthew Gretton-Dann

All, I have updated the minutes from today's Performance Call here: https://wiki.linaro.org/WorkingGroups/ToolChain/Meetings/2012-08-21 The following are the actions from the meeting: * michaelh to folow-up and ping Mans on getting a hold of his benchmark runs * michaelh to investigate regression with movw/movt patch by hand * mgrettondann to run current symbol ref splitting patch over SPEC against FSF trunk * michaelh to point mgrettondann to existing cards * michaelh and mgrettondann to start writing card for PGO work * mgrettondann to pick up Hot/Cold Partitioning patch from ramana, cross-test against SPEC for correctness, and then do a benchmarking run * ramana to create a Blueprint for min-idion in middle-end and update Todo list with link * mgrettondann to update todo list with changes in 2012.08 release. * zchen to work on shrink-wrapping * clyon to update his vext patch The next meeting is on 4 September and a proposed Agenda is here: https://wiki.linaro.org/WorkingGroups/ToolChain/Meetings/2012-09-04 Please add any items you wish to discuss to the agenda. Thanks, Matt -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years

1
0
0 0

Re: [Linaro-toolchain-builds] [cbuild] eglibc-2.16~svn20181 armv7l failed

by Michael Hope

On 18 August 2012 12:06, Ramana Radhakrishnan <ramana.radhakrishnan(a)linaro.org> wrote: > This should have been fixed by this patch . I'm a bit surprised that > we are seeing these failures still ? > > ../ports/sysdeps/unix/sysv/linux/arm/ldsodefs.h:41:0: warning: > "MORE_ELF_HEADER_DATA" redefined [enabled by default] > > http://permalink.gmane.org/gmane.comp.lib.glibc.ports/1428 > > which should have made it back to eglibc 2.16 ? Well, that's embarrassing. The eglibc script is used to both build eglibc and to use a fixed eglibc to test GCC. The latter was winning so every snapshot build was actually building eglibc 2.12. Fixed and testing, -- Michael

13 years

2
2
0 0

[ACTIVITY] report week 33

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 || || || || == clean-up-kvm-patches == * started on driving "read/write cp15 regs from kernel" from the existing QEMU hashtable of cp regs it knows about. First cut seems to work, but needs more testing and also qemu's ARMCPRegInfo struct needs to provide raw_read/write methods which bypass access permission and similar checks. == other == * shepherded various things into upstream QEMU for 1.2 release freeze: arm-devs patch queue, linux-user patches, some minor stuff * qemu-linaro 2012.08 released * travel booked for Connect/ELC-E/KVM Forum; rest is blocked on the Connect conference hotel discount rate/booking info appearing KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&… -- PMM

13 years

1
0
0 0

[ANNOUNCE] Linaro GCC 4.7 and 4.6 2012.08 released

by Michael Hope

The Linaro Toolchain Working Group is pleased to announce the 2012.08 release of both Linaro GCC 4.7 and Linaro GCC 4.6. Linaro GCC 4.7 2012.08 is the fifth release in the 4.7 series. Based off the latest GCC 4.7.1+svn189992 release, it includes many ARM-focused performance improvements and bug fixes. Interesting changes include: * Updates to GCC 4.7.1+svn189992 * An ABI fix for vectors with the wrong layout * Backports improvements to the NEON vdup instruction with immediates * Backports a fix to performance regressions in partial redundancy elimination at high optimisation * Backports faster 64 bit core register adds with immediates A bug has been fixed in GCC's implementation of the AAPCS rules for the layout of vectors that could lead to wrong code being generated. Vectors larger than 8 bytes in size are now by default aligned to an 8-byte boundary. This is an ABI change: code that makes explicit use of vector types may be incompatible with binary objects built with older versions of GCC. Auto-vectorized code is not affected by this change. Fixes: * LP: #1020601 Strange behaviour with __builtin_unreachable() * PR38785 huge performance regression on EEMBC bitmnp01 * PR53447 missed optimization of 64bit ALU operation with small constant Linaro GCC 4.6 2012.08 is the eighteenth release in the 4.6 series. Based off the latest GCC 4.6.3+svn189991 release, this is the fifth release after entering maintenance. Interesting changes include: * Updates to 4.6.3+svn189991 * An ABI fix for vectors with the wrong layout The source tarballs are available from: https://launchpad.net/gcc-linaro/+milestone/4.7-2012.08 https://launchpad.net/gcc-linaro/+milestone/4.6-2012.08 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.08 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

13 years

1
0
0 0

[ACTIVITY] Aug 13-Aug 17

by Christophe Lyon

== Progress == * Out of office Friday 17 * Attended Virtual Connect sessions: * Vectorization * PGO/LTO: provided benchmarking results on Webkit computed in ST last year. * At last managed to have bzr working * Prepared a patch for "constant vec permute operation for the vext instruction" blue-print, based on linaro-gcc/4.7 * Some pending internal work == Next week == * Out of office Monday 20 * Check reviews for my patch to have it accepted.

13 years

1
0
0 0

PGO and LTO session preparation

by Michael Hope

Hi Matt. I've fleshed out the Etherpad for the PGO and LTO session at: http://pad.linaro.org/GzRj35tXFt It's a topic list that needs some specifics. Could you make sure we have basic answers to any correctness or performance questions? Ramana, could you add the specifics from the performance call? I can't seem to find the right meeting in the logs. -- Michael

13 years

3
4
0 0

[ACTIVITY] Aug 13 - Aug 17

by Matthew Gretton-Dann

== Progress == * Out of office Friday 17 * Attended Virtual Connect sessions * Vectorization * Ran PGO/LTO session * Lurked on AArch64/OpenEmbedded and Dalvik Performance sessions * Did the 2012.08 release of the Toolchain * Ran into infrastructure problems with armv5 builds * Most of the build process is now done * Start working on symbol_ref split benchmarking. * Struggled to get my jobs to spawn * Started to backport Ramana's fix to PR54212 * Submitted merge request for 4.7 backport == Next Week == * Ensure 2012.08 release is completed * Get symbol_ref benchmarking going properly * Complete backports of PR54212 * Follow up to Virtual Connect Sessions == Future == * Get my name against some blue-prints * Find a small patch to GCC to use to pipeclean the submission process -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years

1
0
0 0

[ANNOUNCE] Linaro QEMU 2012.08 released

by Peter Maydell

The Linaro Toolchain Working Group is pleased to announce the release of Linaro QEMU 2012.08. Linaro QEMU 2012.08 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. The source tarball is available at: https://launchpad.net/qemu-linaro/+milestone/2012.08 More information on Linaro QEMU is available at: https://launchpad.net/qemu-linaro

13 years

1
0
0 0

Re: [Linaro-toolchain-builds] [cbuild] gcc-linaro-4.7-2012.08 armv7l failed

by Michael Hope

On 15 August 2012 00:45, Matthew Gretton-Dann <matthew.gretton-dann(a)linaro.org> wrote: > So looking at the logs this seems to be a transient data transfer error: > > The logs (http://builds.linaro.org/toolchain/gcc-linaro-4.7-2012.08/logs/armv7l-natty…) > have: > > make[4]: Entering directory `/scratch/cbuild/slave/slaves/tcpanda02' > make -s -f ../../lib/fetch.mk > gcc-linaro-4.7-2012.08/gcc-linaro-4.7-2012.08.tar-spawn 2>&1 | grep -v > '^make\[' > Trying http://builds.linaro.org/toolchain/snapshots/gcc-linaro-4.7/gcc-linaro-4.7-… > Trying http://ex.seabright.co.nz/snapshots/gcc-linaro-4.7/gcc-linaro-4.7-2012.08.t… > Trying http://builds.linaro.org/toolchain/snapshots/gcc-linaro-4.7-2012.08.tar.xz > Trying http://ex.seabright.co.nz/snapshots/gcc-linaro-4.7-2012.08.tar.xz > Trying http://builds.linaro.org/toolchain/snapshots/gcc-linaro-4.7/gcc-linaro-4.7-… > Trying http://ex.seabright.co.nz/snapshots/gcc-linaro-4.7/gcc-linaro-4.7-2012.08.t… > Trying http://builds.linaro.org/toolchain/snapshots/gcc-linaro-4.7-2012.08.tar.bz2 > Trying http://ex.seabright.co.nz/snapshots/gcc-linaro-4.7-2012.08.tar.bz2 > bunzip2: gcc-linaro-4.7-2012.08/gcc-linaro-4.7-2012.08.tar.bz2: data > integrity (CRC) error in data Not sure here. ex.seabright is the authoritative source. Perhaps there was a fault with the proxy in the control lab? The good news is that the test fired and the build failed early. I've logged LP: #1036867 to see if it happens again. > The x86_64 build has succeeded OK though, so I (well Ramana really) > have, eventually, restarted that build. We did encounter some issues > with restarting the build as follows: > > 1) My Launchpad ID doesn't have permissions to spawn jobs through the > web interface at ex.seabright.co.nz Fixed. > 2) So I attempted to spawn the job manually as follows: > > $ ssh -p7023 cbuild(a)ex.seabright.co.nz ./cbuild/tools/spawn.sh > gcc-linaro-4.7-2012.08 armv5-builder > Spawning gcc-linaro-4.7-2012.08 into the queue benchmarks > Spawned into a9-builder > > This wasn't exactly what I expected. What are the correct runes > here to get a build? Spawn picks the closest spawn class based on the filename or, if supplied, the second argument. Here you supplied 'armv5...' which is closest to 'benchmarks'. What you want is to click 'Release' beside the job name in the scheduler view, to respawn through the /spawn interface, or to touch the .job file in cbuild@orion:~/queue/armv5-builder. > I've left this job in place as I've probably done enough damage already... > > 3) Ramana then attempted to use the web-interface at > http://ex.seabright.co.nz/helpers/recent to get the job to rebuild > (http://ex.seabright.co.nz/helpers/scheduler/spawn?queue=armv7l&job=gcc-lina…). > However, this results in a Python exception. Real men don't use user-friendly argument checking :) Well, not on hacks like this tool. There is no armv7l queue so an assert fired. > 4) Finally we used Ramana's credentials on the spawn interface, and > that seems to have spawned the rebuild correctly. Good. > I'll let this run and see what happens. > > Michael, can you just check that things are progressing properly > please, and also give me appropriate permissions on the web interface? Checking: http://ex.seabright.co.nz/helpers/buildlog/gcc-linaro-4.7-2012 shows that the build finished on x86_64 and i686. Checking /scheduler shows that ARM builds are in progress on a9hf, a9, and armv5. Most are in the testsuite and have ~6 hours to go. -- Michael

13 years, 1 month

1
1
0 0

[Activity] Week 32

by Ramana Radhakrishnan

== Progress == Linaro tasks. * Some work on the intrinsics patches. * Looked into auto-inc-dec stuff. Not enough improvements with scheduler changes. * Helped Matt get up to speed and wrote up some stuff for Christophe with the vext examples. * Investigated a bug that Mans reported upstream with the compiler generating vdupeq . Have a patch being tested. == Plans == * Finish up pending patches upstream. (neon intrinsics patches need to be committed) * Finish handing over patches. * Fix PR54212.

13 years, 1 month

1
0
0 0

[Activity] Week 31

by Ramana Radhakrishnan

Looks like I missed sending this for 2 weeks in a row. == Progress == Linaro tasks. * Some upstream discussions on neon testsuite bug. Poked at ML for quite a bit. Looks like regexps in the neon intrinsics testsuite is just wrong. * Looking at a better way of doing the 64 bit arithmetic patches that carrot proposed. Don't like them. * Discussed with Richard about ubfx for a while. * Reviewed the backlog and came up with suggestions for things for people to do . Thought a bit about some stuff that Michael asked me to look at . == Plans == * Look at auto-inc-dec patches more and investigate benchmark results. * Follow up on Intrinsics work. * Follow-up on my intrinsics patches upstream. * Finish looking at PR53664 and clean up testsuite further. * Set up a TC2 for Linaro for benchmarking in the validation lab. == Absences == * 17th Sept - 5th Oct - Vacation approved. * 29th Oct - 5th Nov - Copenhagen Linaro Connect. Travel and hotel to be booked.

13 years, 1 month

1
0
0 0

Linaro 2012-08 GCC 4.6 and 4.7 releases

by Matthew Gretton-Dann

All, Is there anything left to go into the branches that needs to be in the releases this week? I believe Uli's patches have gone in - is there anything else required? I will start spinning the releases around 0800 UTC tomorrow if nothing else is needed for the release. Thanks, Matt -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years, 1 month

2
1
0 0

Options for ARM A9 Cortex-MP without FPU

by Peter

I would like to run Ubuntu 12.04 on a A9 Cortex-MP/armv7-a development system that has *no FPU* hardware floating point unit. Does this mean the entire toolchain needs to be recompiled? Could you please shed light on appropriate settings (toolchain and/or kernel) soft FPU emulation related options for armv7-a without a FPU? Thank...Peter

13 years, 1 month

2
1
0 0

[ACTIVITY] Aug 8 - Aug 10

by Christophe Lyon

== Progress == * Started Linaro ramp up process * Lots of admin, PC setup, Linaro docs reading * Still unable to make bzr work. Investigating proxy restrictions. * Started working on "constant vec permute operation for the vext instruction" * Still some pending internal work == Next week * Out of office Wed 15, Friday 17 and Monday 20 * Attend appropriate Virtual Connect sessions * Progress on "constant vec permute operation for the vext instruction"

13 years, 1 month

1
0
0 0

Virtual Connect next week

by Michael Hope

Virtual Connect is up next week. We've got two sessions lined up: the first on profile guided optimisation and link time optimisation, and the second on next steps with the vectoriser. Some other highlights are the ones on system trace, Dalvik, and Aarch64 via OpenEmbedded bootstrap. The schedule is up at: http://www.linaro.org/linaro-blog/2012/08/07/linaro-announces-virtual-conne… Our sessions are "Analyzing vectorizer performance regressions in GCC 4.7 and 4.8" at 1000 UTC on Monday and "Exploring The Performance Impact of PGO and LTO on ARM" at 1000 UTC on Thursday. You'll need Google Hangout set up to join. For those who can't make it, the sessions also get recorded out to the Linaro OnAir YouTube channel. I've cancelled the Monday regular and Thursday stand up calls. See you next week! -- Michael

13 years, 1 month

3
3
0 0

[ACTIVITY] report week 32

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 == * did enough cleanup to be able to send a coherent initial RFC patchset to qemu-devel/kvmarm. == other == * upstream patch review, in preparation for QEMU 1.2 freeze next week * put together qemu-linaro 2012.08 tarball (release next week) KVM blueprint progress tracker: http://apus.seabright.co.nz/helpers/backlog?group_by=topic&colour_by=state&… -- PMM

13 years, 1 month

1
0
0 0

[ACTIVITY] Aug 6 - Aug 10

by Ulrich Weigand

== GCC == * Back-ported patch to change vector alignment to 8 to FSF GCC 4.6 and 4.7 and Linaro GCC 4.6 and 4.7. * Investigated mp3player benchmark regression with Linaro GCC 4.7 backport of vector alignment patch. 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, 1 month

1
0
0 0

[ACTIVITY] Aug 6 - Aug 10

by Matthew Gretton-Dann

== Progress == * Started Linaro ramp up process * Lots of admin, paperwork, and PC setup * Successfully built compilers from Linaro and upstream trees * Out of office Friday 10 == Next Week == * Out of office Friday 17 * Attend appropriate Virtual Connect sessions * Do the 2012.08 release of the Toolchain * Start working on symbol_ref split benchmarking. == Future == * Find a small patch to GCC to use to pipeclean the submission process -- Matthew Gretton-Dann Linaro Toolchain Working Group matthew.gretton-dann(a)linaro.org

13 years, 1 month

1
0
0 0

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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, 1 month

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

13 years, 1 month

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

13 years, 2 months

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&…

13 years, 2 months

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

13 years, 2 months

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

13 years, 2 months

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

13 years, 2 months

1
0
0 0

2025

2024

2023

2022

2021

2020

2019

2018

2017

2016

2015

2014

2013

2012

2011

2010

linaro-toolchain