linaro-toolchain January 2017

linaro-toolchain@lists.linaro.org

11 participants
33 discussions

by Yao Qi

~ Progress ~ * TCWG-984 Handle exception/error in disassembly, [4/10] Patches are posted and reviewed. Three patches to opcodes are approved and committed. V2 is done to address comments on C++ and unit tests. V2 are being tested. * Patches review, [4/10] ** Review some preparatory SVE patches from Alan. They are good to me, but I expect Joel or someone else to take a look as well. ** Linux kernel awareness debugging. Review the patch sent from linaro, but some one from IBM sends a similar patch series. These two patch sets look similar, but are different on some parts. * Conversation with Paul (openocd maintainer) on irc. [1/10] They really want me to look at some gdb+openocd issues. My Hikey will arrive soon, but they give me some explanations on why cortex-m board is better than cortex-a board in bare-metal, because of simplicity. I explained to them why Linaro focused on cortex-a devices so far. * Linaro Connect. [1/10] Register the connect, book flight and hotel. ~ Plan ~ * TCWG-984 and TCWG-333 * Carefully read Dave M's SVE user space VL control API. * Carefully read IBM's kernel debugging patches. -- Yao Qi

8 years, 3 months

[ACTIVITY] 9 - 13 Jan 2016

by Prathamesh Kulkarni

== This Week == * TCWG-1005 (malloc attr propagation) (6/10) - Worked through bootstrap failures - Patch found 35 functions that could have malloc attribute during gcc build - The current analysis to find candidate functions is too restrictive, working on improving that. - Wrote few test-cases. * TCWG-1006 (returns_nonnull attr propagation) (2/10) - WIP prototype patch * TCWG-1010 (bitwise-dce) (1/10) - Going thru demanded-bits analysis * Misc (1/10) - Meetings == Next Week == - Continue working on TCWG-1005, TCWG-1006 and TCWG-1010

8 years, 3 months

[ACTIVITY] 9-13 January 2017

by Christophe Lyon

== Progress == * Validation - improvements and bug fixes: ABE #2764. and make_docs problem for gcc-4.9 builds) Enhanced abe validation to check builds of gcc-4.9, 5 and 6. make-and-test-release now works. buildbench now works * GCC - Committed fix for pr78253 - discussions on releases (packaging, process improvements) - a few backports for our 6.2-2017.01 snapshot * misc (conf-calls, meetings, emails, ....) - bugzilla followup - moving from ex40-01 to dev-01 - Connect registration: on-going == Next == * ABE & Jenkins jobs patches reviews and bug fixes * GCC: - bug fixing

8 years, 3 months

Re: Does Linaro's GCC 4.9 include Crypto extensions and intrinsics?

by Jeffrey Walton

Thanks guys, that was it. I did not realize the build system was omitting the flags. On Fri, Jan 13, 2017 at 2:23 AM, Pinski, Andrew <Andrew.Pinski(a)cavium.com> wrote: > Can you try -march=armv8+crypto ? > > -----Original Message----- > From: linaro-toolchain [mailto:linaro-toolchain-bounces@lists.linaro.org] On Behalf Of Jeffrey Walton > Sent: Thursday, January 12, 2017 10:56 PM > To: Linaro Toolchain Mailman List <linaro-toolchain(a)lists.linaro.org> > Subject: Does Linaro's GCC 4.9 include Crypto extensions and intrinsics? > > Please forgive my ignorance. I'm working on a Pine64 dev-board Pine64 supplies Linaro's GCC 4.9.2 toolchain. > > I am catching a compile error, and I am trying to determine why. > > Does Linaro's GCC 4.9 provide AES and SHA intrinsics?

8 years, 3 months

Does Linaro's GCC 4.9 include Crypto extensions and intrinsics?

by Jeffrey Walton

