This patch enables the new Transactional Memory Extension announced recently as part of Arm's new architecture technologies. We introduce a new optional extension "tme" to enable this. The following instructions are part of the extension: * tstart <Xt> * ttest <Xt> * tcommit * tcancel #<imm> We have also added ACLE intrinsics for the instructions. *** gcc/ChangeLog *** 2019-07-31 Sudakshina Das <sudi.das@arm.com> * config/aarch64/aarch64-builtins.c (enum aarch64_builtins): Add AARCH64_TME_BUILTIN_TSTART, AARCH64_TME_BUILTIN_TCOMMIT, AARCH64_TME_BUILTIN_TTEST and AARCH64_TME_BUILTIN_TCANCEL. (aarch64_init_tme_builtins): New. (aarch64_init_builtins): Call aarch64_init_tme_builtins. (aarch64_expand_builtin_tme): New. (aarch64_expand_builtin): Handle TME builtins. * config/aarch64/aarch64-c.c (aarch64_update_cpp_builtins): Define __ARM_FEATURE_TME when enabled. * config/aarch64/aarch64-option-extensions.def: Add "tme". * config/aarch64/aarch64.h (AARCH64_FL_TME, AARCH64_ISA_TME): New. (TARGET_TME): New. * config/aarch64/aarch64.md (define_c_enum "unspec"): Add UNSPEC_TTEST. (define_c_enum "unspecv"): Add UNSPECV_TSTART, UNSPECV_TCOMMIT and UNSPECV_TCANCEL. (tstart, ttest, tcommit, tcancel): New instructions. * config/aarch64/arm_acle.h (__tstart, __tcommit): New. (__tcancel, __ttest): New. (_TMFAILURE_REASON, _TMFAILURE_RTRY, _TMFAILURE_CNCL): New macro. (_TMFAILURE_MEM, _TMFAILURE_IMP, _TMFAILURE_ERR): Likewise. (_TMFAILURE_SIZE, _TMFAILURE_NEST, _TMFAILURE_DBG): Likewise. (_TMFAILURE_INT, _TMFAILURE_TRIVIAL): Likewise. * config/arm/types.md: Add new tme type attr. * doc/invoke.texi: Document "tme". *** gcc/testsuite/ChangeLog *** 2019-07-31 Sudakshina Das <sudi.das@arm.com> * gcc.target/aarch64/acle/tme.c: New test. * gcc.target/aarch64/pragma_cpp_predefs_2.c: New test. From-SVN: r273926
| Name |
Last commit
|
Last update |
|---|---|---|
| .. | ||
| README-interworking | Loading commit data... | |
| aarch-common-protos.h | Loading commit data... | |
| aarch-common.c | Loading commit data... | |
| aarch-cost-tables.h | Loading commit data... | |
| aout.h | Loading commit data... | |
| arm-builtins.c | Loading commit data... | |
| arm-c.c | Loading commit data... | |
| arm-cpus.in | Loading commit data... | |
| arm-d.c | Loading commit data... | |
| arm-fixed.md | Loading commit data... | |
| arm-flags.h | Loading commit data... | |
| arm-generic.md | Loading commit data... | |
| arm-ldmstm.ml | Loading commit data... | |
| arm-modes.def | Loading commit data... | |
| arm-opts.h | Loading commit data... | |
| arm-protos.h | Loading commit data... | |
| arm-simd-builtin-types.def | Loading commit data... | |
| arm-tables.opt | Loading commit data... | |
| arm-tune.md | Loading commit data... | |
| arm.c | Loading commit data... | |
| arm.h | Loading commit data... | |
| arm.md | Loading commit data... | |
| arm.opt | Loading commit data... | |
| arm1020e.md | Loading commit data... | |
| arm1026ejs.md | Loading commit data... | |
| arm1136jfs.md | Loading commit data... | |
| arm926ejs.md | Loading commit data... | |
| arm_acle.h | Loading commit data... | |
| arm_acle_builtins.def | Loading commit data... | |
| arm_cmse.h | Loading commit data... | |
| arm_fp16.h | Loading commit data... | |
| arm_neon.h | Loading commit data... | |
| arm_neon_builtins.def | Loading commit data... | |
| arm_vfp_builtins.def | Loading commit data... | |
| bpabi.h | Loading commit data... | |
| constraints.md | Loading commit data... | |
| cortex-a15-neon.md | Loading commit data... | |
| cortex-a15.md | Loading commit data... | |
| cortex-a17-neon.md | Loading commit data... | |
| cortex-a17.md | Loading commit data... | |
| cortex-a5.md | Loading commit data... | |
| cortex-a53.md | Loading commit data... | |
| cortex-a57.md | Loading commit data... | |
| cortex-a7.md | Loading commit data... | |
| cortex-a8-neon.md | Loading commit data... | |
| cortex-a8.md | Loading commit data... | |
| cortex-a9-neon.md | Loading commit data... | |
| cortex-a9.md | Loading commit data... | |
| cortex-m4-fpu.md | Loading commit data... | |
| cortex-m4.md | Loading commit data... | |
| cortex-m7.md | Loading commit data... | |
| cortex-r4.md | Loading commit data... | |
| cortex-r4f.md | Loading commit data... | |
| crypto.def | Loading commit data... | |
| crypto.md | Loading commit data... | |
| driver-arm.c | Loading commit data... | |
| elf.h | Loading commit data... | |
| exynos-m1.md | Loading commit data... | |
| fa526.md | Loading commit data... | |
| fa606te.md | Loading commit data... | |
| fa626te.md | Loading commit data... | |
| fa726te.md | Loading commit data... | |
| fmp626.md | Loading commit data... | |
| freebsd.h | Loading commit data... | |
| fuchsia-elf.h | Loading commit data... | |
| iterators.md | Loading commit data... | |
| iwmmxt.md | Loading commit data... | |
| iwmmxt2.md | Loading commit data... | |
| ldmstm.md | Loading commit data... | |
| ldrdstrd.md | Loading commit data... | |
| linux-eabi.h | Loading commit data... | |
| linux-elf.h | Loading commit data... | |
| linux-gas.h | Loading commit data... | |
| marvell-f-iwmmxt.md | Loading commit data... | |
| marvell-pj4.md | Loading commit data... | |
| mmintrin.h | Loading commit data... | |
| neon.md | Loading commit data... | |
| netbsd-eabi.h | Loading commit data... | |
| netbsd-elf.h | Loading commit data... | |
| parsecpu.awk | Loading commit data... | |
| predicates.md | Loading commit data... | |
| rtems.h | Loading commit data... | |
| semi.h | Loading commit data... | |
| symbian.h | Loading commit data... | |
| sync.md | Loading commit data... | |
| t-aprofile | Loading commit data... | |
| t-arm | Loading commit data... | |
| t-arm-elf | Loading commit data... | |
| t-bpabi | Loading commit data... | |
| t-fuchsia | Loading commit data... | |
| t-linux-androideabi | Loading commit data... | |
| t-linux-eabi | Loading commit data... | |
| t-multilib | Loading commit data... | |
| t-phoenix | Loading commit data... | |
| t-rmprofile | Loading commit data... | |
| t-rtems | Loading commit data... | |
| t-symbian | Loading commit data... | |
| t-vxworks | Loading commit data... | |
| thumb1.md | Loading commit data... | |
| thumb2.md | Loading commit data... | |
| types.md | Loading commit data... | |
| uclinux-eabi.h | Loading commit data... | |
| uclinux-elf.h | Loading commit data... | |
| unknown-elf.h | Loading commit data... | |
| unspecs.md | Loading commit data... | |
| vec-common.md | Loading commit data... | |
| vfp.md | Loading commit data... | |
| vfp11.md | Loading commit data... | |
| vxworks.h | Loading commit data... | |
| vxworks.opt | Loading commit data... | |
| x-arm | Loading commit data... | |
| xgene1.md | Loading commit data... |