- linaro-toolchain - lists.linaro.org

Idea for auto-increment performance improvement

by Richard Sandiford

Last week, Ramana pointed me at an upstream bug report about the inefficient code that GCC generates for vzip, vuzp and vtrn: http://gcc.gnu.org/bugzilla/show_bug.cgi?id=48941 It was filed not longer after the Neon seminar at the summit; I'm not sure whether that was a coincidence or not. I attached a patch to the bug last week and will test it this week. However, a cut-down version shows up another problem that isn't related specifically to intrinsics. Given: #include <arm_neon.h> void foo (float32x4x2_t *__restrict dst, float32x4_t *__restrict src, int n) { while (n--) { dst[0] = vzipq_f32 (src[0], src[1]); dst[1] = vzipq_f32 (src[2], src[3]); dst += 2; src += 4; } } GCC produces: cmp r2, #0 bxeq lr .L3: vldmia r1, {d16-d17} vldr d18, [r1, #16] vldr d19, [r1, #24] vldr d20, [r1, #32] vldr d21, [r1, #40] vldr d22, [r1, #48] vldr d23, [r1, #56] add r3, r0, #32 vzip.32 q8, q9 vzip.32 q10, q11 subs r2, r2, #1 vstmia r0, {d16-d19} add r1, r1, #64 vstmia r3, {d20-d23} add r0, r0, #64 bne .L3 bx lr We're missing many auto-increment opportunities here. I think this is due to the limitations of GCC's auto-inc-dec pass rather than to a problem in the ARM port itself. I think there are two main areas for improvement: - The pass only tries to use auto-incs in cases where there is a separate addition and memory access. It doesn't try to handle cases where there are two consecutive memory accesses of the form *base and *(base + size), even if the address costs make it clear that post-increments would be a win. - The pass uses a backward scan rather than a forward scan, which makes it harder to spot chains of more than two accesses. FWIW, I've got fairly specific ideas about how to do this. Unfortunately, the pass is in need of some TLC before it's easy to make changes. So in terms of work items, how about: 1. Clean up the auto-inc pass so that it's easier to modify 2. Investigate improvements to the pass 3. Submit the changes upstream 4. Backport the changes to the Linaro branches I wrote some patches for (1) last week. I'd estimate it's about 2 weeks' work for (1) and (2). (3) and (4) would hopefully be background tasks. The aim would be for something like: .L3: vldmia r1!, {d16-d17} vldmia r1!, {d18-d19} vldmia r1!, {d20-d21} vldmia r1!, {d22-d23} vzip.32 q8, q9 vzip.32 q10, q11 subs r2, r2, #1 vstmia r0!, {d16-d19} vstmia r0!, {d20-d23} bne .L3 bx lr This should help with auto-vectorised code, as well as normal core code. (Combining the vldmias and vstmias is a different topic. The fact that this particular example could be implemented using one load and one store is to some extent coincidental.) Richard

14 years, 12 months

1
0
0 0

[ACTIVITY] 2011-05-13

by David Gilbert

== String routines == * Gave up on perf on silverbell and redid it on ursa2; now have a full set of perf figures and have updated the workload report to show the spec binaries that use significant time in libc and the routines they spend it in; a handful of tests spend very significant amounts of time in libm. * Have ltrace results from about 75% of spec - some of the others are fighting a bit * Optimised the non-neon memcpy; it's now quite respectable except in one or two cases (2 byte misaligned, and for some odd reason source offset by 8 bytes, destination by 12 is way down on any other combination) (Current result graphs here https://wiki.linaro.org/Internal/People/DaveGilbert?action=AttachFile&do=ge… ) Dave

14 years, 12 months

1
0
0 0

[ACTIVITY] May 8-12

by Ira Rosen

Hi, * continued looking into ffmpeg/libavcodec: - dcadsp.c - the inner loop contains reverse accesses which are not supported on Neon. I think we can handle them using vrev and vswp. - a lot of loops have unknown memory stride. I am exploring a possibility of a combination of scalar loads and vmov into a vector register, but it is probably too expensive. * looking into telecom/conven Ira

15 years

1
0
0 0

[ACTIVITY] May.02 -- May.08

by Chung-Lin Tang