Please forgive my ignorance. I'm working on a Pine64 dev-board Pine64 supplies Linaro's GCC 4.9.2 toolchain. I am catching a compile error, and I am trying to determine why. Does Linaro's GCC 4.9 provide AES and SHA intrinsics? ********** $ uname -a Linux pine64 3.10.102-2-pine64-longsleep #66 SMP PREEMPT Sat Jul 16 10:53:13 CEST 2016 aarch64 GNU/Linux $ gcc --version gcc (Debian/Linaro 4.9.2-10) 4.9.2 Copyright (C) 2014 Free Software Foundation, Inc. ********** $ CFLAGS="-DMBEDTLS_HAVE_ARMV8A_CE=1" make DEBUG=1 V=1 CC aes_armv8a_ce.c aes_armv8a_ce.c: In function 'mbedtls_armv8a_ce_aes_crypt_ecb': aes_armv8a_ce.c:65:4: warning: implicit declaration of function 'vaeseq_u8' [-Wimplicit-function-declaration] state_vec = vaeseq_u8( state_vec, roundkey_vec ); ^ aes_armv8a_ce.c:65:14: error: incompatible types when assigning to type 'uint8x16_t' from type 'int' state_vec = vaeseq_u8( state_vec, roundkey_vec ); ^ aes_armv8a_ce.c:67:4: warning: implicit declaration of function 'vaesmcq_u8' [-Wimplicit-function-declaration] state_vec = vaesmcq_u8( state_vec ); ^ aes_armv8a_ce.c:67:14: error: incompatible types when assigning to type 'uint8x16_t' from type 'int' state_vec = vaesmcq_u8( state_vec ); ^ aes_armv8a_ce.c:74:13: error: incompatible types when assigning to type 'uint8x16_t' from type 'int' state_vec = vaeseq_u8( state_vec, roundkey_vec ); ^ aes_armv8a_ce.c:84:4: warning: implicit declaration of function 'vaesdq_u8' [-Wimplicit-function-declaration] state_vec = vaesdq_u8( state_vec, roundkey_vec ); ^ aes_armv8a_ce.c:84:14: error: incompatible types when assigning to type 'uint8x16_t' from type 'int' state_vec = vaesdq_u8( state_vec, roundkey_vec ); ^ aes_armv8a_ce.c:86:4: warning: implicit declaration of function 'vaesimcq_u8' [-Wimplicit-function-declaration] state_vec = vaesimcq_u8( state_vec ); ^ aes_armv8a_ce.c:86:14: error: incompatible types when assigning to type 'uint8x16_t' from type 'int' state_vec = vaesimcq_u8( state_vec ); ^ aes_armv8a_ce.c:93:13: error: incompatible types when assigning to type 'uint8x16_t' from type 'int' state_vec = vaesdq_u8( state_vec, roundkey_vec ); ^ aes_armv8a_ce.c: In function 'mbedtls_armv8a_ce_gcm_mult': aes_armv8a_ce.c:138:2: warning: implicit declaration of function 'vmull_high_p64' [-Wimplicit-function-declaration] r1 = (uint8x16_t)vmull_high_p64( (poly64x2_t)a_p, (poly64x2_t)b_p ); ^ aes_armv8a_ce.c:138:2: error: can't convert between vector values of different size aes_armv8a_ce.c:141:2: error: can't convert between vector values of different size t0 = (uint8x16_t)vmull_high_p64( (poly64x2_t)a_p, (poly64x2_t)t0 ); ^ aes_armv8a_ce.c:150:2: error: can't convert between vector values of different size t0 = (uint8x16_t)vmull_high_p64( (poly64x2_t)r1, (poly64x2_t)p ); ^ Makefile:170: recipe for target 'aes_armv8a_ce.o' failed make[1]: *** [aes_armv8a_ce.o] Error 1 Makefile:17: recipe for target 'lib' failed make: *** [lib] Error 2 ********** CC sha1_armv8a_ce.c sha1_armv8a_ce.c: In function 'mbedtls_armv8a_ce_sha1_process': sha1_armv8a_ce.c:99:2: warning: implicit declaration of function 'vsha1h_u32' [-Wimplicit-function-declaration] e1 = vsha1h_u32( a ); ^ sha1_armv8a_ce.c:100:2: warning: implicit declaration of function 'vsha1cq_u32' [-Wimplicit-function-declaration] abcd = vsha1cq_u32( abcd, e, wk0 ); /* 0 */ ^ sha1_armv8a_ce.c:100:7: error: incompatible types when assigning to type 'uint32x4_t' from type 'int' abcd = vsha1cq_u32( abcd, e, wk0 ); /* 0 */ ^ sha1_armv8a_ce.c:102:2: warning: implicit declaration of function 'vsha1su0q_u32' [-Wimplicit-function-declaration] w0 = vsha1su0q_u32( w0, w1, w2 ); ^ sha1_armv8a_ce.c:102:5: error: incompatible types when assigning to type 'uint32x4_t' from type 'int' w0 = vsha1su0q_u32( w0, w1, w2 ); ^ sha1_armv8a_ce.c:106:7: error: incompatible types when assigning to type 'uint32x4_t' from type 'int' abcd = vsha1cq_u32( abcd, e1, wk1 ); /* 1 */ ^ sha1_armv8a_ce.c:108:2: warning: implicit declaration of function 'vsha1su1q_u32' [-Wimplicit-function-declaration] w0 = vsha1su1q_u32( w0, w3 ); ^ sha1_armv8a_ce.c:108:5: error: incompatible types when assigning to type 'uint32x4_t' from type 'int' w0 = vsha1su1q_u32( w0, w3 ); ^ sha1_armv8a_ce.c:109:5: error: incompatible types when assigning to type 'uint32x4_t' from type 'int' w1 = vsha1su0q_u32( w1, w2, w3 ); ^ ... ********** $ grep -IR vaeseq_u8 /usr/include /usr/include/clang/3.5.0/include/arm_neon.h:__ai uint8x16_t vaeseq_u8(uint8x16_t __p0, uint8x16_t __p1) { /usr/include/clang/3.5.0/include/arm_neon.h:__ai uint8x16_t vaeseq_u8(uint8x16_t __p0, uint8x16_t __p1) { /usr/include/clang/3.5/include/arm_neon.h:__ai uint8x16_t vaeseq_u8(uint8x16_t __p0, uint8x16_t __p1) { /usr/include/clang/3.5/include/arm_neon.h:__ai uint8x16_t vaeseq_u8(uint8x16_t __p0, uint8x16_t __p1) { $

8 years, 3 months

[ANNOUNCE] Linaro GCC 6 2017.01 snapshot

by Yvan Roux

The Linaro Toolchain Working Group (TCWG) is pleased to announce the 2017.01 snapshot of the Linaro GCC 6 source package. This monthly snapshot[1] is based on FSF GCC 6.3+svn244220 and includes performance improvements and bug fixes backported from mainline GCC. This snapshot contents will be part of the 2017.02 stable[2] quarterly release. This snapshot tarball is available on: http://snapshots.linaro.org/components/toolchain/gcc-linaro/6.3-2017.01/ Interesting changes in this GCC source package snapshot include: * Updates to GCC 6.3+svn244220 * Backport of [Bugfix] Fix PR77673: bswap loads passed end of object * Backport of [ARMv8-M] [AArch32] 1/7 Move memory model declarations in memmodel.h * Backport of [ARMv8-M] [AArch32] 2/7 Adapt atomic and exclusive load and store to ARMv8-M Baseline * Backport of [ARMv8-M] [AArch32] 3/7 Refactor atomic compare_and_swap to make it fit for ARMv8-M Baseline * Backport of [ARMv8-M] [AArch32] 4/7 Adapt atomic compare and swap to ARMv8-M Baseline * Backport of [ARMv8-M] [AArch32] 5/7 Adapt other atomic operations to ARMv8-M Baseline * Backport of [ARMv8-M] [AArch32] 7/7 Enable ARMv8-M atomic and synchronization support for ARMv8-M Baseline * Backport of [ARMv8-M] [AArch32] Added support for ARMV8-M Security Extension cmse_nonsecure_caller intrinsic * Backport of [ARMv8-M] [AArch32] Add multilib mapping for Cortex-M23 & Cortex-M33 * Backport of [ARMv8-M] [AArch32] Add support for ARM Cortex-M23 processor * Backport of [ARMv8-M] [AArch32] Add support for ARM Cortex-M33 processor * Backport of [ARMv8-M] [AArch32] Add support for ARMv8-M's Secure Extensions flag and intrinsics * Backport of [ARMv8-M] [AArch32] ARMv8-M Security Extension's cmse_nonsecure_call: use __gnu_cmse_nonsecure_call * Backport of [ARMv8-M] [AArch32] ARMv8-M Security Extension's cmse_nonsecure_entry: __acle_se label and bxns return * Backport of [ARMv8-M] [AArch32] ARMv8-M Security Extension's cmse_nonsecure_entry: clear registers * Backport of [ARMv8-M] [AArch32] Fix various arm failures with config-list.mk * Backport of [ARMv8-M] [AArch32] Force soft float in ARMv6-M and ARMv8-M Baseline options * Backport of [ARMv8-M] [AArch32] Handling ARMv8-M Security Extension's cmse_nonsecure_call attribute * Backport of [ARMv8-M] [AArch32] Handling ARMv8-M Security Extension's cmse_nonsecure_entry attribute * Backport of [ARMv8-M] [AArch32] Make arm_feature_set agree with type of FL_* macros * Backport of [ARMv8-M] [AArch32] Optional -mthumb for Thumb only targets * Backport of [AArch64] 1/3 Add missing Poly64_t intrinsics to GCC * Backport of [AArch64] 2/3 Add missing Poly64_t intrinsics to GCC * Backport of [AArch64] 3/3 Add tests for missing Poly64_t intrinsics to GCC * Backport of [AArch64] Add more Poly64_t intrinsics to GCC * Backport of [AArch64] more poly64 intrinsics * Backport of [Testsuite] [AArch64] Fix failing poly64 tests on ARM * Backport of [Testsuite] [AArch64] Lower iterator count on gcc.dg/atomic/c11-atomic-exec-5.c for AARCH64 * Backport of [Cleanup] Improve comment for struct symbolic_number in bswap pass 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]. Source package snapshots are defined when the compiler is only put through unit-testing and full validation is not performed. [2]. Stable source package releases are defined as releases where the full Linaro Toolchain validation plan is executed.

8 years, 3 months

[ACTIVITY] Week 01

by Yvan Roux

o 1 day off (2/10) o Teaching activity (4/10) == Progress == o Linaro GCC/Validation (2/10) * 5.4-2017.01-rc1 release notes and publication * Some infra bugfixes and reviews o Misc (1/10) * Various meetings and discussions. * Plan for 2017 == Plan == o GCC 6 branch merge and snapshot

8 years, 3 months

[ACTIVITY] 2-6 January 2017

by Christophe Lyon

== Progress == * Validation - general improvement (jobs, abe cleanup and fixes) - submitted several patches for abe bug reports * GCC - pinged patches, still waiting for feedback * misc (conf-calls, meetings, emails, ....) - bugzilla followup - internal updates/problems after general IT maintenance - reported binutils trunk regressions == Next == * ABE & Jenkins jobs patches reviews and bug fixes * GCC: - bug fixing - Linaro bugzilla cleanup

8 years, 3 months

[ACTIVITY] 3 to 6 January 2017

by kugan

== Activity == - [PR64946] abs vectorization fails for char/short types * Trying to tackle this with ABSU_EXPR * Experimented with implemented in FE vs in gimplification * Hope to get a working prototype this week - Misc * gcc-patches/bug list * Plan for 2017 == Plans for next week == - PR64946 - Catch up on pending patches

8 years, 3 months

[ACTIVITY] 02 - 6 January 2016

by Omair Javaid

=== This Week === Back from month long holiday had a surgery during this period. Add Pine64 as tester to LLDB buildbot [TCWG-1011] [3/10] -- Configure Pine64 with Ubuntu 16.04 image -- Configure network on Pine64 to be used with LLDB buildbot -- Configure Pine64 for AArch32 mode execution -- Configure LLDB buildbot to include Pine64 as tester in both AArch32 and AArch64 modes. -- Run buildbot with Pine64 and monitor stability Monitor LLDB buildbot for minimum down time. [TCWG-712] -- Return from break reset buildbot and testers. Investigate LLDB testsuite failures on Pine64 target (AArch32 and AArch64 modes) [TCWG-1012] [2/10] -- Some tests pass when run individually. -- Some tests fail only when run in testsuite, similar steps pass when run using LLDB commandline. LLDB Arm/AArch64 Investigate and fix testsuite crashes (Pine64 Crashes) [TCWG-792] [1/10] -- LLDB crashing unexpectedly on Pine64 as well. -- Initial investigation suggests test run fine individually and in single thread mode. Meetings and other Miscellaneous Activities [1/10] -- Browse through email backlog. -- Prepared a future ToDo list. BUD17 Travel - Schengen visa application for Budapest, Hungary. [3/10] -- Information gathering and correspondance. -- Form filling and preparation supporting documentation. -- Application submission. -- Interview date is on 10th Jan 2017. === Next Week === Investigate LLDB testsuite failures on Pine64 target (AArch32 and AArch64 modes) [TCWG-1012] -- Continue to investigate, possible fix trivial issues and mark rest as xfail with appropriate bug reports. LLDB Arm/AArch64 Investigate and fix testsuite crashes (Pine64 Crashes) [TCWG-792] -- Find a reliable reason to the issue as this hampers our buildbot work. BUD17 Travel - Schengen visa application for Budapest, Hungary. -- Budapest visa interview travelling to Islamabad 9 - 10 Jan 2017.

8 years, 3 months

2025

2024

2023

2022

2021

2020

2019

2018

2017

2016

2015

2014

2013

2012

2011

2010

linaro-toolchain January 2017