- linaro-toolchain - lists.linaro.org

by Yao Qi

# Progress # * TCWG-162, Aarch64 non-stop debugging (or displaced stepping). [4/10] After testing, patches are posted upstream. * In order to review one c++ debugging patch, learn some C++ abi, vtable and VTT, etc. Understand gcc dump by -fdump-class-hierarchy. [3/10] * Fix GDB cxx build breakage caused by my patch. [1/10] * Ask the effect of -fstack-check=specific to AArch64 prologue. GDB needs update. [1/10] * Misc, email, meeting. [1/10]. # Plan # * TCWG-162, commit patches if no objections. * TCWG-387, use libopcodes to decode instructions in GDB. -- Yao

10 years

1
0
0 0

ILP32 is a parity feature to x86_64 (x32)

by Pinski, Andrew

10 years

2
1
0 0

Fw: [Bug target/67877] New: Split stack needs to be support for AARCH64

by Pinski, Andrew

FYI. This is a parity feature with both PowerPC64 and x86_64. Needed to support GCCgo. Note full gold support is needed too. ---------- Forwarded message ---------- From: pinskia at gcc dot gnu.org <gcc-bugzilla(a)gcc.gnu.org> Date: Tue, Oct 6, 2015 at 3:30 PM Subject: [Bug target/67877] New: Split stack needs to be support for AARCH64 To: gcc-bugs(a)gcc.gnu.org https://gcc.gnu.org/bugzilla/show_bug.cgi?id=67877 Bug ID: 67877 Summary: Split stack needs to be support for AARCH64 Product: gcc Version: 6.0 Status: UNCONFIRMED Severity: normal Priority: P3 Component: target Assignee: unassigned at gcc dot gnu.org Reporter: pinskia at gcc dot gnu.org Target Milestone: --- Target: aarch64-linux-gnu* To support gccgo better split stack should be implemented.

10 years, 1 month

1
0
0 0

[ACTIVITY] 28th August - 2nd October

by Bernie Ogden

Connect recovery - [2/10] Investigate effectiveness of noise-control measures - TCWG-358 [3/10] * Host node crashed, tried to recover it, failed, started building a new one Jenkins automation - TCWG-348 [3/10] * Everything in place up to first interaction with LAVA kvm * Considered LAVA team's micro-instance proposal Misc [2/10] =Plan= Discuss micro-instance proposal Work on whatever comes out of discussion Finish building new host node, get experiments running again

10 years, 1 month

1
0
0 0

[ACTIVITY] 14th - 18th September

by Bernie Ogden

Investigate effectiveness of noise-control measures - TCWG-358 [6/10] * Finished setup, started running experiments * Initial data pretty noisy, more runs needed * Kicked off more runs for week of Connect Ensure that all critical data is logged - TCWG-349 [1/10] * Logged a few more variables, tested, merged * Put down until we have a controlled image build Misc - [3/10]

10 years, 1 month

1
0
0 0

[ACTIVITY] Week 40

by Yvan Roux

* 2 post-connect days off (4/10) == Progress == o Linaro GCC (3/10) * Backporting armv8-1 support * Dealing with conflicts o Misc (3/10) * Various meetings * Internal report on Connect == Plan == o Backports o Releases process tasks

10 years, 1 month

1
0
0 0

[Weekly] 28 SEPTEMBER - 2 October 2015

by Michael Collison

== This week == * TCWG-317 - Exploit wide add operations when appropriate for Aarch32 (4/10) - Patch sent upstream for review - Fixed some failing tree-ssa testcases by modifying 'check_effective_target_vect_widen_sum_hi_to_si_pattern' to indicate Aarch32 supports vector widening add - Fixed length attributes on patterns in neon.md - Added test cases to ChangeLog - Debugging failures on -flto and arm big endian * TCWG-369 - Exploit wide add operations when appropriate for Aarch64 (3/10) - Fixed some failing tree-ssa testcases by modifying 'check_effective_target_vect_widen_sum_hi_to_si_pattern' to indicate Aarch64 supports vector widening add - Debugging tree-ssa test suite failures * Bugzilla 57195 (mode iterator bug) blocked compiling new pattern (1/10) - Patch checked in upstream on trunk * TCWG-77 - Transform end of loop conditions to min_expr (2/10) - Submitted upstream waiting for final approval - Merged multiple patterns into one pattern in match.md - Rewrote test case to work on all targets * Misc (1/10) - Conference calls == Next week == - Holiday/vacation

10 years, 1 month

1
0
0 0

[ACTIVITY] 28 September-2 October 2015

by Kugan

== Progress == - 1 day off recovering from travel and 1 public holiday (4/10) - https://gcc.gnu.org/ml/gcc-patches/2015-07/msg02196.html (1/10) * Approved patch * re-based and retesting before committing - https://gcc.gnu.org/ml/gcc-patches/2015-10/msg00129.html (1/10) * Found a latent issue while testing patches * posted a patch for review - Widening pass (TCWG-547) - 4/10 * Working on review comments == Plan == * Monday public holiday * Post the revised patch for widening pass * commit approved patches

10 years, 1 month

1
0
0 0

[ACTIVITY]

by Renato Golin

== Progress == * Monday off (2/10) * Buildbot (6/10) - Investigating sanitizer crash in Thumb2+NEON - Testing IFC6410 with Linaro 15.09 - CPUs good, 1.7GHz on all cores, stable, cool - Not enough space on local (fast) flash - USB stick stable, but slow (3h vs 2h on Chrome 2) - USB disk unstable and slow (power management, etc) - SATA broken, and slow * Infrastructure (1/10) - Discussing LAVA instance in TCWG lab, benchmarks - Playing with D02: corrupted system, but the machine is *fast* * Background (1/10) - Code review, meetings, discussions, general support, etc. == Plan == * More infrastructure meetings * More buildbot work * Whatever...