== Last week == * Launchpad #748138: "ICE in redirect_jump, at jump.c:1443". Related to shrink-wrap, discussed a bit with Bernd off-list. Sent fix today (Mon.) to gnu-internal; will need to merge to Linaro. * CoreMark combine canonicalize compares patch set: bootstrapped and tested with clean results on powerpc, added comments and updated upstream submission. Machine independent parts okayed by Jeff Law, now committed upstream. ARM parts still pending review. * Compiled back-list of upstream patches, and sent to patches(a)linaro.org * Traveled to Budapest, Hungary for Linaro Developer Summit on Saturday. == This week == * Linaro Developer Summit at Budapest all week.

15 years

1
0
0 0

[ACTIVITY] May 2 - May 6

by Ulrich Weigand

== GDB == * Committed support for NEON registers in core dumps (bug #615972) to Linaro GDB (not yet in mainline). * Investigated root cause of bug #615996 (gdb.cp/templates.exp) and started exploring ways to fix it. == GCC == * Committed fix for bug #759409 (Profiled bootstrap fails in GCC 4.5) to FSF GCC 4.5 branch and Linaro GCC 4.5. 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

15 years

1
0
0 0

[ACTIVITY] 3th - 6th May

by Andrew Stubbs

Worked on the ARM 16 -> 64-bit multiply-and-accumulate problem. Bernd kindly provided a prototype patch to help. I've tried to understand what needs to be done, but I didn't have enough time to get to the bottom of it. So far, I think I know why the existing code doesn't work, and I think I have a way forward. It does appear that the real problem ought to be solved in the tree optimizers, though. Committed the FSF GCC 4.5.3 merge to the Linaro 4.5 branch. Testing did not show any trouble. Matthias requested an additional 4.5 merge to pick up a new bug fix, so I've done the merge, and submitted the merge request for testing. Committed Maxim's compound conditionals optimization patch - a merge from Linaro GCC 4.5. There was some confusion caused by the lp:gcc-linaro/4.6 branch history accidentally getting re-written. After some discussion on #bzr I managed to figure out what happened, posted a warning to linaro-toolchain mailing list, and changed the branch configuration to prevent it happening again. Committed Mark Shinwell's BRANCH_COST patch to Linaro GCC 4.6 - another merge from GCC 4.5. Merged from FSF GCC 4.6 to Linaro 4.6 and submitted the patch for testing. Richard Earnshaw approved my recent Thumb2 constants patch, but only if I modify it slightly. I've begun work on the changes, but I still need to test them. I won't be able to commit them until the ADDW/SUBW patch has been approved. Ramana has reviewed my EABI half-precision function names patch, and discovered that the return types are wrong. I have no idea how this happened - the changes are deliberate so they must have been based on something, but I no longer have the same documents I had when I did the work, and it clearly doesn't match my current ones. In any case, the changes make no practical difference as function return values are always as wide a register anyway. * Other Public holiday on Monday. * Next week I will be attending UDS in Budapest from 8th - 14th May. I shall continue to read my email, but will not be attending any calls. ---- Upstream patched requiring review: * NEON scheduling patch http://gcc.gnu.org/ml/gcc-patches/2011-02/msg01431.html * ARM Thumb2 addw/subw support. http://www.mail-archive.com/gcc-patches@gcc.gnu.org/msg03783.html

15 years

1
0
0 0

[ACTIVITY] 2011-05-06

by David Gilbert

== Bug fighting == * Tracked bug 774175 (apt segfault on armel on oneiric) down to the cortex-a8 branch erratum bug that we found as part of the bug jam a few weeks ago (affecting the more obscure vtk package) - Richard's existing binutils fix should fix this. == String routines == * Struggled to get 'perf' to get sane results from profiling spec; some of the samples are obviously being associated with the wrong process somewhere along the process (e.g. it's showing significant samples in the sh process but in a library that's used by the actual benchmark. * latrace on spec still running on ursa2 * Wrote a non-neon memcpy; as expected it's aligned performance is very similar to libc/kernel - it's a bit faster in some places but slower in some odd places (e.g. n*32+1 bytes is a lot slower for some reason). It's also really bad on mis-aligned cases, I tried to take advantage of the v7's ability to do misaligned loads - but they really are quite slow. Dave

15 years

2
2
0 0

Summit!

by Michael Hope

Hi everyone. Welcome to Budapest. The schedule is at: http://summit.ubuntu.com/uds-o/track/linaro-toolchain/ and should be pretty solid now. The NEON and strings ones may change to a room with a conference line, but we'll see. Thursday and Friday are mostly clear. Be at the hotel by 8:45. The plenary is at 9 am and is followed by a Linaro all-hands at 10. I've tried to reserve the room 'Ady' for general work and meetings but do try to make good use of the summit by having a look at the other sessions listed at: http://summit.ubuntu.com/uds-o/ and the full list of toolchain topics at: https://blueprints.launchpad.net/linaro-toolchain?searchtext=toolchain-o and subscribe to the interesting ones. Note that the schedule will keep changing through the week so keep a good eye on the board. Some that I found interesting are: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-cont… https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-hard… https://blueprints.launchpad.net/ubuntu/+spec/other-o-arm-boot-speed https://blueprints.launchpad.net/ubuntu/+spec/other-o-arm-firefox-startup https://blueprints.launchpad.net/ubuntu/+spec/other-o-arm-port-lightspark https://blueprints.launchpad.net/ubuntu/+spec/linaro-platforms-o-ubuntu-tra… with the full list at: https://blueprints.launchpad.net/~michaelh1/+specs?role=subscriber See you all tomorrow! -- Michael

15 years

1
0
0 0

[ACTIVITY] Weekly status

by Richard Sandiford

== This week == * Committed interleaved load/store vectorisation changes upstream. * Merged the vldN and vstN intrinsic improvements into Linaro 4.5 and 4.6. (Thanks for the quick reviews here.) * Backported the interleaved load/store vectorisation changes to Linaro 4.5 and 4.6. This took a while because the patch series touches turbulent code. Submitted merge requests. * Merged Sergey Grechanik's NEON reload improvement into Linaro 4.5 and 4.6. * Got ready for summit. Richard

15 years

1
0
0 0

[ACTIVITY] weekly status

by Ken Werner

Hi, * finished libunwind support of detection and handling of signal frames on ARM Linux. RT and non-RT signal frames are handled for both >=2.6.18 and <2.6.18 kernels. The *test-resume-sig testcases are passing now. * briefly looked into what needs to be done in order to add 64bit __sync_* ops * prepared for LDS Regards Ken

15 years

1
0
0 0

[ACTIVITY] report week 18

by Peter Maydell

RAG: Red: Amber: Green: GSoC QEMU student project approved Current Milestones: | Planned | Estimate | Actual | qemu-linaro 2011-05 | 2011-05-19 | 2011-05-19 | | Historical Milestones: finish qemu-cont-integration | 2011-01-25 | 2011-01-25 | handed off | first qemu-linaro release | 2011-02-08 | 2011-02-08 | 2011-02-08 | qemu-linaro 2011-03 | 2011-03-08 | 2011-03-08 | 2011-03-08 | qemu-linaro 2011-04 | 2011-04-21 | 2011-04-21 | 2011-04-21 | (short week, following holiday) == merge-correctness-fixes == * some minor patches committed: SPARC build issues, Neon UNDEFs, restore base reg properly for Thumb LDMs that abort midway * v2 of configure patch to print list of valid targets * some work on fixing QEMU FPSCR status flags (last remaining item in this blueprint); submitted a patchset fixing everything except the various VCVT instructions (which have trickier softfloat bugs) * submitted patch fixing NaN behaviour in VMLA/VMLS/VNMLA/VNMLS == other == * the Google Summer of Code QEMU project to work on upstreaming some of the Android emulator has been approved; I will be mentoring Patrick Jackson, who is the student who will be doing this work * qemu-linaro 2011-05 is unlikely to have any code changes since 2011-04; we might release it anyway just because it's the final one of the cycle Current qemu patch status is tracked here: https://wiki.linaro.org/PeterMaydell/QemuPatchStatus Absences: 13-19 May: UDS, Budapest (maybe but unlikely) 15-16 August: QEMU/KVM strand at LinuxCon NA, Vancouver [LinuxCon proper follows on 17-19th]

15 years

1
0
0 0

Fwd: Linaro forums replaced by "Ask Linaro"

by Andrew Stubbs

There's already a couple of tools-related questions on here. We should probably make sure we monitor it regularly. This isn't to hard, once you're signed up, you can mark certain topics as 'interesting' and then you'll get email notifications when there's a post. Andrew -------- Original Message -------- Subject: Linaro forums replaced by "Ask Linaro" Date: Fri, 06 May 2011 15:58:53 +0200 From: Michael Opdenacker <michael.opdenacker(a)linaro.org> Organization: Linaro To: everyone <everyone(a)linaro.org> Greetings, We are pleased to announce the replacement of our forums by a new "Ask Linaro" service. Better than forums, we expect this service to bring more questions and answers, and incite people to join the Linaro community by sharing their experience. We count on your participation. See http://ask.linaro.org/ Cheers, Michael. -- Michael Opdenacker - Community Manager Linaro, http://linaro.org Cell: +33 621 604 642 IRC: 'opm' in #linaro on irc.freenode.net

15 years

1
0
0 0

Pushing to diverged branches

by Andrew Stubbs

Hi all, We seem to have had an accident! This morning I merged one of my patches to lp:gcc-linaro/4.6, and this afternoon I got an email from Launchpad notifying me that a mystery revision had been deleted. It seems that Richard has somehow overwritten my change with his. Luckily I've spotted it and will fix it now, but it could very easily have got lost. I'm not sure what's happened here, but I'm pretty sure bzr does not just do this silently. I thought you needed to specify --overwrite to do this on purpose, but perhaps there's a bzr bug here? Anyway, could everyone please be very careful when they do bzr push to the release branches. Thanks Andrew

15 years

5
14
0 0

[ACTIVITY] May 1-5

by Revital Eres

Hello, [1] Regarding the patch 'Support closing_branch_deps' http://gcc.gnu.org/ml/gcc-patches/2011-03/msg00350.html Continued discussions with Ayal Zaks (SMS maintainer) regrading this patch. (http://gcc.gnu.org/ml/gcc-patches/2011-05/msg00250.html) I'm now working on simplifying the patch for resubmission according the recommendation. [2] Regarding the patch 'Avoid considering debug_insn when calculating SCCs' http://gcc.gnu.org/ml/gcc-patches/2011-04/msg01294.html The problem exposed while testing patch [3] and it seems that is part of a bigger problem -- SMS does not support debug_insn properly. I've asked Alexandre Oliva who inserted the support for debug_insn to haifa sched and selective sched to help with that. [3] Regarding the patch 'Support instructions with REG_INC_NOTE' http://gcc.gnu.org/ml/gcc-patches/2011-04/msg01309.html The fix for debug_insn (which the patch [2] tries to solve) is needed for bootstrapping this patch. So I'm putting it on hold for now. Thanks, Revital

15 years

1
0
0 0

[ACTIVITY] May 1-5

by Ira Rosen

Hi, - backported vzip fix to GCC 4.5 and 4.6 (PR 48252) - merged auto-detection of vector size patch to gcc-linaro 4.6 - started looking into vectorization of ffmpeg Ira

15 years

1
0
0 0

uboot data abort when optimizated with Os under Linaro toolchain 4.5 2011.03/04

by Yuping Luo

Hi, I am trying add usb gadget mass storage to uboot , and got run-time abortion on usbmsd.c with the default u-boot Os option. I use linaro 2011.03 4.5.3 version, and my trials as following: 1) During debugging , I found the abort exception in usbmsd_init_strings(). if declaring it with noinline function, like static void usbmsd_init_strings (void) __attribute__((noinline)); it works, however, next steps still failed. 2) compling uboot with O0, everyhing is ok. 3) try other toolchain. It works with codesourcery's 2011.03-41 and ubuntu 4.5 version, while failed with 2011.04 4.5 linaro version. 4) I have dumped the obj files, seeming some funcs optimized ,analysing the details is out of my knowledge, :( . please check the src and objdump files in one compressed file) toolchain: ypluo@ypluo-dt:~/work/Current/L38EVB/Main/out/prima2cb$ arm-none-linux-gnueabi-gcc --v Using built-in specs. COLLECT_GCC=arm-none-linux-gnueabi-gcc COLLECT_LTO_WRAPPER=/home/ypluo/work/Current/Tools/toolchain/linaro-201103-csr-build-armv7-vfpv3_x86_32/bin/../libexec/gcc/arm-none-linux-gnueabi/4.5.3/lto-wrapper Target: arm-none-linux-gnueabi Configured with: /media/8ccb10fd-862c-47d2-99fb-144e7188e1fb/home/vmuser/development/toolchain/build-toolchain/gcc-linaro-4.5-2011.03-0/configure --target=arm-none-linux-gnueabi --prefix=/media/8ccb10fd-862c-47d2-99fb-144e7188e1fb/home/vmuser/development/toolchain/build-toolchain/tools --enable-languages=c,c++ --with-arch=armv7-a --with-float=softfp --with-fpu=vfpv3-d16 --with-mode=thumb --enable-shared --enable-multiarch --enable-threads=posix --enable-nls --enable-clocale=gnu --enable-libstdcxx-debug --enable-libstdcxx-time=yes --disable-werror --with-pkgversion='Ubuntu/Linaro 4.5-2011.3-csr-build' --enable-poison-system-directories Thread model: posix gcc version 4.5.3 20110221 (prerelease) (Ubuntu/Linaro 4.5-2011.3-csr-build) ypluo@ypluo-dt:~/work/Current/L38EVB/Main/out/prima2cb$ /home/ypluo/mywork/toolchain/arm-2011.03/bin/arm-none-linux-gnueabi-gcc --v Using built-in specs. COLLECT_GCC=/home/ypluo/mywork/toolchain/arm-2011.03/bin/arm-none-linux-gnueabi-gcc COLLECT_LTO_WRAPPER=/mywork/toolchain/arm-2011.03/bin/../libexec/gcc/arm-none-linux-gnueabi/4.5.2/lto-wrapper Target: arm-none-linux-gnueabi Configured with: /scratch/janisjo/arm-linux-lite/src/gcc-4.5-2011.03/configure --build=i686-pc-linux-gnu --host=i686-pc-linux-gnu --target=arm-none-linux-gnueabi --enable-threads --disable-libmudflap --disable-libssp --disable-libstdcxx-pch --enable-extra-sgxxlite-multilibs --with-arch=armv5te --with-gnu-as --with-gnu-ld --with-specs='%{save-temps: -fverbose-asm} %{funwind-tables|fno-unwind-tables|mabi=*|ffreestanding|nostdlib:;:-funwind-tables} -D__CS_SOURCERYGXX_MAJ__=2011 -D__CS_SOURCERYGXX_MIN__=3 -D__CS_SOURCERYGXX_REV__=41 %{O2:%{!fno-remove-local-statics: -fremove-local-statics}} %{O*:%{O|O0|O1|O2|Os:;:%{!fno-remove-local-statics: -fremove-local-statics}}}' --enable-languages=c,c++ --enable-shared --enable-lto --enable-symvers=gnu --enable-__cxa_atexit --with-pkgversion='Sourcery G++ Lite 2011.03-41' --with-bugurl=https://support.codesourcery.com/GNUToolchain/ --disable-nls --prefix=/opt/codesourcery --with-sysroot=/opt/codesourcery/arm-none-linux-gnueabi/libc --with-build-sysroot=/scratch/janisjo/arm-linux-lite/install/arm-none-linux-gnueabi/libc --with-gmp=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-mpfr=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-mpc=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-ppl=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-host-libstdcxx='-static-libgcc -Wl,-Bstatic,-lstdc++,-Bdynamic -lm' --with-cloog=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-libelf=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --disable-libgomp --enable-poison-system-directories --with-build-time-tools=/scratch/janisjo/arm-linux-lite/install/arm-none-linux-gnueabi/bin --with-build-time-tools=/scratch/janisjo/arm-linux-lite/install/arm-none-linux-gnueabi/bin Thread model: posix gcc version 4.5.2 (Sourcery G++ Lite 2011.03-41) Please let me know if other info needed. Many thanks. Yuping