10 years, 1 month

1
0
0 0

[ACTIVITY] 28 September-2 October 2015

by Yao Qi

# Progress # * TCWG-373, Aarch64 non-stop debugging (or displaced stepping). [2/10] Patches V1 are ready for upstream submission, but find opcodes has already interfaces to decode instructions, so decide to use opcodes for aarch64 GDB first. * TCWG-387, one patch exposing one opcode interface is pushed in. [4/10] Switch software single step code for aarch64 to using opcodes interface. Patch is pushed in. Rewriting prologue analyser to use opcode interface too. * TCWG-159, Kernel awareness in GDB. [1/10] Resume the work as Peter Griffin has cycles to do so. We are happy with the plan so far. * Review arm software breakpoint in GDBserver patches. [1/10] * Misc, [2/10] # Plan # * TCWG-387, TCWG-373 -- Yao

10 years, 1 month

1
0
0 0

[ACTIVITY] 28 September-2 October 2015

by Christophe Lyon

== Progress == 2 days off (4/10) * Infrastructure/validation: (3/10) further checking of cross-testing results stability on aarch64-linux - found a workaround for a timestamp problem (_Pragma3 testcase) - looked at c11-atomic-exec-5 whose execution time ranges between 1s and 1h :-) - forcing make check to -j8 seems to work well, will work on a nicer improvement * reported and briefly looked at failure in a new libstdc++ test (directory_iterator) on armv5t * Misc (conf calls, meetings, emails, ....) (2/10) * Internal (1/10) - GNU linker patch review

10 years, 1 month

2
2
0 0

[ANNOUNCE] Linaro Binary Toolchain Release-Candidate GCC 5.1 2015.08-rc2

by Ryan Arnold

The Linaro Toolchain Working Group is pleased to announce the availability of the Linaro Stable Binary Toolchain Release-Candidate GCC 5.1-2015.08-rc2 Archives. http://snapshots.linaro.org/components/toolchain/binaries/5.1-2015.08-rc2/ These archives provide cross-toolchain executables (compiler, debugger, linker, etc.) and shared libraries (libstdc++, libc, etc.) that target ARM or Aarch64 GNU/Linux and bare-metal environments. The cross-toolchain binaries execute on a Linux or MS Windows (under mingw32) host operating-system. Please evaluate this release-candidate for correctness. Linaro will shortly spin the Linaro GCC 5.1-2015.08 release if this release-candidate passes stakeholder validation. For bugs related to this release-candidate please email linaro-toolchain(a)lists.linaro.org or file a bug at http:// https://bugs.linaro.org/enter_bug.cgi?product=Linux%20Binary%20toolchain NEWS * 2015.08-rc2 * The Linaro 2015.08-rc2 release-candidate binary toolchain is based on the Linaro GCC-5.1-2015.08-rc1 release-candidate source archive. The only changes between 2015.08-rc1 and 2015.08-rc2 were the following changes in how the binary toolchains were built. The compiler itself was not changed. * x86_64 hosted, armv8l-linux-gnueabihf targetted cross toolchains are now correctly configured. This was broken in 2015.08-rc1. The cross-compiler targetting armv8l-linux-gnueabihf is now correctly configured with --with-arch=armv8-a --with-fpu=neon-fp-armv8 --with-float=hard --disable-multilib --enable-multiarch. * Glibc’s slibdir and libdir were once again modified to address Linaro Bugzilla 1717 – Linaro-4.9-2015.05 moved system libs from /libc/lib/ to /libc/usr/lib/ which breaks things. The following are now the correct locations: libdir=lib/ (linker-scripts and static archives) slibdir=usr/lib/ (shared objects) rtlddir=lib/ (dynamic linker) * 2015.08-rc1 * x86_64 hosted, armv8l-linux-gnueabihf targetted cross toolchain now provided. Delivering on REQ-477 – Enable x86_64 to Aarch32 (32-bit ARMv8-A) cross binary toolchain product release and CARD-1637 – Enable Aarch32 (32-bit ARMv8-A) cross binary toolchain product releases , armv8l-linux-gnueabihf targetted toolchains are now available as part of this release-candidate. * Python support in GDB for both Linux and Mingw32 (32-bit windows). Delivered as requested in the linaro-toolchain mailing list post title – windows binary builds with gdb-python enabled?. * Added missing expat support to GDB. This addresses the following linaro-toolchain mailing list post – "Missing expat support in GDB 7.8 multi-lib enablement for arm bare-metal targets." * A fix for multilib enablement in baremetal toolchains (as described in ABE Review 6862). * Library Paths are now congruent with older Linaro Toolchain path layouts. This addresses Linaro Bugzilla 1717 – Linaro-4.9-2015.05 moved system libs from /libc/lib/ to /libc/usr/lib/ which breaks things. libdir=lib/ (shared objects) slibdir=usr/lib/ (static libraries) rtlddir=lib/ (dynamic linker)

10 years, 1 month

1
0
0 0

[ACTIVITY]

by Renato Golin

== Progress == * Buildbot (2/10) - Investigating sanitizer crash in AArch64 - Found: 247264, reverted 247674 - Other sanitizer crashes * Maintenance (4/10) - More VMA investigations, discussions - More TargetTuple discussions - Investigating BLX bug on ARMv4 (PR24858) * Background (4/10) - Code review, meetings, discussions, general support, etc. - Connect stuff, orchestrating meetings next week == Progress 2 == Connect == Plan == * Look into new kernel for dragon boards * Look into libraries bot, try to upstream it * Continue VMA discussions, prototype

10 years, 1 month

1
0
0 0

[ACTIVITY] 21th-25th September

by Yao Qi

# Progress # * TCWG-189, Aarch64 fast tracepoint. [2/10] Done. Patches are committed. * TCWG-373, Support displaced stepping on aarch64-linux. [4/10] GDB works basically, still need to refactor and polish the code. * TCWG-374, Test displaced stepping on aarch64-linux. [1/10] Add new tests. * TCWG-166, gdbserver support for tracepoints on ARM. [3/10]. Review patches, play with patches, and investigate on some issues. Ongoing. # Plan # * TCWG-373, TCWG-374, and TCWG-166. -- Yao

10 years, 1 month

1
0
0 0

problems with gdb in 4.9-2014.09_linux 32-bit

by Sergio R. Caprile