15 years

2
1
0 0

uboot data abort when optimizated with Os under Linaro toolchain 4.5 2011.03/04

by Yuping Luo

Hi, I am trying add usb gadget mass storage to uboot , and got run-time abortion on usbmsd.c with the default u-boot Os option. I use linaro 2011.03 4.5.3 version, and my trials as following: 1) During debugging , I found the abort exception in usbmsd_init_strings(). if declaring it with noinline function, like static void usbmsd_init_strings (void) __attribute__((noinline)); it works, however, next steps still failed. 2) compling uboot with O0, everyhing is ok. 3) try other toolchain. It works with codesourcery's 2011.03-41 and ubuntu 4.5 version, while failed with 2011.04 4.5 linaro version. 4) I have dumped the obj files, seeming some funcs optimized , analysing the details is out of my knowledge, :( . please check the attached three files. toolchain: ypluo@ypluo-dt:~/work/Current/L38EVB/Main/out/prima2cb$ arm-none-linux-gnueabi-gcc --v Using built-in specs. COLLECT_GCC=arm-none-linux-gnueabi-gcc COLLECT_LTO_WRAPPER=/home/ypluo/work/Current/Tools/toolchain/linaro-201103-csr-build-armv7-vfpv3_x86_32/bin/../libexec/gcc/arm-none-linux-gnueabi/4.5.3/lto-wrapper Target: arm-none-linux-gnueabi Configured with: /media/8ccb10fd-862c-47d2-99fb-144e7188e1fb/home/vmuser/development/toolchain/build-toolchain/gcc-linaro-4.5-2011.03-0/configure --target=arm-none-linux-gnueabi --prefix=/media/8ccb10fd-862c-47d2-99fb-144e7188e1fb/home/vmuser/development/toolchain/build-toolchain/tools --enable-languages=c,c++ --with-arch=armv7-a --with-float=softfp --with-fpu=vfpv3-d16 --with-mode=thumb --enable-shared --enable-multiarch --enable-threads=posix --enable-nls --enable-clocale=gnu --enable-libstdcxx-debug --enable-libstdcxx-time=yes --disable-werror --with-pkgversion='Ubuntu/Linaro 4.5-2011.3-csr-build' --enable-poison-system-directories Thread model: posix gcc version 4.5.3 20110221 (prerelease) (Ubuntu/Linaro 4.5-2011.3-csr-build) ypluo@ypluo-dt:~/work/Current/L38EVB/Main/out/prima2cb$ /home/ypluo/mywork/toolchain/arm-2011.03/bin/arm-none-linux-gnueabi-gcc --v Using built-in specs. COLLECT_GCC=/home/ypluo/mywork/toolchain/arm-2011.03/bin/arm-none-linux-gnueabi-gcc COLLECT_LTO_WRAPPER=/mywork/toolchain/arm-2011.03/bin/../libexec/gcc/arm-none-linux-gnueabi/4.5.2/lto-wrapper Target: arm-none-linux-gnueabi Configured with: /scratch/janisjo/arm-linux-lite/src/gcc-4.5-2011.03/configure --build=i686-pc-linux-gnu --host=i686-pc-linux-gnu --target=arm-none-linux-gnueabi --enable-threads --disable-libmudflap --disable-libssp --disable-libstdcxx-pch --enable-extra-sgxxlite-multilibs --with-arch=armv5te --with-gnu-as --with-gnu-ld --with-specs='%{save-temps: -fverbose-asm} %{funwind-tables|fno-unwind-tables|mabi=*|ffreestanding|nostdlib:;:-funwind-tables} -D__CS_SOURCERYGXX_MAJ__=2011 -D__CS_SOURCERYGXX_MIN__=3 -D__CS_SOURCERYGXX_REV__=41 %{O2:%{!fno-remove-local-statics: -fremove-local-statics}} %{O*:%{O|O0|O1|O2|Os:;:%{!fno-remove-local-statics: -fremove-local-statics}}}' --enable-languages=c,c++ --enable-shared --enable-lto --enable-symvers=gnu --enable-__cxa_atexit --with-pkgversion='Sourcery G++ Lite 2011.03-41' --with-bugurl=https://support.codesourcery.com/GNUToolchain/ --disable-nls --prefix=/opt/codesourcery --with-sysroot=/opt/codesourcery/arm-none-linux-gnueabi/libc --with-build-sysroot=/scratch/janisjo/arm-linux-lite/install/arm-none-linux-gnueabi/libc --with-gmp=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-mpfr=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-mpc=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-ppl=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-host-libstdcxx='-static-libgcc -Wl,-Bstatic,-lstdc++,-Bdynamic -lm' --with-cloog=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --with-libelf=/scratch/janisjo/arm-linux-lite/obj/host-libs-2011.03-41-arm-none-linux-gnueabi-i686-pc-linux-gnu/usr --disable-libgomp --enable-poison-system-directories --with-build-time-tools=/scratch/janisjo/arm-linux-lite/install/arm-none-linux-gnueabi/bin --with-build-time-tools=/scratch/janisjo/arm-linux-lite/install/arm-none-linux-gnueabi/bin Thread model: posix gcc version 4.5.2 (Sourcery G++ Lite 2011.03-41) Please let me know if other info needed. Many thanks. Yuping