Hello, I'm starting work on an ARM Cortex-A5 platform. I've setup a cross-build environment on Centos 6, my toolchain is gcc-linaro-arm-linux-gnueabihf-4.9-2014.09_linux since my build system is 32-bits (I don't have 64-bit hardware/OS available). I've written a simple hello_world and managed to compile on my build environment and execute in the target system. However, I can't debug the application. #include <stdio.h> int main(int argc, char **argv) { printf("Hello world! (hola mundo) [v2]\n"); return 0; } [toradex@EL-Toradex Hello_world]$ ~/gcc-linaro/bin/arm-linux-gnueabihf-gcc -g -o Hello_world main.c I've already confirmed that the program to debug runs OK, I've connected via SSH and run it, it just prints a hello message as expected. When I try to debug, I get a SIGSEGV and then the following reports: If I use the provided gdbinit in gcc-linaro/share/gdb/gdbinit, I get the following error: ---------------------------------------------------------------------- /home/toradex/gcc-linaro/share/gdb/gdbinit:6: Error in sourced command file: Python scripting is not supported in this copy of GDB. ---------------------------------------------------------------------- If I don't, then gdb complains it can't locate source files: ---------------------------------------------------------------------- Can't find a source file at "/cbuild/slaves/oorts/crosstool-ng/builds/arm-linux-gnueabihf-linux/.build/src/eglibc-linaro-2.19-2014.08/elf/dl-fini.c" Locate the file or edit the source lookup path to include its location. ---------------------------------------------------------------------- The SIGSEGV occurs before main(), I can't do anything on startup: ---------------------------------------------------------------------- TARGET: ------ root@colibri-vf:~# gdbserver :2345 /home/root/Hello_world BUILD: ----- [toradex@EL-Toradex ~]$ gcc-linaro/bin/arm-linux-gnueabihf-gdb workspace/Hello_world/Debug/Hello_world GNU gdb (crosstool-NG linaro-1.13.1-4.9-2014.09 - Linaro GCC 4.9-2014.09) 7.6.1-2013.10 Copyright (C) 2013 Free Software Foundation, Inc. License GPLv3+: GNU GPL version 3 or later <http://gnu.org/licenses/gpl.html> This is free software: you are free to change and redistribute it. There is NO WARRANTY, to the extent permitted by law. Type "show copying" and "show warranty" for details. This GDB was configured as "--host=i686-build_pc-linux-gnu --target=arm-linux-gnueabihf". For bug reporting instructions, please see: <https://bugs.launchpad.net/gcc-linaro>... Reading symbols from /media/sf_EL-Toradex/Hello_world/Debug/Hello_world...done. (gdb) target remote 192.168.1.6:2345 Remote debugging using 192.168.1.6:2345 Reading symbols from /home/toradex/gcc-linaro-arm-linux-gnueabihf-4.9-2014.09_linux/arm-linux-gnueabihf/libc/lib/ld-linux-armhf.so.3...done. Loaded symbols for /home/toradex/gcc-linaro-arm-linux-gnueabihf-4.9-2014.09_linux/arm-linux-gnueabihf/libc/lib/ld-linux-armhf.so.3 process_dl_debug (dl_debug=0x0, dl_debug@entry=<error reading variable: Cannot access memory at address 0x34>) at rtld.c:2415 2415 rtld.c: No such file or directory. (gdb) continue Continuing. Program received signal SIGSEGV, Segmentation fault. 0x76fe36f8 in _dl_sort_fini (maps=0x7efff98c, nmaps=0, used=0x0, ns=<optimized out>) at dl-fini.c:70 70 dl-fini.c: No such file or directory. (gdb) ---------------------------------------------------------------------- I do need some help here. Following is what I know how to get out of /proc/mypid/ Thanks. ---------------------------------------------------------------------- AT "ERROR READING VARIABLE" root@colibri-vf:~# cat /proc/438/maps 00010000-00011000 r-xp 00000000 00:0d 15533 /home/root/Hello_world 00020000-00021000 rw-p 00000000 00:0d 15533 /home/root/Hello_world 76fd8000-76ff7000 r-xp 00000000 00:0d 15010 /lib/ld-2.19-2014.04.so 76ffd000-76ffe000 r-xp 00000000 00:00 0 [sigpage] 76ffe000-77000000 rw-p 0001e000 00:0d 15010 /lib/ld-2.19-2014.04.so 7efdf000-7f000000 rw-p 00000000 00:00 0 [stack] ffff0000-ffff1000 r-xp 00000000 00:00 0 [vectors] root@colibri-vf:~# cat /proc/438/stack [<8002b2c4>] ptrace_stop+0x11c/0x214 [<8002c3b8>] get_signal+0x2c8/0x534 [<80011088>] do_signal+0x1a0/0x3ec [<80011468>] do_work_pending+0x90/0xd0 [<8000e5e0>] work_pending+0xc/0x20 [<ffffffff>] 0xffffffff root@colibri-vf:~# cat /proc/438/stat 438 (Hello_world) t 435 438 412 34816 438 1073741824 33 0 0 0 0 0 0 0 20 0 1 0 171447 286720 20 4294967295 65536 66668 2130705728 2130705728 1996328256 0 0 268435456 0 2147660484 0 0 17 0 0 0 0 0 0 132204 132488 135168 2130705997 2130706020 2130706020 2130706405 0 root@colibri-vf:~# cat /proc/438/status Name: Hello_world State: t (tracing stop) Tgid: 438 Ngid: 0 Pid: 438 PPid: 435 TracerPid: 435 Uid: 0 0 0 0 Gid: 0 0 0 0 FDSize: 32 Groups: 0 VmPeak: 304 kB VmSize: 280 kB VmLck: 0 kB VmPin: 0 kB VmHWM: 80 kB VmRSS: 80 kB VmData: 4 kB VmStk: 136 kB VmExe: 4 kB VmLib: 124 kB VmPTE: 6 kB VmSwap: 0 kB Threads: 1 SigQ: 0/819 SigPnd: 0000000000000000 ShdPnd: 0000000000000000 SigBlk: 0000000000000000 SigIgn: 0000000010000000 SigCgt: 0000000000000000 CapInh: 0000000000000000 CapPrm: 0000003fffffffff CapEff: 0000003fffffffff CapBnd: 0000003fffffffff Cpus_allowed: 1 Cpus_allowed_list: 0 voluntary_ctxt_switches: 1 nonvoluntary_ctxt_switches: 0 root@colibri-vf:~# cat /proc/438/syscall 0 0x0 0x0 0x0 0x0 0x0 0x0 0x7efffd40 0x76fd8d40 root@colibri-vf:~# AFTER "CONTINUE", WHEN "SIGSEGV" -------------------------------- root@colibri-vf:~# cat /proc/438/maps 00010000-00011000 r-xp 00000000 00:0d 15533 /home/root/Hello_world 00020000-00021000 rw-p 00000000 00:0d 15533 /home/root/Hello_world 76ea1000-76fca000 r-xp 00000000 00:0d 15031 /lib/libc-2.19-2014.04.so 76fca000-76fd2000 ---p 00129000 00:0d 15031 /lib/libc-2.19-2014.04.so 76fd2000-76fd5000 rw-p 00129000 00:0d 15031 /lib/libc-2.19-2014.04.so 76fd5000-76fd8000 rw-p 00000000 00:00 0 76fd8000-76ff7000 r-xp 00000000 00:0d 15010 /lib/ld-2.19-2014.04.so 76ff7000-76ff8000 rw-p 00000000 00:00 0 76ff8000-76ffc000 r--p 00000000 00:0d 14058 /etc/ld.so.cache 76ffc000-76ffd000 rw-p 00000000 00:00 0 76ffd000-76ffe000 r-xp 00000000 00:00 0 [sigpage] 76ffe000-77000000 rw-p 0001e000 00:0d 15010 /lib/ld-2.19-2014.04.so 7efdf000-7f000000 rw-p 00000000 00:00 0 ffff0000-ffff1000 r-xp 00000000 00:00 0 [vectors] root@colibri-vf:~# cat /proc/438/stack [<8002b2c4>] ptrace_stop+0x11c/0x214 [<8002c3b8>] get_signal+0x2c8/0x534 [<80011088>] do_signal+0x1a0/0x3ec [<80011468>] do_work_pending+0x90/0xd0 [<8000e5e0>] work_pending+0xc/0x20 [<ffffffff>] 0xffffffff root@colibri-vf:~# cat /proc/438/stat 438 (Hello_world) t 435 438 412 34816 438 1073741824 49 0 0 0 0 0 0 0 20 0 1 0 171447 1585152 74 4294967295 65536 66668 2130705728 0 1996371704 0 0 268435456 0 2147660484 0 0 17 0 0 0 0 0 0 132204 132488 135168 2130705997 2130706020 2130706020 2130706405 0 root@colibri-vf:~# cat /proc/438/status Name: Hello_world State: t (tracing stop) Tgid: 438 Ngid: 0 Pid: 438 PPid: 435 TracerPid: 435 Uid: 0 0 0 0 Gid: 0 0 0 0 FDSize: 32 Groups: 0 VmPeak: 1548 kB VmSize: 1548 kB VmLck: 0 kB VmPin: 0 kB VmHWM: 296 kB VmRSS: 296 kB VmData: 24 kB VmStk: 136 kB VmExe: 4 kB VmLib: 1312 kB VmPTE: 6 kB VmSwap: 0 kB Threads: 1 SigQ: 0/819 SigPnd: 0000000000000000 ShdPnd: 0000000000000000 SigBlk: 0000000000000000 SigIgn: 0000000010000000 SigCgt: 0000000000000000 CapInh: 0000000000000000 CapPrm: 0000003fffffffff CapEff: 0000003fffffffff CapBnd: 0000003fffffffff Cpus_allowed: 1 Cpus_allowed_list: 0 voluntary_ctxt_switches: 2 nonvoluntary_ctxt_switches: 1 root@colibri-vf:~# cat /proc/438/syscall 0 0xffffffff 0x1934 0x76ffed90 0x76ea1000 0x0 0x0 0x0 0x76fe36f8 root@colibri-vf:~# --

10 years, 1 month

2
3
0 0

[ACTIVITY] 14th-18th September

by Yao Qi

# Progress # * TCWG-188, aarch64 GDB multi-arch support. [2/10] All patches went upstream except that one is blocked by kernel patch. The work is done! * TCWG-189, aarch64 fast tracepoint support. [2/10] Update them and post V2 out. Pending for review. * TCWG-373, Aarch64 non-stop debugging (or displaced stepping). [2/10] Think about it, and break it into pieces. Refactor fast tracepoint code so that some can be reused for displaced stepping. * TCWG-375, Don't skip gdb.asm/asm-source.exp on aarch64. [1/10] Patch is pushed in. * TCWG-166, Review arm tracepoint patches from Ericsson upstream. [1/10] May have something wrong for permanent breakpoint on thumb code. Need to figure out a case to trigger that. * Misc, meeting and training. [2/10] # Plan # * TCWG-189, TCWG-373, TCWG-166. -- Yao

10 years, 1 month

1
0
0 0

[ANNOUNCE] Linaro GCC 5 2015.09 snapshot

by Yvan Roux

The Linaro Toolchain Working Group (TCWG) is pleased to announce the 2015.09 snapshot of the Linaro GCC 5 source package. This monthly snapshot[1] is based on FSF GCC 5.2+svn227732 and includes performance improvements and bug fixes backported from mainline GCC. This snapshot contents will be part of the 2015.11 stable [1] quarterly release. This snapshot tarball is available on: http://snapshots.linaro.org/components/toolchain/gcc-linaro/ Interesting changes in this GCC source package snapshot include: * Updates to GCC 5.2+svn227732 * Backport of [Bugfix] [AArch32] PR target/26702 * Backport of [Bugfix] [AArch32] PR target/26702 * Backport of [Bugfix] [AArch32] PR rtl-optimization/34503 * Backport of [Bugfix] [AArch32] PR target/64208 iwmmxt pattern * Backport of [Bugfix] [AArch32] PR target/65924 * Backport of [Bugfix] [AArch64] PR 65770 vstN_lane on bigendian * Backport of [Bugfix] [AArch64] PR 65375 Fix RTX cost for vector SET * Backport of [Bugfix] [AArch64] PR target/65491: Classify V1TF vectors as AAPCS64 short vectors rather than composite types * Backport of [Bugfix] [AArch64] PR target/66049 * Backport of [Bugfix] [AArch64] PR 63949 * Backport of [Bugfix] PR rtl-optimization/64616 Move insns without introducing new temporaries in loop2_invariant * Backport of [Bugfix] PR rtl-optimization/66076 * Backport of [Bugfix] PR tree-optimization/65447 * Backport of [AArch32] Add cpu_defines.h for ARM * Backport of [AArch32] Additional bics patterns * Backport of [AArch32] Add support for CFI directives in fp emulation routines for ARM * Backport of [AArch32] Add support for crtfastmath * Backport of [AArch32] Apply arm.h change for previous commit * Backport of [AArch32] (*arm_subsi3_insn): Fixed redundant alternatives * Backport of [AArch32] Fix up bootstrap and fix typo in related changelog entry * Backport of [AArch32] Handle UNSPEC_VOLATILE in rtx costs and don't recurse inside the unspec * Backport of [AArch32] insns attributes and alternative cleanups * Backport of [AArch32] Make tune params tables more self-documenting * Backport of [AArch32] Remove vec_shr and vec_shr optabs * Backport of [AArch32] Use uppercase for code iterator names * Backport of [AArch64] Add alternative 'extr' pattern, calculate rtx cost properly * Backport of [AArch64] Add branch-cost to cpu tuning information * Backport of [AArch64] Add __extension__ and __always_inline__ to crypto intrinsics * Backport of [AArch64] Add vcond(u?)didi pattern * Backport of [AArch64] Fix aarch64_rtx_costs of PLUS/MINUS * Backport of [AArch64] Fix Cortex-A53 shift costs * Backport of [AArch64] Fix geniterators.sh to use standard BRE syntax in sed * Backport of [AArch64] Fix up new line in previous commit * Backport of [AArch64] Handle FLOAT and UNSIGNED_FLOAT in rtx costs * Backport of [AArch64] Idiomatic 64x1 comparisons in arm_neon.h * Backport of [AArch64] Implement -m{cpu,tune,arch}=native using only /proc/cpuinfo * Backport of [AArch64] In aarch64_class_max_nregs use UNITS_PER_VREG and UNITS_PER_WORD * Backport of [AArch64] Make aarch64_min_divisions_for_recip_mul configurable * Backport of [AArch64] Properly cost FABD pattern * Backport of [AArch64] Properly cost MNEG/[SU]MNEGL patterns * Backport of [AArch64] Properly handle mvn-register and add EON+shift pattern and cost appropriately * Backport of [AArch64] Properly handle SHIFT ops and EXTEND in aarch64_rtx_mult_cost * Backport of [AArch64] Remember to cost operand 0 in FP compare-with-0.0 case * Backport of [AArch64] Use extend_arith rtx cost appropriately * Backport of [AArch64] Use mov for add with large immediate * Backport of [AArch64] Fix a couple of bugs regarding loop invariant motion discovered by spec2k6 on aarch64 * Backport of [Musl libc] Add musl support to GCC * Backport of [Musl libc] libitm fixes for musl support * Backport of [Musl libc] musl libc config * Backport of [Musl libc] mips musl support * Backport of [Musl libc] unwind fix for musl * Backport of [Musl libc] libstdc++, libgfortran gthr workaround for musl * Backport of [Musl libc] fixincludes update for musl support * Backport of [Musl libc] [AArch32] [4/13] arm musl support * Backport of [Musl libc] [AArch64] [3/13] aarch64 musl support * Backport of [Testsuite] [AArch32] advsimd-intrinsics.exp: dg-do-what=compile if HW does not have Neon * Backport of [Testsuite] [AArch32] Fix test for pr64616 * Backport of [Testsuite] [AArch32] Require Thumb2 effective target * Backport of [Testsuite] [AArch32] Fix r222371 (PR target/26702) * Backport of [Testsuite] Cleanup advsimd-intrinsics.exp, removing unnecessary loop * Backport of [Testsuite] don't clobber dg-do-what-default in advsimd-intrinsics.exp * Backport of [Testsuite] don't try to execute simd.exp tests on targets without NEON * Backport of [Testsuite] move check-gcc parallelize value into C front end * Backport of [Testsuite] new vqmovn test * Backport of [Testsuite] new vqmovun test * Backport of [Testsuite] new vqrdmulh_lane test * Backport of [Testsuite] new vqrdmulh_n test * Backport of [Testsuite] new vqrdmulh test * Backport of [Testsuite] new vqrshl test * Backport of [Testsuite] new vqrshn_n test * Backport of [Testsuite] new vqrshun_n test * Backport of [Testsuite] new vqshl_n test * Backport of [Testsuite] new vqshl test * Backport of [Testsuite] new vqshlu_n test * Backport of [Testsuite] new vqshrn_n test * Backport of [Testsuite] new vqshrun_n test * Backport of [Testsuite] Reinstate torture-init and torture-finalize in advsimd-intrinsics.exp * Backport of [Misc] Try REG_EQUAL for nonzero_bits * Backport of [Misc] Don't reset ssa_name infor in struct iv * Backport of [Misc] make clean' fix * Backport of [Misc] Make vector_compare_rtx cope with VOID mode constants * Backport of [Misc] set_nonzero_bits_and_sign_copies/combine.c * Backport of [Misc] Expand pow (x, CONST) using square roots when possible * Backport of [Doc] [AArch32] (ARM Options, mtune): add missing entries * Backport of [Doc] Add missing jit and lto info..... * Backport of [Doc] Declaring Attributes of Functions/split by target * Backport of [Doc] reorganize (Type Attributes) and (Variable Attributes) * Backport of [Doc] Update __atomic builtins documentation * Backport of [Doc] Update definition location of attribute_spec in documentation Feedback and Support Subscribe to the important Linaro mailing lists and join our IRC channels to stay on top of Linaro development. ** Linaro Toolchain Development "mailing list":http://lists.linaro.org/mailman/listinfo/linaro-toolchain ** Linaro Toolchain IRC channel on irc.freenode.net at @#linaro-tcwg@ * Bug reports should be filed in bugzilla against GCC product:http://bugs.linaro.org/enter_bug.cgi?product=GCC * Interested in commercial support? inquire at "Linaro support":mailto:support@linaro.org [1]. Stable source package releases are defined as releases where the full Linaro Toolchain validation plan is executed. [2]. Source package snapshots are defined when the compiler is only put through unit-testing and full validation is not performed.

10 years, 1 month

1
0
0 0

[ACTIVITY] 7th-11th September

by Bernie Ogden

Ensure all critical (benchmarking) data is logged - TCWG-349 [1/10] * Added logging of several factors * Documented what we do and don't log Noise control experiments on Juno - TCWG-349 [4/10] * Rediscovered that my Juno is an r0, not an r1 * Rebuilt target image in a carefully scripted way * Fiddled about with differences between local and LAVA targets * Ran a couple of trials to test infrastructure Connect preparation - [2/10] * General sorting out of tickets et al * Final pass through benchmarking presentation Misc - [3/10] =Plan= Merge 'logging' branch Final pass through logging documentation Run some noise experiments on Juno If time, work on Jenkins benchmarking jobs

10 years, 1 month

1
0
0 0

[ACTIVITY] 7 - 11 September 2015

by Omair Javaid

== Progress == LLDB development -- Progress to add support for un-alinged watchpoints on AArch64 [TCWG-367] [5/10] -- Truncating watched bits wasnt accepted as a solution, will look into issues during connect. -- Trying to figure out a way to use multiple watchpoint slots for a single watchpoint. Miscellaneous [1/10] -- Meetings, emails, discussions etc. -- Travel preparations Holiday 10 - 11 September 2015 - Travelling to US == Plan == Holiday 14 - 18 September 2015 Connect 21 - 25 September 2015 Holiday 28 September - 5th October 2015

10 years, 1 month

1
0
0 0

Building for armv6/ARM1136J-S using ABE

by Bill Davis

Hi, I've tried probably a dozen different ABE build command lines with various combinations of cpu/arch/tune on the latest tree and on the 2014.09 release and am unable to build for the armv6/1136J-S. Before bothering the list, I scoured the gzipped archive back through 2013, and there is little mention of any problems OR successes with armv6. I am wondering if armv6 is supported, and if so, what is the secret sauce ABE command line to build successfully for the 1136J-S. Some of the builds I tried were missing tarball components, others fail later on such as the one below that gets through building gcc and bombs building the eabi. -------------------- 'abe.sh -target arm-linux-gnueabi -build all -set cpu=arm1136j-s' produces the following, see further below for the gcc version data: arm-linux-gnueabi-gcc ../sysdeps/arm/aeabi_memclr.c -c -std=gnu99 -fgnu89-inline -O2 -Wall -Werror -Winline -Wno-error=undef -Wundef -Wwrite-strings -fmerge-all-constants -frounding-math -g -Wstrict-prototypes -I../include -I/home/billd/_build/builds/x86_64-unknown-linux-gnu/arm-linux-gnueabi/glibc.git~release-2.21-master/csu -I/home/billd/_build/builds/x86_64-unknown-linux-gnu/arm-linux-gnueabi/glibc.git~release-2.21-master -I../sysdeps/unix/sysv/linux/arm -I../sysdeps/arm/nptl -I../sysdeps/unix/sysv/linux/include -I../sysdeps/unix/sysv/linux -I../sysdeps/nptl -I../sysdeps/pthread -I../sysdeps/gnu -I../sysdeps/unix/inet -I../sysdeps/unix/sysv -I../sysdeps/unix/arm -I../sysdeps/unix -I../sysdeps/posix -I../sysdeps/arm/armv6 -I../sysdeps/arm/include -I../sysdeps/arm -I../sysdeps/wordsize-32 -I../sysdeps/ieee754/flt-32 -I../sysdeps/ieee754/dbl-64 -I../sysdeps/ieee754 -I../sysdeps/generic -I.. -I../libio -I. -nostdinc -isystem /home/billd/_build/builds/destdir/x86_64-unknown-linux-gnu/lib/gcc/arm-linux-gnueabi/5.1.1/include -isystem /home/billd/_build/builds/destdir/x86_64-unknown-linux-gnu/lib/gcc/arm-linux-gnueabi/5.1.1/include-fixed -isystem /home/billd/_build/sysroots/arm-linux-gnueabi/usr/include -D_LIBC_REENTRANT -include /home/billd/_build/builds/x86_64-unknown-linux-gnu/arm-linux-gnueabi/glibc.git~release-2.21-master/libc-modules.h -DMODULE_NAME=libc -include ../include/libc-symbols.h -o /home/billd/_build/builds/x86_64-unknown-linux-gnu/arm-linux-gnueabi/glibc.git~release-2.21-master/csu/aeabi_memclr.o -MD -MP -MF /home/billd/_build/builds/x86_64-unknown-linux-gnu/arm-linux-gnueabi/glibc.git~release-2.21-master/csu/aeabi_memclr.o.dt -MT /home/billd/_build/builds/x86_64-unknown-linux-gnu/arm-linux-gnueabi/glibc.git~release-2.21-master/csu/aeabi_memclr.o /tmp/ccTT8UgL.s: Assembler messages: /tmp/ccTT8UgL.s:492: Error: lo register required -- `add pc,r3,#(0xffff0fc0-0xffff0fff)' /tmp/ccTT8UgL.s:490: Error: invalid immediate: -61441 is out of range make[2]: *** [/home/billd/_build/builds/x86_64-unknown-linux-gnu/arm-linux-gnueabi/glibc.git~release-2.21-master/csu/libc-start.o] Error 1 --- here is the gcc -v output for the build above. ---- ./arm-linux-gnueabi-gcc -v Using built-in specs. COLLECT_GCC=./arm-linux-gnueabi-gcc COLLECT_LTO_WRAPPER=/home/billd/_build/builds/destdir/x86_64-unknown-linux-gnu/libexec/gcc/arm-linux-gnueabi/5.1.1/lto-wrapper Target: arm-linux-gnueabi Configured with: '/home/billd/_build/snapshots/gcc.git~linaro-gcc-5-branch/configure' SHELL=/bin/bash --with-bugurl=https://bugs.linaro.org --with-mpc=/home/billd/_build/builds/destdir/x86_64-unknown-linux-gnu --with-mpfr=/home/billd/_build/builds/destdir/x86_64-unknown-linux-gnu --with-gmp=/home/billd/_build/builds/destdir/x86_64-unknown-linux-gnu --with-gnu-as --with-gnu-ld --disable-libstdcxx-pch --disable-libmudflap --with-cpu=arm1136j-s --with-cloog=no --with-ppl=no --with-isl=no --disable-nls --enable-c99 --with-fpu=vfpv3-d16 --with-float=softfp --with-mode=thumb --disable-multilib --enable-multiarch --disable-libssp --disable-libquadmath --disable-threads --without-headers --with-newlib --disable-libmudflap --disable-bootstrap --disable-decimal-float --disable-libgomp --disable-libatomic --disable-libsanitizer --disable-plugins --disable-libitm MAKEINFO=echo --enable-languages=c --with-sysroot=/home/billd/_build/builds/sysroot-arm-linux-gnueabi --disable-shared --with-glibc-version=2.18 --build=x86_64-unknown-linux-gnu --host=x86_64-unknown-linux-gnu --target=arm-linux-gnueabi --prefix=/home/billd/_build/builds/destdir/x86_64-unknown-linux-gnu Thread model: single gcc version 5.1.1 20150608 (Linaro GCC 5.1-2015.06-1~dev)

10 years, 1 month

3
3
0 0

[ACTIVITY] Week 37

by Yvan Roux

== Progress == o Linaro GCC validation (8/10) * Finished on-going backports validation * Still dealing with jenkins/infra instability * Prepared branch merge * Continue on my new reviewing/validation tool o Misc (2/10) * Various meetings * AArch64 libunwind patch review == Plan == o Finish branch merge o GCC snapshot o Travel to SFO'15

10 years, 1 month

1
0
0 0

[ACTIVITY] 7-11 September 2015

by Christophe Lyon

== Progress == * GCC (4/10) - AdvSIMD failures on aarch64_be: looking at tbl[34] intrinsics * Releases/snapshots/validation (3/10) * Misc (3/10) - meetings, conf-calls, emails - Connect preparation == Next == * GCC aarch64_be AdvSIMD * Validation / reviews / backports * Connect preparation

10 years, 1 month

1
0
0 0

[Weekly] 07-11 SEPTEMBER 2015

by Michael Collison

== This week == * TCWG-316 -Exploit vector multiply by scalar instructions when multiple scalars are used as coefficients in a loop (5/10) - Wrote patterns to allow combine pass to mergenon-standard multiply by lane patterns. * Bugzilla 57195 (mode iterator bug) blocked compiling new pattern (1/10) - Updated patch based on upstream comments and re-sent upstream * TCWG-77 - Transform end of loop conditions to min_expr (1/10) - Writing dejagnu test case. - Writing function to check for min expr support on target * Misc (1/10) - Conference calls * Holiday (2/10) == Next week == - Complete TCWG-77 and send upstream - Continued investigation into TCWG-316

10 years, 1 month

1
0
0 0

[activity] 07 - 11 Sep 2015

by Prathamesh Kulkarni

== This week == * TCWG-80 (1/10) - PRE and dead-store elimination ipa pass (WIP upstream) already handles optimization * TCWG-120 (2/10) - Investigating 3 possible approaches: a) fold arm_andsi3_insn/arm_cmpsi_insn to zeroextractsi_compare0_scratch/andsi3_compare0_scratch b) Undo cse in test conditions, and modify arm_rtx_costs to fold arm_andsi3_insn/arm_cmpsi_insn to zeroextractsi_compare0_scratch/andsi3_compare0_scratch c) Expand directly to zeroextractsi_compare0_scratch/andsi3_compare0_scratch - Not sure whether the generated assembly is better (in terms of speed) than with trunk. asm diff at -O1: http://pastebin.com/yXBHHkhM * TCWG-72 (2/10) - Rebased Kugan's patch * TCWG-299 (3/10) - Simple workaround for PR65837 - configure gcc with --with-fpu=neon - Firefox trunk doesn't build with gcc for arm, using apt-get source firefox - LTO build fails with out-of-memory on my laptop in qemu-arm chroot * TCWG-319 (1/10) - Benchmarking setup with Bernie on Juno for running SPEC. - SPEC Runs without error on Juno-{a53,a57} and APM * Misc (1/10) - Meetings == Next Week == - Continue with TCWG-120, TCWG-72, TCWG-319