15 years

2
1
0 0

[ACTIVITY] 26th -28th April

by Andrew Stubbs

My MOVW patch from last week left an unused variable that killed -Werror builds, so I posted a new patch to fix it. http://www.mail-archive.com/gcc-patches@gcc.gnu.org/msg04141.html Ramana approved that in record time, so I've committed it. Tom has committed Mark Shinwell's BRANCH_COST patch upstream, so I have backported it to Linaro GCC 4.6. Maxim has committed his compound conditionals patch upstream, so I've backported that to Linaro GCC 4.6 also. Reviewed what other patches are queued for forward porting to 4.6/7, hoping that other's might have picked some of them off, and found no other progress just yet. Reduced the test case for GCC PR48783. For some reason it is retaining ".global" directives for symbols that have been optimized away, which leads to link errors in the kernel build. Tried to find out why the "discourage neon in A8" patch has caused test failures. I'm still not sure - I've asked Michael Hope to rerun the tests in case it's just random. Reposted the EABI half-precision patch with the extra bits Joseph says it needed in the version scripts. http://www.mail-archive.com/gcc-patches@gcc.gnu.org/msg04251.html Looked at the linking problem reported by Barry Song on the linaro-toolchain list. * Other Public holidays on Monday and Friday. * Future I will be attending UDS in Budapest from 8th - 14th May. I shall continue to read my email, but will not be attending any calls. ---- Upstream patched requiring review: * NEON scheduling patch http://gcc.gnu.org/ml/gcc-patches/2011-02/msg01431.html * ARM Thumb2 addw/subw support. http://www.mail-archive.com/gcc-patches@gcc.gnu.org/msg03783.html * ARM Thumb2 Replicated constants http://www.mail-archive.com/gcc-patches@gcc.gnu.org/msg03883.html * ARM EABI half-precision function names (reposted 2011-04-27). http://www.mail-archive.com/gcc-patches@gcc.gnu.org/msg04251.html