10 years, 1 month

1
0
0 0

Missing expat support in GDB 7.8

by Andreas Schmidl

Hi! The pre-built version of the stable version of Linaro Toolchain (Linaro GDB 2015.02-3) for Windows is shipped with GDB 7.8-2014.09-1-git. GDB was built with the following options: (gdb) show configuration This GDB was configured as follows: configure --host=i686-w64-mingw32 --target=arm-linux-gnueabihf --with-auto-load-dir=$debugdir:$datadir/auto-load --with-auto-load-safe-path=$debugdir:$datadir/auto-load --without-expat --with-gdb-datadir=/home/buildslave/workspace/BinaryRelease/label/hetzner/target/arm-linux-gnueabihf/_build/builds/destdir/i686-w64-mingw32/share/gdb (relocatable) --with-jit-reader-dir=/home/buildslave/workspace/BinaryRelease/label/hetzner/target/arm-linux-gnueabihf/_build/builds/destdir/i686-w64-mingw32/lib/gdb (relocatable) --without-libunwind-ia64 --without-lzma --without-guile --with-separate-debug-dir=/home/buildslave/workspace/BinaryRelease/label/hetzner/target/arm-linux-gnueabihf/_build/builds/destdir/i686-w64-mingw32/lib/debug (relocatable) --without-zlib --without-babeltrace As you can see in the output GDB was built without expat support. This is a major problem for widely used micro controllers like ARM Cortex A8 (e.g. used in Beaglebone Black), because the technical description of this microcontroller is loaded out of xml files (arm-with-neon.xml part of GDB). It's also possible to do that manually with "set tdesc filename <xml-file>, before connecting to the target. Without having the expat option enabled the g package, which is sent from gdbserver during establishing a connection to gdb, can't be parsed correctly. The result is in the first step a warning because of the missing xml support and later on a error regarding the unexpected content of the g package: warning: Can not parse XML target description; XML support was disabled at compile time Remote 'g' packet reply is too long: 00000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000f0fcffbe00000000407afdb6300000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000000 Old GDB versions of Linaro Toolchain like 7.6.1-2013.10 doesn't have that problem because they were compiled with enabled expat support. In my opinion there can be two root causes regarding that missing expat support: a) Expat support was explicitly disabled with --without-expat option during the built of GDB. b) On the build machine there wasn't a expat library available when gdb was built. Best regards, Andreas Schmidl

10 years, 1 month

1
0
0 0

2025

2024

2023

2022

2021

2020

2019

2018

2017

2016

2015

2014

2013

2012

2011

2010

linaro-toolchain