15 years

1
0
0 0

linaro-android track

by Zach Pfeffer

All, I apologize for the broad distribution. Alexander and I have been getting the Android track going. We have the following topics. Most of these have subscribers. Would everyone mind taking a look through this list and subscribing or suggesting people who should be involved? I'll be getting more details into each of these this week. Hosting and Distribution of Linaro Builds https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-buil… This topic will focus on building and distributing Linaro Android builds. Topics will include: binary and source distribution, source and binary overlays (proprietary components and blobs from TI, Samsung, etc), license click-through, build and distribution location or method (host images and/or support on-demand image builds) and release tagging and naming. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-buil… Android Code Review https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-code… This discussion will focus on Android code review. Topics will include Gerrit, continuous integration, maintainers, reviewers and validation. We'll focus on integrating the Android development model with Linaro. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-code… Android Continuous Integration and Building https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-cont… This discussion will focus on Linaro Android continuous integration and builds. Topics include: infrastructure and validation requirements, test subsets for merges and unit testing. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-cont… Android LEB Validation and Test Suite https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-vali… This discussion will focus on LEB validation and test suites. Topics will include: Monkey, CTS, Monkeyrunner, unit-tests, continuous integration merge tests. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-vali… 2011 ELC Follow Up and Planning https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-2011… Linaro had a good meeting at the 2011 Embedded Linux Conference. Many things were discussed. This session will talk about next steps and future planning. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-2011… Android Hardfloat Experiment https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-hard… This session will discuss strategies to find hot-spots that could benefit from hardfloat without breaking overall binary compatibility with market apps. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-hard… Android LEB Documentation https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-leb-… This session will focus on discussing what documentation we need for LEB use and bundled with releases. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-leb-… Linaro Android Toolchain Distribution https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-tool… This session will discuss how to distribute the various components of the Linaro toolchain. We'll discuss NDK and platform distribution, support on Ubuntu, Fedora and Mac, what components do we need to publish and benchmarking toolchain improvements. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-tool… LEB Board Review and Deliverable Requirements https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-leb-… This discussion will talk about defining new member deliverable for Android LEBs, reviewing what's been delivered and assessing if we can raise the bar, discuss other low-cost high-volume board that currently exist or are on the way (Nexus One, Nexus S, Snowball), talk about LEB candidates, discuss cost ceilings (is the Elba board too expensive, for instance). Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-leb-… Open Source Development for Non-Application Cores https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-non-… This session will explore how to open up development for the various DSP and video cores that exist on many SoCs that are running Android to allow open source development of multimedia acceleration. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-non-… Upstream Android Build https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-upst… This topic will discuss which changes we can upstream. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-upst… ADB Shell Improvements https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-adb-… The adb shell lacks many features we take for granted. There is a need for a little more functionality, this session will discuss this. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-adb-… Android Beyond Phones and Advanced Topics https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-beyo… This session will discuss the future of Android. It'll be a brainstorming session to talk about topics like: dual lib (bionic/glibc) support in Android, bringing apt-get into Android, Android as a general computing platform, expanded enterprise networking, expanded packages, traditional Linux application support, security certification and headless Android. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-beyo… JTAG for the World https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-jtag This session will talk about improving tools for Ubuntu hosted JTAG tools, open JTAG script development and available JTAG platforms. Subscribe: https://blueprints.launchpad.net/linaro-android/+spec/linaro-android-o-jtag… -Zach

15 years

1
0
0 0

[ACTIVITY] Apr.25 -- May.01

by Chung-Lin Tang

== Last week == * CoreMark ARMv6/v7 regression patch set for combine: exchanged some comments on upstream list with Jeff Law. Started some testing on powerpc64, hit some issues with native bootstrap that I don't think I completely overcome, but at least completed a 32-bit bootstrap successfully. Unfortunately hit two regressions after running tests, will work on fixing this week, and update the upstream submission. * PR48783: unused reference to __aeabi_uldivmod. Investigated and found this to be a case where during RTL expand, .global directives for the __aeabi_* runtime symbols are directly inserted after some div optab didn't have the insns, and a libfunc was to be used. However later optimizations that removed the divisions left the .global symbols dangling with no uses. We could probably just avoid adding the directives completely for the EABI functions. * PR42017: ARM LR register not used in leaf functions. This is a case where DF takes EPILOGUE_USES as part of the initial live registers at end of functionn, and liveness computations never get to kill it, since there are no function calls to clobber in a leaf function. Submitted a patch to remove LR from EPILOGUE_USES before reload, awaiting review. * LP #689887: investigated more; not much progress, but found that the bootstrap fail happens only under --with-mode=thumb (Thumb-2). Under ARM mode the native bootstrap succeeds. == This week == * Try to fix the problems with the CoreMark combine patches. * Investigate more optimizations/bugs. * Prepare for travel to Budapest on Saturday.

15 years

1
0
0 0

[ACTIVITY] April 26-28

by Revital Eres

Hello, - Continued analysing DENbench benchmarks. - Discussed the SMS patched with Ayal Zaks (SMS maintainer). - Booked the flights for Budapest summit. Thanks, Revital

15 years

1
0
0 0

[ACTIVITY] April 27-28

by Ira Rosen

Hi, gcc-linaro/4.6 - if-conversion improvement (needed to vectorize Telecom/viterbi) - merged - auto-detection of vector size - proposed for merging GCC FSF - fixed PR 48765 on trunk - completed testig of vzip fix (PR 48252) on gcc 4.5 and gcc 4.6 Ira

15 years

1
0
0 0

[ACTIVITY] weekly status

by Ken Werner

Hi, libunwind: * the initial support for resuming at a certain stack frame went upsream * learned about the various signal frame layouts on ARM * RT frames, non-RT frames for present and pre 2.6.18 kernels * implemented support for RT signal frame detection on ARM * started to implement support for unw_resume if signal frames are involved * attended a class on Friday Note: Monday was a public holiday. Regards Ken

15 years

1
0
0 0

[ACTIVITY] Apr 26 - Apr 29

by Ulrich Weigand

== GDB == * Committed series of patches to fix bug #615978 (Failure to software single-step into signal handler) to mainline and Linaro GDB. * Drafted blueprint linaro-toolchain-o-cross-debug == GCC == * Split bug #771900 (Linaro GCC 4.5 switch optimization breaks profiled bootstrap) off bug #759409 (Profiled bootstrap fails in GCC 4.5). Tracked down root cause of bug #759409 / PR middle-end/43085, and posted fix to gcc-patches. 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

15 years

1
0
0 0

Toolchain summit blueprints

by Michael Hope

Hi there. The toolchain session blueprints for the summit are now up on Launchpad: https://blueprints.launchpad.net/linaro-toolchain?searchtext=toolchain-o You can check out the schedule here: http://summit.ubuntu.com/uds-o/track/linaro-toolchain/ although it's really only for show at the moment. Expect things to jump around as the constraints kick in. Please go through these blueprints and subscribe yourself to them. You can check your list of blueprints at: https://blueprints.launchpad.net/people/+me?searchtext=toolchain-o -- Michael

15 years

1
0
0 0

2026

2025

2024

2023

2022

2021

2020

2019

2018

2017

2016

2015

2014

2013

2012

2011

2010

linaro-toolchain