Tcwg-commits August 2015

tcwg-commits@lists.linaro.org

1 participants
602 discussions

[gcc] branch trunk updated (4757c55 -> 05458f8)

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a change to branch trunk in repository gcc. from 4757c55 Compile IAMCU tests with -fno-pie -no-pie new 05458f8 Fix incorrect date in 2015-07-28 change. The 1 revisions listed above as "new" are entirely new to this repository and will be described in separate emails. The revisions listed as "adds" were already present in the repository and have only been added to this reference. Summary of changes: ChangeLog | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] branch hjl/pr66960/x86 updated (386f403 -> 0e48982)

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a change to branch hjl/pr66960/x86 in repository gcc. discards 386f403 Add __builtin_stack_top adds e880695 * c-pretty-print.c (unary_expression) [INDIRECT_REF]: Don't [...] adds a8a727a Use lowpart_subreg instead of simplify_gen_subreg adds be3783f [V850] Hookize LIBCALL_VALUE adds fa7dcde Daily bump. adds eb37590 * sv.po: Update. adds 2aa16f1 * sv.po: Update. adds 86a932e Don't cancel loop tree in parloops adds 58c4f49 * go-lang.c (go_langhook_init_options_struct): Don't set x_fl [...] adds b1cd5ae 2015-07-31 Richard Biener <rguenther(a)suse.de> adds 5d262bd Refactoring masked built-in decls to use proper mask type. adds 56b4132 2015-07-31 Richard Biener <rguenther(a)suse.de> adds 4150a43 PR sanitizer/66977 * typeck.c (get_member_function_from_ptr [...] adds 2d86a0e PR target/66870 * config/rs6000/rs6000.c (machine_function) [...] adds 245894e * config/m32r/m32r.c (m32r_attribute_identifier): New functi [...] adds 530bb69 [ARM][2/3] Make if_neg_move and if_move_neg into insn_and_split adds 8b3c974 compiler: Don't allow builtin function values. adds ad10d66 * MAINTAINERS (nvptx): Add self. adds 8289950 compiler: Update unicode tables. adds 6d69611 compiler: Check the type in function declarations. adds 4d51316 PR target/67049 * config/sh/sh.md (GOTaddr2picreg): Fix typo [...] adds 5f1045b compiler: Report errors for malformed builtin calls. adds 4691a53 Daily bump. adds 5955834 Allow non-overflow ops in reductions adds 814b1ca 2015-08-01 Paul Thomas <pault(a)gcc.gnu.org> adds 6ffea52 Daily bump. adds 68a98a7 Fix PR 66521 adds 3d5db02 2015-08-01 Michael Collison <michael.collison(a)linaro.org [...] adds 9255be0 Refactor entry point to -Wmisleading-indentation adds f95bfdd Remove is_first_nonwhitespace_on_line(), instead improve get_ [...] adds 17afcef Improve -Wmisleading-indentation heuristics adds 5b252e9 gcc/ChangeLog 2015-07-28 Martin Sebor <msebor(a)redhat.com> adds 408da55 Daily bump. adds d1a8d2a * MAINTAINERS (loop ivopts): Add the entry and myself. adds 9dd88d4 2015-08-03 Richard Biener <rguenther(a)suse.de> adds 535bc42 2015-08-03 Richard Biener <rguenther(a)suse.de> adds f11d6df 2015-08-03 Richard Biener <rguenther(a)suse.de> adds 5a0909a 2015-08-03 Richard Biener <rguenther(a)suse.de> adds a929e01 [RTL-ifcvt] Improve conditional select ops on immediates adds c63a11d Fix random class_allocate_18.f90 failure adds 6cb6651 [ARM] PR target/66731 Fix vnmul insn with -frounding-math adds 605922a gcc/ChangeLog: adds 5ba71b3 2015-08-03 Richard Biener <rguenther(a)suse.de> adds ec66e09 2015-08-03 Richard Biener <rguenther(a)suse.de> adds 05999bf 2015-08-03 Richard Biener <rguenther(a)suse.de> adds c909938 PR c/67088 * c-decl.c (check_bitfield_type_and_width): Add [...] adds 0686247 Avoid recomputing the defining predicate chains for the same PHI adds 18c03b4 * Makefile.in (OBJS): Put gimple-match.o and generic-match.o first. adds 6cf098e PR libstdc++/67078 * include/bits/range_access.h (size, emp [...] adds 51ea8bc PR middle-end/66314 PR gcov-profile/66899 * tree-ssa-threa [...] adds ddfc9c6 2015-08-03 Steven G. Kargl <kargl(a)gcc.gnu.org> adds 1d9f8a1 Add a testcase for PR tree-optimization/67077 adds 97d09b3 2015-08-03 Michael Meissner <meissner(a)linux.vnet.ibm.com> adds eedb218 PR target/67060 * config/pa/pa.md (call_reg_64bit): Remove [...] adds 7dcad76 PR go/67101 adds fc2edda libgo/testsuite: kill sleep process in gotest adds e6d1c8b compiler: Don't make erroneous type descriptors. adds f27f157 PR middle-end/64744 PR middle-end/48470 PR middle-end/4340 [...] adds cb96a11 compiler: Don't allow multiple function declarations. adds 17c0b84 Refactoring of timevar API adds 8ad9537 gcc/ * config/rs6000/htm.md (tabort.): Restrict the source o [...] adds e487326 syscall: RawSockaddr fix for ppc64, ppc64le adds 2d72810 Daily bump. adds fae2de1 * plugin/plugin-nvptx.c: Don't include dlfcn.h. (cuda_errli [...] adds ff429db 2015-08-04 Thomas Preud'homme <thomas.preudhomme(a)arm.com> adds 1b02261 runtime: initialize variable to avoid compiler warning adds 207b828 * tree-if-conv.c: Fix various typos in comments. * tree-vec [...] adds c53bd1d PR fortran/64022 adds e198177 * config/fpu-387.h (get_fpu_trap_exceptions): Add temporary [...] adds 693a749 * config/fpu-387.h: Remove unwanted whitespace. adds 38758f3 2015-08-04 Richard Biener <rguenther(a)suse.de> adds 245cad5 [AArch64][1/14] Add ident field to struct processor adds 9356ca1 [AArch64][2/14] Refactor arches handling, add arch enum identifier adds 50021c3 [AArch64][3/14] Refactor option override code adds 36d84ec * config/i386/i386.c (ix86_expand_int_movcc): Check result o [...] adds ee92bc9 [AArch64][4/14] Create TARGET_FIX_ERR_A53_835769 and use that [...] adds 3f215f2 [AArch64][5/14] Make flag_omit_leaf_frame_pointer intialize t [...] adds a0db861 [AArch64][6/14] Implement TARGET_OPTION_SAVE/TARGET_OPTION_RESTORE adds f59387a [AArch64][7/14] Implement TARGET_SET_CURRENT_FUNCTION adds aadb8e1 [AArch64][8/14] Implement TARGET_OPTION_VALID_ATTRIBUTE_P adds b0269e3 [AArch64][9/14] Implement TARGET_CAN_INLINE_P adds 26db532 [AArch64][10/14] Implement target pragmas adds dad9014 [AArch64][11/14] Re-layout SIMD builtin types on builtin expansion adds b65ae63 [AArch64][12/14] Target attributes and target pragmas tests adds 5de59ee [doc][13/14] Document AArch64 target attributes and pragmas adds cd33329 [AArch64][14/14] Reuse target_option_current_node when passin [...] adds d8cc4c5 2015-08-04 Paolo Carlini <paolo.carlini(a)oracle.com> adds 4757c55 Compile IAMCU tests with -fno-pie -no-pie new 0e48982 Add __builtin_stack_top This update added new revisions after undoing existing revisions. That is to say, some revisions that were in the old version of the branch are not in the new version. This situation occurs when a user --force pushes a change and generates a repository containing something like this: * -- * -- B -- O -- O -- O (386f403) \ N -- N -- N refs/heads/hjl/pr66960/x86 (0e48982) You should already have received notification emails for all of the O revisions, and so the following emails describe only the N revisions from the common base, B. Any revisions marked "omits" are not gone; other references still refer to them. Any revisions marked "discards" are gone forever. The 1 revisions listed above as "new" are entirely new to this repository and will be described in separate emails. The revisions listed as "adds" were already present in the repository and have only been added to this reference. Summary of changes: ChangeLog | 8 + MAINTAINERS | 2 + gcc/ChangeLog | 1107 ++++++- gcc/DATESTAMP | 2 +- gcc/Makefile.in | 15 +- gcc/builtins.c | 28 +- gcc/c-family/ChangeLog | 31 + gcc/c-family/c-common.h | 7 - gcc/c-family/c-indentation.c | 299 +- gcc/c-family/c-indentation.h | 52 + gcc/c-family/c-pretty-print.c | 8 +- gcc/c-family/c.opt | 4 + gcc/c/ChangeLog | 19 + gcc/c/c-decl.c | 24 +- gcc/c/c-parser.c | 81 +- gcc/cfgexpand.c | 30 +- gcc/combine.c | 4 +- gcc/common/config/aarch64/aarch64-common.c | 19 +- gcc/config.gcc | 2 + gcc/config/aarch64/aarch64-arches.def | 15 +- gcc/config/aarch64/aarch64-builtins.c | 39 +- gcc/config/aarch64/aarch64-c.c | 203 ++ gcc/config/aarch64/aarch64-cores.def | 22 +- gcc/config/aarch64/aarch64-elf-raw.h | 2 +- gcc/config/aarch64/aarch64-linux.h | 2 +- gcc/config/aarch64/aarch64-opts.h | 9 + gcc/config/aarch64/aarch64-protos.h | 14 + gcc/config/aarch64/aarch64.c | 1486 +++++++-- gcc/config/aarch64/aarch64.h | 104 +- gcc/config/aarch64/aarch64.opt | 35 +- gcc/config/aarch64/arm_acle.h | 10 +- gcc/config/aarch64/arm_neon.h | 19 +- gcc/config/aarch64/driver-aarch64.c | 8 +- gcc/config/aarch64/t-aarch64 | 5 + gcc/config/arm/arm.c | 9 +- gcc/config/arm/arm.md | 98 +- gcc/config/arm/vfp.md | 23 + gcc/config/i386/i386-builtin-types.def | 864 +++--- gcc/config/i386/i386.c | 3191 ++++++++++---------- gcc/config/m32r/m32r.c | 10 + gcc/config/pa/pa.md | 6 - gcc/config/rs6000/altivec.md | 21 +- gcc/config/rs6000/constraints.md | 12 + gcc/config/rs6000/htm.md | 2 +- gcc/config/rs6000/predicates.md | 8 + gcc/config/rs6000/rs6000.c | 15 + gcc/config/rs6000/rs6000.h | 2 + gcc/config/rs6000/vector.md | 28 +- gcc/config/rs6000/vsx.md | 143 +- gcc/config/sh/sh.md | 2 +- gcc/config/v850/v850.c | 15 +- gcc/config/v850/v850.h | 6 - gcc/config/v850/v850.md | 1 + gcc/configure | 41 +- gcc/configure.ac | 26 + gcc/cp/ChangeLog | 28 + gcc/cp/mangle.c | 8 + gcc/cp/parser.c | 100 +- gcc/cp/typeck.c | 7 + gcc/doc/extend.texi | 168 +- gcc/doc/invoke.texi | 9 +- gcc/doc/md.texi | 19 +- gcc/emit-rtl.c | 5 +- gcc/expr.c | 14 +- gcc/fold-const.c | 50 - gcc/fortran/ChangeLog | 23 + gcc/fortran/class.c | 1 + gcc/fortran/simplify.c | 79 +- gcc/fortran/trans-expr.c | 10 +- gcc/fortran/trans-intrinsic.c | 2 + gcc/function.c | 6 +- gcc/genmatch.c | 432 ++- gcc/gimple-fold.c | 116 +- gcc/gimple-match-head.c | 35 +- gcc/go/ChangeLog | 6 + gcc/go/go-lang.c | 9 +- gcc/go/gofrontend/MERGE | 2 +- gcc/go/gofrontend/expressions.cc | 3 +- gcc/go/gofrontend/gogo.cc | 65 +- gcc/go/gofrontend/gogo.h | 4 + gcc/go/gofrontend/lex.cc | 487 +-- gcc/go/gofrontend/parse.cc | 5 +- gcc/graphite-sese-to-poly.c | 7 +- gcc/ifcvt.c | 63 +- gcc/jit/ChangeLog | 63 + gcc/jit/docs/_build/texinfo/libgccjit.texi | 892 ++++-- gcc/jit/docs/topics/compatibility.rst | 21 + gcc/jit/docs/topics/contexts.rst | 3 +- gcc/jit/docs/topics/index.rst | 1 + gcc/jit/docs/topics/performance.rst | 240 ++ gcc/jit/jit-playback.c | 11 +- gcc/jit/jit-playback.h | 2 + gcc/jit/jit-recording.c | 2 + gcc/jit/jit-recording.h | 7 + gcc/jit/libgccjit++.h | 117 + gcc/jit/libgccjit.c | 109 + gcc/jit/libgccjit.h | 84 + gcc/jit/libgccjit.map | 12 + gcc/loop-invariant.c | 3 + gcc/loop-iv.c | 11 - gcc/main.c | 2 +- gcc/match.pd | 33 +- gcc/omp-low.c | 32 +- gcc/po/ChangeLog | 4 + gcc/po/sv.po | 128 +- gcc/rtl.h | 5 +- gcc/simplify-rtx.c | 15 +- gcc/testsuite/ChangeLog | 153 + .../c-c++-common/Wmisleading-indentation.c | 166 + gcc/testsuite/g++.dg/Wframe-address-in-Wall.C | 14 + gcc/testsuite/g++.dg/Wframe-address.C | 70 + gcc/testsuite/g++.dg/Wno-frame-address.C | 6 + gcc/testsuite/g++.dg/cpp1y/var-templ34.C | 20 + gcc/testsuite/g++.dg/ubsan/pr66977.C | 27 + gcc/testsuite/gcc.dg/Wframe-address-in-Wall.c | 14 + gcc/testsuite/gcc.dg/Wframe-address.c | 54 + gcc/testsuite/gcc.dg/Wno-frame-address.c | 6 + gcc/testsuite/gcc.dg/autopar/reduc-2char.c | 10 +- gcc/testsuite/gcc.dg/autopar/reduc-2short.c | 10 +- gcc/testsuite/gcc.dg/autopar/reduc-8.c | 7 +- gcc/testsuite/gcc.dg/pr66314.c | 33 + gcc/testsuite/gcc.dg/pr66899.c | 41 + gcc/testsuite/gcc.dg/pr67043.c | 32 + gcc/testsuite/gcc.dg/pr67077.c | 20 + gcc/testsuite/gcc.dg/pr67088.c | 18 + gcc/testsuite/gcc.dg/vect/trapv-vect-reduc-4.c | 2 +- .../gcc.target/aarch64/arm_neon-nosimd-error.c | 11 - .../gcc.target/aarch64/cpu-diagnostics-3.c | 2 +- gcc/testsuite/gcc.target/aarch64/csel_bfx_1.c | 11 + gcc/testsuite/gcc.target/aarch64/csel_imms_inc_1.c | 42 + .../gcc.target/aarch64/pragma_cpp_predefs_1.c | 255 ++ gcc/testsuite/gcc.target/aarch64/target_attr_1.c | 14 + gcc/testsuite/gcc.target/aarch64/target_attr_10.c | 16 + gcc/testsuite/gcc.target/aarch64/target_attr_11.c | 13 + gcc/testsuite/gcc.target/aarch64/target_attr_12.c | 13 + gcc/testsuite/gcc.target/aarch64/target_attr_13.c | 16 + gcc/testsuite/gcc.target/aarch64/target_attr_14.c | 20 + gcc/testsuite/gcc.target/aarch64/target_attr_15.c | 15 + gcc/testsuite/gcc.target/aarch64/target_attr_2.c | 39 + gcc/testsuite/gcc.target/aarch64/target_attr_3.c | 34 + gcc/testsuite/gcc.target/aarch64/target_attr_4.c | 30 + gcc/testsuite/gcc.target/aarch64/target_attr_5.c | 20 + gcc/testsuite/gcc.target/aarch64/target_attr_6.c | 20 + gcc/testsuite/gcc.target/aarch64/target_attr_7.c | 24 + gcc/testsuite/gcc.target/aarch64/target_attr_8.c | 22 + gcc/testsuite/gcc.target/aarch64/target_attr_9.c | 22 + .../gcc.target/aarch64/target_attr_crypto_ice_1.c | 21 + gcc/testsuite/gcc.target/arm/mincmp.c | 20 + gcc/testsuite/gcc.target/arm/pr43404.c | 10 + gcc/testsuite/gcc.target/arm/pr48470.c | 11 + gcc/testsuite/gcc.target/arm/pr64744-1.c | 40 + gcc/testsuite/gcc.target/arm/pr64744-2.c | 13 + gcc/testsuite/gcc.target/arm/vnmul-1.c | 18 + gcc/testsuite/gcc.target/arm/vnmul-2.c | 18 + gcc/testsuite/gcc.target/arm/vnmul-3.c | 18 + gcc/testsuite/gcc.target/arm/vnmul-4.c | 18 + gcc/testsuite/gcc.target/i386/iamcu/abi-iamcu.exp | 2 +- gcc/testsuite/gcc.target/i386/pr66960-1.c | 2 +- .../gcc.target/powerpc/htm-tabort-no-r0.c | 12 + gcc/testsuite/gfortran.dg/associated_target_6.f03 | 49 + gcc/testsuite/gfortran.dg/class_allocate_20.f90 | 32 + gcc/testsuite/gfortran.dg/ieee/ieee_7.f90 | 12 +- gcc/testsuite/gfortran.dg/ieee/large_1.f90 | 138 + gcc/testsuite/jit.dg/test-benchmark.c | 20 +- ...y.c => test-error-gcc_jit_timer_pop-mismatch.c} | 10 +- ...y.c => test-error-gcc_jit_timer_pop-too-many.c} | 9 +- gcc/timevar.c | 245 +- gcc/timevar.def | 2 + gcc/timevar.h | 35 +- gcc/toplev.c | 18 +- gcc/toplev.h | 4 +- gcc/tree-if-conv.c | 14 +- gcc/tree-parloops.c | 49 +- gcc/tree-ssa-threadupdate.c | 19 +- gcc/tree-ssa-uninit.c | 71 +- gcc/tree-vect-data-refs.c | 35 +- gcc/tree-vect-loop.c | 6 +- gcc/tree-vect-stmts.c | 28 +- gcc/tree-vectorizer.h | 15 +- gcc/tree.c | 69 + gcc/tree.h | 2 + gcc/vtable-verify.c | 92 +- gcc/vtable-verify.h | 5 + libcpp/po/ChangeLog | 4 + libcpp/po/sv.po | 6 +- libgfortran/ChangeLog | 14 + libgfortran/config/fpu-387.h | 37 +- libgfortran/gfortran.map | 10 + libgfortran/ieee/ieee_arithmetic.F90 | 760 +++-- libgfortran/ieee/ieee_exceptions.F90 | 30 +- libgfortran/ieee/ieee_helper.c | 18 + libgo/Makefile.am | 11 + libgo/Makefile.in | 5 + libgo/go/syscall/socket_linux.go | 5 - libgo/go/syscall/socket_linux_ppc64x_type.go | 14 + libgo/go/syscall/socket_linux_type.go | 14 + libgo/runtime/mprof.goc | 6 +- libgo/testsuite/gotest | 2 +- libgomp/ChangeLog | 11 + libgomp/plugin/plugin-nvptx.c | 90 +- libstdc++-v3/ChangeLog | 5 + libstdc++-v3/include/bits/range_access.h | 14 +- libvtv/ChangeLog | 11 + libvtv/testsuite/Makefile.am | 16 +- libvtv/testsuite/Makefile.in | 14 +- libvtv/testsuite/lib/libvtv.exp | 37 +- libvtv/vtv_malloc.cc | 2 +- libvtv/vtv_rts.cc | 7 +- 208 files changed, 11300 insertions(+), 4165 deletions(-) create mode 100644 gcc/c-family/c-indentation.h create mode 100644 gcc/config/aarch64/aarch64-c.c create mode 100644 gcc/jit/docs/topics/performance.rst create mode 100644 gcc/testsuite/g++.dg/Wframe-address-in-Wall.C create mode 100644 gcc/testsuite/g++.dg/Wframe-address.C create mode 100644 gcc/testsuite/g++.dg/Wno-frame-address.C create mode 100644 gcc/testsuite/g++.dg/cpp1y/var-templ34.C create mode 100644 gcc/testsuite/g++.dg/ubsan/pr66977.C create mode 100644 gcc/testsuite/gcc.dg/Wframe-address-in-Wall.c create mode 100644 gcc/testsuite/gcc.dg/Wframe-address.c create mode 100644 gcc/testsuite/gcc.dg/Wno-frame-address.c create mode 100644 gcc/testsuite/gcc.dg/pr66314.c create mode 100644 gcc/testsuite/gcc.dg/pr66899.c create mode 100644 gcc/testsuite/gcc.dg/pr67043.c create mode 100644 gcc/testsuite/gcc.dg/pr67077.c create mode 100644 gcc/testsuite/gcc.dg/pr67088.c delete mode 100644 gcc/testsuite/gcc.target/aarch64/arm_neon-nosimd-error.c create mode 100644 gcc/testsuite/gcc.target/aarch64/csel_bfx_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/csel_imms_inc_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/pragma_cpp_predefs_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_10.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_11.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_12.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_13.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_14.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_15.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_2.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_3.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_4.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_5.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_6.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_7.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_8.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_9.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_crypto_ice_1.c create mode 100644 gcc/testsuite/gcc.target/arm/mincmp.c create mode 100644 gcc/testsuite/gcc.target/arm/pr43404.c create mode 100644 gcc/testsuite/gcc.target/arm/pr48470.c create mode 100644 gcc/testsuite/gcc.target/arm/pr64744-1.c create mode 100644 gcc/testsuite/gcc.target/arm/pr64744-2.c create mode 100644 gcc/testsuite/gcc.target/arm/vnmul-1.c create mode 100644 gcc/testsuite/gcc.target/arm/vnmul-2.c create mode 100644 gcc/testsuite/gcc.target/arm/vnmul-3.c create mode 100644 gcc/testsuite/gcc.target/arm/vnmul-4.c create mode 100644 gcc/testsuite/gcc.target/powerpc/htm-tabort-no-r0.c create mode 100644 gcc/testsuite/gfortran.dg/associated_target_6.f03 create mode 100644 gcc/testsuite/gfortran.dg/class_allocate_20.f90 create mode 100644 gcc/testsuite/gfortran.dg/ieee/large_1.f90 copy gcc/testsuite/jit.dg/{test-empty.c => test-error-gcc_jit_timer_pop-mismatch.c} (50%) copy gcc/testsuite/jit.dg/{test-empty.c => test-error-gcc_jit_timer_pop-too-many.c} (54%) create mode 100644 libgo/go/syscall/socket_linux_ppc64x_type.go create mode 100644 libgo/go/syscall/socket_linux_type.go -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] 01/01: Add __builtin_stack_top

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a commit to branch hjl/pr66960/x86 in repository gcc. commit 0e48982ac9525fad385dc8d4810d11641977a9dc Author: H.J. Lu <hjl.tools(a)gmail.com> Date: Tue Jul 21 14:32:09 2015 -0700 Add __builtin_stack_top When __builtin_frame_address is used to retrieve the address of the function stack frame, the frame pointer register is required, which wastes one register and 2 instructions. For x86-32, one less register means significant negative impact on performance. This patch adds a new builtin function, __builtin_stack_top, to x86 backend. It returns the stack address when the function is called. gcc/ PR target/66960 * config/i386/i386.c (ix86_expand_prologue): Sorry if DRAP is used and the stack address has been taken. (ix86_builtins): Add IX86_BUILTIN_STACK_TOP. (ix86_init_mmx_sse_builtins): Add __builtin_stack_top. (ix86_expand_builtin): Handle IX86_BUILTIN_STACK_TOP. * config/i386/i386.h (machine_function): Add stack_top_taken. * doc/extend.texi: Document __builtin_stack_top. gcc/testsuite/ PR target/66960 * gcc.target/i386/pr66960-1.c: New test. * gcc.target/i386/pr66960-2.c: Likewise. * gcc.target/i386/pr66960-3.c: Likewise. * gcc.target/i386/pr66960-4.c: Likewise. * gcc.target/i386/pr66960-5.c: Likewise. --- gcc/config/i386/i386.c | 28 ++++++++++++++++++++++++++ gcc/config/i386/i386.h | 4 ++++ gcc/doc/extend.texi | 6 ++++++ gcc/testsuite/gcc.target/i386/pr66960-1.c | 33 +++++++++++++++++++++++++++++++ gcc/testsuite/gcc.target/i386/pr66960-2.c | 33 +++++++++++++++++++++++++++++++ gcc/testsuite/gcc.target/i386/pr66960-3.c | 17 ++++++++++++++++ gcc/testsuite/gcc.target/i386/pr66960-4.c | 21 ++++++++++++++++++++ gcc/testsuite/gcc.target/i386/pr66960-5.c | 21 ++++++++++++++++++++ 8 files changed, 163 insertions(+) diff --git a/gcc/config/i386/i386.c b/gcc/config/i386/i386.c index 1b0cade..887fa36 100644 --- a/gcc/config/i386/i386.c +++ b/gcc/config/i386/i386.c @@ -11575,6 +11575,12 @@ ix86_expand_prologue (void) { int align_bytes = crtl->stack_alignment_needed / BITS_PER_UNIT; + /* Can't use DRAP if the stack address has been taken. */ + if (cfun->machine->stack_top_taken) + sorry ("%<__builtin_stack_top%> not supported with stack" + " realignment. This may be worked around by adding" + " -maccumulate-outgoing-args."); + /* Only need to push parameter pointer reg if it is caller saved. */ if (!call_used_regs[REGNO (crtl->drap_reg)]) { @@ -30741,6 +30747,9 @@ enum ix86_builtins IX86_BUILTIN_READ_FLAGS, IX86_BUILTIN_WRITE_FLAGS, + /* Get the stack address when the function is called. */ + IX86_BUILTIN_STACK_TOP, + IX86_BUILTIN_MAX }; @@ -34353,6 +34362,10 @@ ix86_init_mmx_sse_builtins (void) def_builtin (OPTION_MASK_ISA_MWAITX, "__builtin_ia32_mwaitx", VOID_FTYPE_UNSIGNED_UNSIGNED_UNSIGNED, IX86_BUILTIN_MWAITX); + /* Get the stack address when the function is called. */ + def_builtin (0, "__builtin_stack_top", + PVOID_FTYPE_VOID, IX86_BUILTIN_STACK_TOP); + /* Add FMA4 multi-arg argument instructions */ for (i = 0, d = bdesc_multi_arg; i < ARRAY_SIZE (bdesc_multi_arg); i++, d++) { @@ -40228,6 +40241,21 @@ addcarryx: emit_insn (gen_xabort (op0)); return 0; + case IX86_BUILTIN_STACK_TOP: + cfun->machine->stack_top_taken = true; + + if (!target + || GET_MODE (target) != Pmode + || !register_operand (target, Pmode)) + target = gen_reg_rtx (Pmode); + + /* After the prologue, stack top is at -WORD(AP) in the current + frame. */ + emit_insn (gen_rtx_SET (target, + plus_constant (Pmode, arg_pointer_rtx, + -UNITS_PER_WORD))); + return target; + default: break; } diff --git a/gcc/config/i386/i386.h b/gcc/config/i386/i386.h index 7bd23ec..3781a22 100644 --- a/gcc/config/i386/i386.h +++ b/gcc/config/i386/i386.h @@ -2492,6 +2492,10 @@ struct GTY(()) machine_function { /* If true, it is safe to not save/restore DRAP register. */ BOOL_BITFIELD no_drap_save_restore : 1; + /* If true, the stack address of the current function has been + taken. */ + BOOL_BITFIELD stack_top_taken : 1; + /* If true, there is register available for argument passing. This is used only in ix86_function_ok_for_sibcall by 32-bit to determine if there is scratch register available for indirect sibcall. In diff --git a/gcc/doc/extend.texi b/gcc/doc/extend.texi index 2a47943..8023871 100644 --- a/gcc/doc/extend.texi +++ b/gcc/doc/extend.texi @@ -16807,6 +16807,12 @@ The following built-in function is always available. @item void __builtin_ia32_pause (void) Generates the @code{pause} machine instruction with a compiler memory barrier. + +@item void *__builtin_stack_top (void) +This function is similar to calling @code{__builtin_frame_address} +with a value of @code{0}, but it returns the stack address when the +function is called. Unlike @code{__builtin_frame_address}, the frame +pointer register isn't required. @end table The following floating-point built-in functions are made available in the diff --git a/gcc/testsuite/gcc.target/i386/pr66960-1.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..477d90d --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-1.c @@ -0,0 +1,33 @@ +/* { dg-do compile { target *-*-linux* } } */ +/* { dg-options "-O2 -fomit-frame-pointer" { target { lp64 } } } */ +/* { dg-options "-O2 -fomit-frame-pointer -maddress-mode=short" { target { x32 } } } */ +/* { dg-options "-O2 -fomit-frame-pointer -miamcu -fno-pic" { target { ia32 } } } */ + +extern char **environ; +extern void exit (int status); +extern int main (long argc, char **argv, char **envp); + +void +_start (void) +{ + void *argc_p = __builtin_stack_top (); + char **argv = (char **) (argc_p + sizeof (void *)); + long argc = *(long *) argc_p; + int status; + + environ = argv + argc + 1; + + status = main (argc, argv, environ); + + exit (status); +} + +/* { dg-final { scan-assembler "movq\[ \t\]8\\(%rsp\\), %rdi" { target lp64 } } } */ +/* { dg-final { scan-assembler "leaq\[ \t\]16\\(%rsp\\), %rsi" { target lp64 } } } */ +/* { dg-final { scan-assembler "leaq\[ \t\]24\\(%rsp,%rdi,8\\), %rdx" { target lp6 [...] +/* { dg-final { scan-assembler "movl\[ \t\]8\\(%esp\\), %edi" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]12\\(%rsp\\), %esi" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]4\\(%rsi,%rdi,4\\), %edx" { target x32 [...] +/* { dg-final { scan-assembler "movl\[ \t\]\\(%esp\\), %eax" { target ia32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]4\\(%esp\\), %edx" { target ia32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]8\\(%esp,%eax,4\\), %ecx" { target ia32 [...] diff --git a/gcc/testsuite/gcc.target/i386/pr66960-2.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..b9dbde2 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-2.c @@ -0,0 +1,33 @@ +/* { dg-do compile { target *-*-linux* } } */ +/* { dg-options "-O2 -fno-omit-frame-pointer" { target { lp64 } } } */ +/* { dg-options "-O2 -fno-omit-frame-pointer -maddress-mode=short" { target { x32 [...] +/* { dg-options "-O2 -fno-omit-frame-pointer -miamcu" { target { ia32 } } } */ + +extern char **environ; +extern void exit (int status); +extern int main (long argc, char **argv, char **envp); + +void +_start (void) +{ + void *argc_p = __builtin_stack_top (); + char **argv = (char **) (argc_p + sizeof (void *)); + long argc = *(long *) argc_p; + int status; + + environ = argv + argc + 1; + + status = main (argc, argv, environ); + + exit (status); +} + +/* { dg-final { scan-assembler "movq\[ \t\]8\\(%rbp\\), %rdi" { target lp64 } } } */ +/* { dg-final { scan-assembler "leaq\[ \t\]16\\(%rbp\\), %rsi" { target lp64 } } } */ +/* { dg-final { scan-assembler "leaq\[ \t\]24\\(%rbp,%rdi,8\\), %rdx" { target lp6 [...] +/* { dg-final { scan-assembler "movl\[ \t\]8\\(%ebp\\), %edi" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]12\\(%rbp\\), %esi" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]4\\(%rsi,%rdi,4\\), %edx" { target x32 [...] +/* { dg-final { scan-assembler "movl\[ \t\]4\\(%ebp\\), %eax" { target ia32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]8\\(%ebp\\), %edx" { target ia32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]12\\(%ebp,%eax,4\\), %ecx" { target ia3 [...] diff --git a/gcc/testsuite/gcc.target/i386/pr66960-3.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..48cf25e --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-3.c @@ -0,0 +1,17 @@ +/* { dg-do compile { target *-*-linux* } } */ +/* { dg-options "-O2 -mno-accumulate-outgoing-args" { target { lp64 } } } */ +/* { dg-options "-O2 -mno-accumulate-outgoing-args -maddress-mode=short" { target [...] +/* { dg-options "-O2 -mno-accumulate-outgoing-args -miamcu" { target { ia32 } } } */ + +extern void abort (void); +extern int check_int (int *i, int align); +typedef int aligned __attribute__((aligned(64))); + +void * +foo (void) +{ + aligned j; + if (check_int (&j, __alignof__(j)) != j) + abort (); + return __builtin_stack_top (); +} /* { dg-message "sorry, unimplemented: .__builtin_stack_top. not supported" } */ diff --git a/gcc/testsuite/gcc.target/i386/pr66960-4.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..44c0b26 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-4.c @@ -0,0 +1,21 @@ +/* { dg-do compile { target *-*-linux* } } */ +/* { dg-options "-O2 -maccumulate-outgoing-args" { target { lp64 } } } */ +/* { dg-options "-O2 -maccumulate-outgoing-args -maddress-mode=short" { target { x [...] +/* { dg-options "-O2 -maccumulate-outgoing-args -miamcu" { target { ia32 } } } */ + +extern void abort (void); +extern int check_int (int *i, int align); +typedef int aligned __attribute__((aligned(64))); + +void * +foo (void) +{ + aligned j; + if (check_int (&j, __alignof__(j)) != j) + abort (); + return __builtin_stack_top (); +} + +/* { dg-final { scan-assembler "leaq\[ \t\]8\\(%rbp\\), %rax" { target lp64 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]8\\(%rbp\\), %eax" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]4\\(%ebp\\), %eax" { target ia32 } } } */ diff --git a/gcc/testsuite/gcc.target/i386/pr66960-5.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..d449437 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-5.c @@ -0,0 +1,21 @@ +/* { dg-do link } */ +/* { dg-options "-O" } */ + +extern void link_error (void); + +__attribute__ ((noinline, noclone)) +void +foo (void) +{ + void **p = __builtin_stack_top (); + void *ra = __builtin_return_address (0); + if (*p != ra) + link_error (); +} + +int +main (void) +{ + foo (); + return 0; +} -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] branch hjl/pr66960/generic updated (03ff139 -> 267982f)

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a change to branch hjl/pr66960/generic in repository gcc. discards 03ff139 Add __builtin_stack_top adds e880695 * c-pretty-print.c (unary_expression) [INDIRECT_REF]: Don't [...] adds a8a727a Use lowpart_subreg instead of simplify_gen_subreg adds be3783f [V850] Hookize LIBCALL_VALUE adds fa7dcde Daily bump. adds eb37590 * sv.po: Update. adds 2aa16f1 * sv.po: Update. adds 86a932e Don't cancel loop tree in parloops adds 58c4f49 * go-lang.c (go_langhook_init_options_struct): Don't set x_fl [...] adds b1cd5ae 2015-07-31 Richard Biener <rguenther(a)suse.de> adds 5d262bd Refactoring masked built-in decls to use proper mask type. adds 56b4132 2015-07-31 Richard Biener <rguenther(a)suse.de> adds 4150a43 PR sanitizer/66977 * typeck.c (get_member_function_from_ptr [...] adds 2d86a0e PR target/66870 * config/rs6000/rs6000.c (machine_function) [...] adds 245894e * config/m32r/m32r.c (m32r_attribute_identifier): New functi [...] adds 530bb69 [ARM][2/3] Make if_neg_move and if_move_neg into insn_and_split adds 8b3c974 compiler: Don't allow builtin function values. adds ad10d66 * MAINTAINERS (nvptx): Add self. adds 8289950 compiler: Update unicode tables. adds 6d69611 compiler: Check the type in function declarations. adds 4d51316 PR target/67049 * config/sh/sh.md (GOTaddr2picreg): Fix typo [...] adds 5f1045b compiler: Report errors for malformed builtin calls. adds 4691a53 Daily bump. adds 5955834 Allow non-overflow ops in reductions adds 814b1ca 2015-08-01 Paul Thomas <pault(a)gcc.gnu.org> adds 6ffea52 Daily bump. adds 68a98a7 Fix PR 66521 adds 3d5db02 2015-08-01 Michael Collison <michael.collison(a)linaro.org [...] adds 9255be0 Refactor entry point to -Wmisleading-indentation adds f95bfdd Remove is_first_nonwhitespace_on_line(), instead improve get_ [...] adds 17afcef Improve -Wmisleading-indentation heuristics adds 5b252e9 gcc/ChangeLog 2015-07-28 Martin Sebor <msebor(a)redhat.com> adds 408da55 Daily bump. adds d1a8d2a * MAINTAINERS (loop ivopts): Add the entry and myself. adds 9dd88d4 2015-08-03 Richard Biener <rguenther(a)suse.de> adds 535bc42 2015-08-03 Richard Biener <rguenther(a)suse.de> adds f11d6df 2015-08-03 Richard Biener <rguenther(a)suse.de> adds 5a0909a 2015-08-03 Richard Biener <rguenther(a)suse.de> adds a929e01 [RTL-ifcvt] Improve conditional select ops on immediates adds c63a11d Fix random class_allocate_18.f90 failure adds 6cb6651 [ARM] PR target/66731 Fix vnmul insn with -frounding-math adds 605922a gcc/ChangeLog: adds 5ba71b3 2015-08-03 Richard Biener <rguenther(a)suse.de> adds ec66e09 2015-08-03 Richard Biener <rguenther(a)suse.de> adds 05999bf 2015-08-03 Richard Biener <rguenther(a)suse.de> adds c909938 PR c/67088 * c-decl.c (check_bitfield_type_and_width): Add [...] adds 0686247 Avoid recomputing the defining predicate chains for the same PHI adds 18c03b4 * Makefile.in (OBJS): Put gimple-match.o and generic-match.o first. adds 6cf098e PR libstdc++/67078 * include/bits/range_access.h (size, emp [...] adds 51ea8bc PR middle-end/66314 PR gcov-profile/66899 * tree-ssa-threa [...] adds ddfc9c6 2015-08-03 Steven G. Kargl <kargl(a)gcc.gnu.org> adds 1d9f8a1 Add a testcase for PR tree-optimization/67077 adds 97d09b3 2015-08-03 Michael Meissner <meissner(a)linux.vnet.ibm.com> adds eedb218 PR target/67060 * config/pa/pa.md (call_reg_64bit): Remove [...] adds 7dcad76 PR go/67101 adds fc2edda libgo/testsuite: kill sleep process in gotest adds e6d1c8b compiler: Don't make erroneous type descriptors. adds f27f157 PR middle-end/64744 PR middle-end/48470 PR middle-end/4340 [...] adds cb96a11 compiler: Don't allow multiple function declarations. adds 17c0b84 Refactoring of timevar API adds 8ad9537 gcc/ * config/rs6000/htm.md (tabort.): Restrict the source o [...] adds e487326 syscall: RawSockaddr fix for ppc64, ppc64le adds 2d72810 Daily bump. adds fae2de1 * plugin/plugin-nvptx.c: Don't include dlfcn.h. (cuda_errli [...] adds ff429db 2015-08-04 Thomas Preud'homme <thomas.preudhomme(a)arm.com> adds 1b02261 runtime: initialize variable to avoid compiler warning adds 207b828 * tree-if-conv.c: Fix various typos in comments. * tree-vec [...] adds c53bd1d PR fortran/64022 adds e198177 * config/fpu-387.h (get_fpu_trap_exceptions): Add temporary [...] adds 693a749 * config/fpu-387.h: Remove unwanted whitespace. adds 38758f3 2015-08-04 Richard Biener <rguenther(a)suse.de> adds 245cad5 [AArch64][1/14] Add ident field to struct processor adds 9356ca1 [AArch64][2/14] Refactor arches handling, add arch enum identifier adds 50021c3 [AArch64][3/14] Refactor option override code adds 36d84ec * config/i386/i386.c (ix86_expand_int_movcc): Check result o [...] adds ee92bc9 [AArch64][4/14] Create TARGET_FIX_ERR_A53_835769 and use that [...] adds 3f215f2 [AArch64][5/14] Make flag_omit_leaf_frame_pointer intialize t [...] adds a0db861 [AArch64][6/14] Implement TARGET_OPTION_SAVE/TARGET_OPTION_RESTORE adds f59387a [AArch64][7/14] Implement TARGET_SET_CURRENT_FUNCTION adds aadb8e1 [AArch64][8/14] Implement TARGET_OPTION_VALID_ATTRIBUTE_P adds b0269e3 [AArch64][9/14] Implement TARGET_CAN_INLINE_P adds 26db532 [AArch64][10/14] Implement target pragmas adds dad9014 [AArch64][11/14] Re-layout SIMD builtin types on builtin expansion adds b65ae63 [AArch64][12/14] Target attributes and target pragmas tests adds 5de59ee [doc][13/14] Document AArch64 target attributes and pragmas adds cd33329 [AArch64][14/14] Reuse target_option_current_node when passin [...] adds d8cc4c5 2015-08-04 Paolo Carlini <paolo.carlini(a)oracle.com> adds 4757c55 Compile IAMCU tests with -fno-pie -no-pie new 267982f Add __builtin_stack_top This update added new revisions after undoing existing revisions. That is to say, some revisions that were in the old version of the branch are not in the new version. This situation occurs when a user --force pushes a change and generates a repository containing something like this: * -- * -- B -- O -- O -- O (03ff139) \ N -- N -- N refs/heads/hjl/pr66960/generic (267982f) You should already have received notification emails for all of the O revisions, and so the following emails describe only the N revisions from the common base, B. Any revisions marked "omits" are not gone; other references still refer to them. Any revisions marked "discards" are gone forever. The 1 revisions listed above as "new" are entirely new to this repository and will be described in separate emails. The revisions listed as "adds" were already present in the repository and have only been added to this reference. Summary of changes: ChangeLog | 8 + MAINTAINERS | 2 + gcc/ChangeLog | 1107 ++++++- gcc/DATESTAMP | 2 +- gcc/Makefile.in | 15 +- gcc/builtins.c | 28 +- gcc/c-family/ChangeLog | 31 + gcc/c-family/c-common.h | 7 - gcc/c-family/c-indentation.c | 299 +- gcc/c-family/c-indentation.h | 52 + gcc/c-family/c-pretty-print.c | 8 +- gcc/c-family/c.opt | 4 + gcc/c/ChangeLog | 19 + gcc/c/c-decl.c | 24 +- gcc/c/c-parser.c | 81 +- gcc/cfgexpand.c | 30 +- gcc/combine.c | 4 +- gcc/common/config/aarch64/aarch64-common.c | 19 +- gcc/config.gcc | 2 + gcc/config/aarch64/aarch64-arches.def | 15 +- gcc/config/aarch64/aarch64-builtins.c | 39 +- gcc/config/aarch64/aarch64-c.c | 203 ++ gcc/config/aarch64/aarch64-cores.def | 22 +- gcc/config/aarch64/aarch64-elf-raw.h | 2 +- gcc/config/aarch64/aarch64-linux.h | 2 +- gcc/config/aarch64/aarch64-opts.h | 9 + gcc/config/aarch64/aarch64-protos.h | 14 + gcc/config/aarch64/aarch64.c | 1486 +++++++-- gcc/config/aarch64/aarch64.h | 104 +- gcc/config/aarch64/aarch64.opt | 35 +- gcc/config/aarch64/arm_acle.h | 10 +- gcc/config/aarch64/arm_neon.h | 19 +- gcc/config/aarch64/driver-aarch64.c | 8 +- gcc/config/aarch64/t-aarch64 | 5 + gcc/config/arm/arm.c | 9 +- gcc/config/arm/arm.md | 98 +- gcc/config/arm/vfp.md | 23 + gcc/config/i386/i386-builtin-types.def | 864 +++--- gcc/config/i386/i386.c | 3191 ++++++++++---------- gcc/config/m32r/m32r.c | 10 + gcc/config/pa/pa.md | 6 - gcc/config/rs6000/altivec.md | 21 +- gcc/config/rs6000/constraints.md | 12 + gcc/config/rs6000/htm.md | 2 +- gcc/config/rs6000/predicates.md | 8 + gcc/config/rs6000/rs6000.c | 15 + gcc/config/rs6000/rs6000.h | 2 + gcc/config/rs6000/vector.md | 28 +- gcc/config/rs6000/vsx.md | 143 +- gcc/config/sh/sh.md | 2 +- gcc/config/v850/v850.c | 15 +- gcc/config/v850/v850.h | 6 - gcc/config/v850/v850.md | 1 + gcc/configure | 41 +- gcc/configure.ac | 26 + gcc/cp/ChangeLog | 28 + gcc/cp/mangle.c | 8 + gcc/cp/parser.c | 100 +- gcc/cp/typeck.c | 7 + gcc/doc/extend.texi | 168 +- gcc/doc/invoke.texi | 9 +- gcc/doc/md.texi | 19 +- gcc/emit-rtl.c | 5 +- gcc/expr.c | 14 +- gcc/fold-const.c | 50 - gcc/fortran/ChangeLog | 23 + gcc/fortran/class.c | 1 + gcc/fortran/simplify.c | 79 +- gcc/fortran/trans-expr.c | 10 +- gcc/fortran/trans-intrinsic.c | 2 + gcc/function.c | 6 +- gcc/genmatch.c | 432 ++- gcc/gimple-fold.c | 116 +- gcc/gimple-match-head.c | 35 +- gcc/go/ChangeLog | 6 + gcc/go/go-lang.c | 9 +- gcc/go/gofrontend/MERGE | 2 +- gcc/go/gofrontend/expressions.cc | 3 +- gcc/go/gofrontend/gogo.cc | 65 +- gcc/go/gofrontend/gogo.h | 4 + gcc/go/gofrontend/lex.cc | 487 +-- gcc/go/gofrontend/parse.cc | 5 +- gcc/graphite-sese-to-poly.c | 7 +- gcc/ifcvt.c | 63 +- gcc/jit/ChangeLog | 63 + gcc/jit/docs/_build/texinfo/libgccjit.texi | 892 ++++-- gcc/jit/docs/topics/compatibility.rst | 21 + gcc/jit/docs/topics/contexts.rst | 3 +- gcc/jit/docs/topics/index.rst | 1 + gcc/jit/docs/topics/performance.rst | 240 ++ gcc/jit/jit-playback.c | 11 +- gcc/jit/jit-playback.h | 2 + gcc/jit/jit-recording.c | 2 + gcc/jit/jit-recording.h | 7 + gcc/jit/libgccjit++.h | 117 + gcc/jit/libgccjit.c | 109 + gcc/jit/libgccjit.h | 84 + gcc/jit/libgccjit.map | 12 + gcc/loop-invariant.c | 3 + gcc/loop-iv.c | 11 - gcc/main.c | 2 +- gcc/match.pd | 33 +- gcc/omp-low.c | 32 +- gcc/po/ChangeLog | 4 + gcc/po/sv.po | 128 +- gcc/rtl.h | 5 +- gcc/simplify-rtx.c | 15 +- gcc/testsuite/ChangeLog | 153 + .../c-c++-common/Wmisleading-indentation.c | 166 + gcc/testsuite/g++.dg/Wframe-address-in-Wall.C | 14 + gcc/testsuite/g++.dg/Wframe-address.C | 70 + gcc/testsuite/g++.dg/Wno-frame-address.C | 6 + gcc/testsuite/g++.dg/cpp1y/var-templ34.C | 20 + gcc/testsuite/g++.dg/ubsan/pr66977.C | 27 + gcc/testsuite/gcc.dg/Wframe-address-in-Wall.c | 14 + gcc/testsuite/gcc.dg/Wframe-address.c | 54 + gcc/testsuite/gcc.dg/Wno-frame-address.c | 6 + gcc/testsuite/gcc.dg/autopar/reduc-2char.c | 10 +- gcc/testsuite/gcc.dg/autopar/reduc-2short.c | 10 +- gcc/testsuite/gcc.dg/autopar/reduc-8.c | 7 +- gcc/testsuite/gcc.dg/pr66314.c | 33 + gcc/testsuite/gcc.dg/pr66899.c | 41 + gcc/testsuite/gcc.dg/pr67043.c | 32 + gcc/testsuite/gcc.dg/pr67077.c | 20 + gcc/testsuite/gcc.dg/pr67088.c | 18 + gcc/testsuite/gcc.dg/vect/trapv-vect-reduc-4.c | 2 +- .../gcc.target/aarch64/arm_neon-nosimd-error.c | 11 - .../gcc.target/aarch64/cpu-diagnostics-3.c | 2 +- gcc/testsuite/gcc.target/aarch64/csel_bfx_1.c | 11 + gcc/testsuite/gcc.target/aarch64/csel_imms_inc_1.c | 42 + .../gcc.target/aarch64/pragma_cpp_predefs_1.c | 255 ++ gcc/testsuite/gcc.target/aarch64/target_attr_1.c | 14 + gcc/testsuite/gcc.target/aarch64/target_attr_10.c | 16 + gcc/testsuite/gcc.target/aarch64/target_attr_11.c | 13 + gcc/testsuite/gcc.target/aarch64/target_attr_12.c | 13 + gcc/testsuite/gcc.target/aarch64/target_attr_13.c | 16 + gcc/testsuite/gcc.target/aarch64/target_attr_14.c | 20 + gcc/testsuite/gcc.target/aarch64/target_attr_15.c | 15 + gcc/testsuite/gcc.target/aarch64/target_attr_2.c | 39 + gcc/testsuite/gcc.target/aarch64/target_attr_3.c | 34 + gcc/testsuite/gcc.target/aarch64/target_attr_4.c | 30 + gcc/testsuite/gcc.target/aarch64/target_attr_5.c | 20 + gcc/testsuite/gcc.target/aarch64/target_attr_6.c | 20 + gcc/testsuite/gcc.target/aarch64/target_attr_7.c | 24 + gcc/testsuite/gcc.target/aarch64/target_attr_8.c | 22 + gcc/testsuite/gcc.target/aarch64/target_attr_9.c | 22 + .../gcc.target/aarch64/target_attr_crypto_ice_1.c | 21 + gcc/testsuite/gcc.target/arm/mincmp.c | 20 + gcc/testsuite/gcc.target/arm/pr43404.c | 10 + gcc/testsuite/gcc.target/arm/pr48470.c | 11 + gcc/testsuite/gcc.target/arm/pr64744-1.c | 40 + gcc/testsuite/gcc.target/arm/pr64744-2.c | 13 + gcc/testsuite/gcc.target/arm/vnmul-1.c | 18 + gcc/testsuite/gcc.target/arm/vnmul-2.c | 18 + gcc/testsuite/gcc.target/arm/vnmul-3.c | 18 + gcc/testsuite/gcc.target/arm/vnmul-4.c | 18 + gcc/testsuite/gcc.target/i386/iamcu/abi-iamcu.exp | 2 +- gcc/testsuite/gcc.target/i386/pr66960-1.c | 2 +- .../gcc.target/powerpc/htm-tabort-no-r0.c | 12 + gcc/testsuite/gfortran.dg/associated_target_6.f03 | 49 + gcc/testsuite/gfortran.dg/class_allocate_20.f90 | 32 + gcc/testsuite/gfortran.dg/ieee/ieee_7.f90 | 12 +- gcc/testsuite/gfortran.dg/ieee/large_1.f90 | 138 + gcc/testsuite/jit.dg/test-benchmark.c | 20 +- ...y.c => test-error-gcc_jit_timer_pop-mismatch.c} | 10 +- ...y.c => test-error-gcc_jit_timer_pop-too-many.c} | 9 +- gcc/timevar.c | 245 +- gcc/timevar.def | 2 + gcc/timevar.h | 35 +- gcc/toplev.c | 18 +- gcc/toplev.h | 4 +- gcc/tree-if-conv.c | 14 +- gcc/tree-parloops.c | 49 +- gcc/tree-ssa-threadupdate.c | 19 +- gcc/tree-ssa-uninit.c | 71 +- gcc/tree-vect-data-refs.c | 35 +- gcc/tree-vect-loop.c | 6 +- gcc/tree-vect-stmts.c | 28 +- gcc/tree-vectorizer.h | 15 +- gcc/tree.c | 69 + gcc/tree.h | 2 + gcc/vtable-verify.c | 92 +- gcc/vtable-verify.h | 5 + libcpp/po/ChangeLog | 4 + libcpp/po/sv.po | 6 +- libgfortran/ChangeLog | 14 + libgfortran/config/fpu-387.h | 37 +- libgfortran/gfortran.map | 10 + libgfortran/ieee/ieee_arithmetic.F90 | 760 +++-- libgfortran/ieee/ieee_exceptions.F90 | 30 +- libgfortran/ieee/ieee_helper.c | 18 + libgo/Makefile.am | 11 + libgo/Makefile.in | 5 + libgo/go/syscall/socket_linux.go | 5 - libgo/go/syscall/socket_linux_ppc64x_type.go | 14 + libgo/go/syscall/socket_linux_type.go | 14 + libgo/runtime/mprof.goc | 6 +- libgo/testsuite/gotest | 2 +- libgomp/ChangeLog | 11 + libgomp/plugin/plugin-nvptx.c | 90 +- libstdc++-v3/ChangeLog | 5 + libstdc++-v3/include/bits/range_access.h | 14 +- libvtv/ChangeLog | 11 + libvtv/testsuite/Makefile.am | 16 +- libvtv/testsuite/Makefile.in | 14 +- libvtv/testsuite/lib/libvtv.exp | 37 +- libvtv/vtv_malloc.cc | 2 +- libvtv/vtv_rts.cc | 7 +- 208 files changed, 11300 insertions(+), 4165 deletions(-) create mode 100644 gcc/c-family/c-indentation.h create mode 100644 gcc/config/aarch64/aarch64-c.c create mode 100644 gcc/jit/docs/topics/performance.rst create mode 100644 gcc/testsuite/g++.dg/Wframe-address-in-Wall.C create mode 100644 gcc/testsuite/g++.dg/Wframe-address.C create mode 100644 gcc/testsuite/g++.dg/Wno-frame-address.C create mode 100644 gcc/testsuite/g++.dg/cpp1y/var-templ34.C create mode 100644 gcc/testsuite/g++.dg/ubsan/pr66977.C create mode 100644 gcc/testsuite/gcc.dg/Wframe-address-in-Wall.c create mode 100644 gcc/testsuite/gcc.dg/Wframe-address.c create mode 100644 gcc/testsuite/gcc.dg/Wno-frame-address.c create mode 100644 gcc/testsuite/gcc.dg/pr66314.c create mode 100644 gcc/testsuite/gcc.dg/pr66899.c create mode 100644 gcc/testsuite/gcc.dg/pr67043.c create mode 100644 gcc/testsuite/gcc.dg/pr67077.c create mode 100644 gcc/testsuite/gcc.dg/pr67088.c delete mode 100644 gcc/testsuite/gcc.target/aarch64/arm_neon-nosimd-error.c create mode 100644 gcc/testsuite/gcc.target/aarch64/csel_bfx_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/csel_imms_inc_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/pragma_cpp_predefs_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_10.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_11.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_12.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_13.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_14.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_15.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_2.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_3.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_4.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_5.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_6.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_7.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_8.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_9.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_crypto_ice_1.c create mode 100644 gcc/testsuite/gcc.target/arm/mincmp.c create mode 100644 gcc/testsuite/gcc.target/arm/pr43404.c create mode 100644 gcc/testsuite/gcc.target/arm/pr48470.c create mode 100644 gcc/testsuite/gcc.target/arm/pr64744-1.c create mode 100644 gcc/testsuite/gcc.target/arm/pr64744-2.c create mode 100644 gcc/testsuite/gcc.target/arm/vnmul-1.c create mode 100644 gcc/testsuite/gcc.target/arm/vnmul-2.c create mode 100644 gcc/testsuite/gcc.target/arm/vnmul-3.c create mode 100644 gcc/testsuite/gcc.target/arm/vnmul-4.c create mode 100644 gcc/testsuite/gcc.target/powerpc/htm-tabort-no-r0.c create mode 100644 gcc/testsuite/gfortran.dg/associated_target_6.f03 create mode 100644 gcc/testsuite/gfortran.dg/class_allocate_20.f90 create mode 100644 gcc/testsuite/gfortran.dg/ieee/large_1.f90 copy gcc/testsuite/jit.dg/{test-empty.c => test-error-gcc_jit_timer_pop-mismatch.c} (50%) copy gcc/testsuite/jit.dg/{test-empty.c => test-error-gcc_jit_timer_pop-too-many.c} (54%) create mode 100644 libgo/go/syscall/socket_linux_ppc64x_type.go create mode 100644 libgo/go/syscall/socket_linux_type.go -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] 01/01: Add __builtin_stack_top

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a commit to branch hjl/pr66960/generic in repository gcc. commit 267982f7c76cc6eece0dd7896555d27291f587ef Author: H.J. Lu <hjl.tools(a)gmail.com> Date: Tue Jul 21 14:32:09 2015 -0700 Add __builtin_stack_top When __builtin_frame_address is used to retrieve the address of the function stack frame, the frame pointer register is required, which wastes one register and 2 instructions. For x86-32, one less register means significant negative impact on performance. This patch adds a new builtin function, __builtin_stack_top. It returns the stack address when the function is called. This patch only enables __builtin_stack_top for x86 backend. Using __builtin_stack_top with other backends will lead to sorry, unimplemented: ‘__builtin_stack_top’ not supported on this target TARGET_STACK_TOP_RTX must be defined to enable __builtin_stack_top. default_stack_top_rtx may be extended to support more backends, including those with INITIAL_FRAME_ADDRESS_RTX. gcc/ PR target/66960 * builtin-types.def (BT_FN_PTR_VOID): New function type. * builtins.c (expand_builtin): Handle BUILT_IN_STACK_TOP. (is_simple_builtin): Likewise. * ipa-pure-const.c (special_builtin_state): Likewise. * builtins.def: Add BUILT_IN_STACK_TOP. * function.h (function): Add stack_top_taken. * target.def (stack_top_rtx): New target hook. * targhooks.c (default_stack_top_rtx): New. * targhooks.h (default_stack_top_rtx): Likewise. * config/i386/i386.c (ix86_expand_prologue): Sorry if DRAP is used and the stack address has been taken. (TARGET_STACK_TOP_RTX): New. * doc/extend.texi: Document __builtin_stack_top. * doc/tm.texi.in (TARGET_STACK_TOP_RTX): New. * doc/tm.texi: Regenerated. gcc/testsuite/ PR target/66960 * gcc.target/i386/pr66960-1.c: New test. * gcc.target/i386/pr66960-2.c: Likewise. * gcc.target/i386/pr66960-3.c: Likewise. * gcc.target/i386/pr66960-4.c: Likewise. * gcc.target/i386/pr66960-5.c: Likewise. --- gcc/builtin-types.def | 1 + gcc/builtins.c | 11 +++++++++++ gcc/builtins.def | 1 + gcc/config/i386/i386.c | 8 ++++++++ gcc/doc/extend.texi | 7 +++++++ gcc/doc/tm.texi | 5 +++++ gcc/doc/tm.texi.in | 2 ++ gcc/function.h | 3 +++ gcc/ipa-pure-const.c | 1 + gcc/target.def | 7 +++++++ gcc/targhooks.c | 9 +++++++++ gcc/targhooks.h | 3 +++ gcc/testsuite/gcc.target/i386/pr66960-1.c | 33 +++++++++++++++++++++++++++++++ gcc/testsuite/gcc.target/i386/pr66960-2.c | 33 +++++++++++++++++++++++++++++++ gcc/testsuite/gcc.target/i386/pr66960-3.c | 17 ++++++++++++++++ gcc/testsuite/gcc.target/i386/pr66960-4.c | 21 ++++++++++++++++++++ gcc/testsuite/gcc.target/i386/pr66960-5.c | 21 ++++++++++++++++++++ 17 files changed, 183 insertions(+) diff --git a/gcc/builtin-types.def b/gcc/builtin-types.def index 0e34531..2b6b5ab 100644 --- a/gcc/builtin-types.def +++ b/gcc/builtin-types.def @@ -177,6 +177,7 @@ DEF_FUNCTION_TYPE_1 (BT_FN_COMPLEX_LONGDOUBLE_LONGDOUBLE, BT_COMPLEX_LONGDOUBLE, BT_LONGDOUBLE) DEF_FUNCTION_TYPE_1 (BT_FN_PTR_UINT, BT_PTR, BT_UINT) DEF_FUNCTION_TYPE_1 (BT_FN_PTR_SIZE, BT_PTR, BT_SIZE) +DEF_FUNCTION_TYPE_1 (BT_FN_PTR_VOID, BT_PTR, BT_VOID) DEF_FUNCTION_TYPE_1 (BT_FN_INT_INT, BT_INT, BT_INT) DEF_FUNCTION_TYPE_1 (BT_FN_INT_UINT, BT_INT, BT_UINT) DEF_FUNCTION_TYPE_1 (BT_FN_INT_LONG, BT_INT, BT_LONG) diff --git a/gcc/builtins.c b/gcc/builtins.c index eb7b7b2..b257baf 100644 --- a/gcc/builtins.c +++ b/gcc/builtins.c @@ -6210,6 +6210,16 @@ expand_builtin (tree exp, rtx target, rtx subtarget, machine [...] case BUILT_IN_CONSTANT_P: return const0_rtx; + case BUILT_IN_STACK_TOP: + if (targetm.calls.stack_top_rtx) + { + cfun->stack_top_taken = true; + return targetm.calls.stack_top_rtx (); + } + else + sorry ("%<__builtin_stack_top%> not supported on this target"); + break; + case BUILT_IN_FRAME_ADDRESS: case BUILT_IN_RETURN_ADDRESS: return expand_builtin_frame_address (fndecl, exp); @@ -12399,6 +12409,7 @@ is_simple_builtin (tree decl) case BUILT_IN_RETURN: case BUILT_IN_AGGREGATE_INCOMING_ADDRESS: case BUILT_IN_FRAME_ADDRESS: + case BUILT_IN_STACK_TOP: case BUILT_IN_VA_END: case BUILT_IN_STACK_SAVE: case BUILT_IN_STACK_RESTORE: diff --git a/gcc/builtins.def b/gcc/builtins.def index 80e4a9c..62f0523 100644 --- a/gcc/builtins.def +++ b/gcc/builtins.def @@ -778,6 +778,7 @@ DEF_EXT_LIB_BUILTIN (BUILT_IN_FFSL, "ffsl", BT_FN_INT_LONG, [...] DEF_EXT_LIB_BUILTIN (BUILT_IN_FFSLL, "ffsll", BT_FN_INT_LONGLONG, ATTR_CONST_NO [...] DEF_EXT_LIB_BUILTIN (BUILT_IN_FORK, "fork", BT_FN_PID, ATTR_NOTHROW_LIST) DEF_GCC_BUILTIN (BUILT_IN_FRAME_ADDRESS, "frame_address", BT_FN_PTR_UINT, A [...] +DEF_GCC_BUILTIN (BUILT_IN_STACK_TOP, "stack_top", BT_FN_PTR_VOID, ATTR_NULL) /* [trans-mem]: Adjust BUILT_IN_TM_FREE if BUILT_IN_FREE is changed. */ DEF_LIB_BUILTIN (BUILT_IN_FREE, "free", BT_FN_VOID_PTR, ATTR_NOTHROW_LEAF_LIST) DEF_GCC_BUILTIN (BUILT_IN_FROB_RETURN_ADDR, "frob_return_addr", BT_FN_PTR_P [...] diff --git a/gcc/config/i386/i386.c b/gcc/config/i386/i386.c index 1b0cade..0c77363 100644 --- a/gcc/config/i386/i386.c +++ b/gcc/config/i386/i386.c @@ -11575,6 +11575,12 @@ ix86_expand_prologue (void) { int align_bytes = crtl->stack_alignment_needed / BITS_PER_UNIT; + /* Can't use DRAP if the stack address has been taken. */ + if (cfun->stack_top_taken) + sorry ("%<__builtin_stack_top%> not supported with stack" + " realignment. This may be worked around by adding" + " -maccumulate-outgoing-args."); + /* Only need to push parameter pointer reg if it is caller saved. */ if (!call_used_regs[REGNO (crtl->drap_reg)]) { @@ -52513,6 +52519,8 @@ ix86_operands_ok_for_move_multiple (rtx *operands, bool load, #define TARGET_UPDATE_STACK_BOUNDARY ix86_update_stack_boundary #undef TARGET_GET_DRAP_RTX #define TARGET_GET_DRAP_RTX ix86_get_drap_rtx +#undef TARGET_STACK_TOP_RTX +#define TARGET_STACK_TOP_RTX default_stack_top_rtx #undef TARGET_STRICT_ARGUMENT_NAMING #define TARGET_STRICT_ARGUMENT_NAMING hook_bool_CUMULATIVE_ARGS_true #undef TARGET_STATIC_CHAIN diff --git a/gcc/doc/extend.texi b/gcc/doc/extend.texi index 2a47943..834b7f4 100644 --- a/gcc/doc/extend.texi +++ b/gcc/doc/extend.texi @@ -8841,6 +8841,13 @@ option is in effect. Such calls should only be made in debugging situations. @end deftypefn +@deftypefn {Built-in Function} {void *} __builtin_stack_top (void) +This function is similar to calling @code{__builtin_frame_address} +with a value of @code{0}, but it returns the stack address when the +function is called. Unlike @code{__builtin_frame_address}, the frame +pointer register isn't required. +@end deftypefn + @node Vector Extensions @section Using Vector Instructions through Built-in Functions diff --git a/gcc/doc/tm.texi b/gcc/doc/tm.texi index f95646c..e2cd480 100644 --- a/gcc/doc/tm.texi +++ b/gcc/doc/tm.texi @@ -11483,6 +11483,11 @@ argument list due to stack realignment. Return @code{NULL [...] is needed. @end deftypefn +@deftypefn {Target Hook} rtx TARGET_STACK_TOP_RTX (void) +This hook should return an rtx for the stack address when the function +is called. +@end deftypefn + @deftypefn {Target Hook} bool TARGET_ALLOCATE_STACK_SLOTS_FOR_ARGS (void) When optimization is disabled, this hook indicates whether or not arguments should be allocated to stack slots. Normally, GCC allocates diff --git a/gcc/doc/tm.texi.in b/gcc/doc/tm.texi.in index 2383fb9..9167069 100644 --- a/gcc/doc/tm.texi.in +++ b/gcc/doc/tm.texi.in @@ -8181,6 +8181,8 @@ and the associated definitions of those functions. @hook TARGET_GET_DRAP_RTX +@hook TARGET_STACK_TOP_RTX + @hook TARGET_ALLOCATE_STACK_SLOTS_FOR_ARGS @hook TARGET_CONST_ANCHOR diff --git a/gcc/function.h b/gcc/function.h index e92c17c..dd1c38a 100644 --- a/gcc/function.h +++ b/gcc/function.h @@ -378,6 +378,9 @@ struct GTY(()) function { /* Set when the tail call has been identified. */ unsigned int tail_call_marked : 1; + + /* Set when the address of the stack top has been taken. */ + unsigned int stack_top_taken : 1; }; /* Add the decl D to the local_decls list of FUN. */ diff --git a/gcc/ipa-pure-const.c b/gcc/ipa-pure-const.c index 8fd8c36..2405082 100644 --- a/gcc/ipa-pure-const.c +++ b/gcc/ipa-pure-const.c @@ -480,6 +480,7 @@ special_builtin_state (enum pure_const_state_e *state, bool *looping, case BUILT_IN_CXA_END_CLEANUP: case BUILT_IN_EH_COPY_VALUES: case BUILT_IN_FRAME_ADDRESS: + case BUILT_IN_STACK_TOP: case BUILT_IN_APPLY: case BUILT_IN_APPLY_ARGS: *looping = false; diff --git a/gcc/target.def b/gcc/target.def index 4edc209..7a30f39 100644 --- a/gcc/target.def +++ b/gcc/target.def @@ -4525,6 +4525,13 @@ argument list due to stack realignment. Return @code{NULL} [...] is needed.", rtx, (void), NULL) +/* Get the stack address when the function is called. */ +DEFHOOK +(stack_top_rtx, + "This hook should return an rtx for the stack address when the function\n\ +is called.", + rtx, (void), NULL) + /* Return true if all function parameters should be spilled to the stack. */ DEFHOOK diff --git a/gcc/targhooks.c b/gcc/targhooks.c index 3eca47e..f188272 100644 --- a/gcc/targhooks.c +++ b/gcc/targhooks.c @@ -1926,4 +1926,13 @@ can_use_doloop_if_innermost (const widest_int &, const wides [...] return loop_depth == 1; } +/* Get the stack address when the function is called. After the + prologue, stack top is at -WORD(AP) in the current frame. */ + +rtx +default_stack_top_rtx (void) +{ + return plus_constant (Pmode, arg_pointer_rtx, -UNITS_PER_WORD); +} + #include "gt-targhooks.h" diff --git a/gcc/targhooks.h b/gcc/targhooks.h index 5ae991d..094a589 100644 --- a/gcc/targhooks.h +++ b/gcc/targhooks.h @@ -240,4 +240,7 @@ extern void default_setup_incoming_vararg_bounds (cumulative_ar [...] tree type ATTRIBUTE_UNUSED, int *pretend_arg_size ATTRIBUTE_UNUSED, int second_time ATTRIBUTE_UNUSED); + +extern rtx default_stack_top_rtx (void); + #endif /* GCC_TARGHOOKS_H */ diff --git a/gcc/testsuite/gcc.target/i386/pr66960-1.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..477d90d --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-1.c @@ -0,0 +1,33 @@ +/* { dg-do compile { target *-*-linux* } } */ +/* { dg-options "-O2 -fomit-frame-pointer" { target { lp64 } } } */ +/* { dg-options "-O2 -fomit-frame-pointer -maddress-mode=short" { target { x32 } } } */ +/* { dg-options "-O2 -fomit-frame-pointer -miamcu -fno-pic" { target { ia32 } } } */ + +extern char **environ; +extern void exit (int status); +extern int main (long argc, char **argv, char **envp); + +void +_start (void) +{ + void *argc_p = __builtin_stack_top (); + char **argv = (char **) (argc_p + sizeof (void *)); + long argc = *(long *) argc_p; + int status; + + environ = argv + argc + 1; + + status = main (argc, argv, environ); + + exit (status); +} + +/* { dg-final { scan-assembler "movq\[ \t\]8\\(%rsp\\), %rdi" { target lp64 } } } */ +/* { dg-final { scan-assembler "leaq\[ \t\]16\\(%rsp\\), %rsi" { target lp64 } } } */ +/* { dg-final { scan-assembler "leaq\[ \t\]24\\(%rsp,%rdi,8\\), %rdx" { target lp6 [...] +/* { dg-final { scan-assembler "movl\[ \t\]8\\(%esp\\), %edi" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]12\\(%rsp\\), %esi" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]4\\(%rsi,%rdi,4\\), %edx" { target x32 [...] +/* { dg-final { scan-assembler "movl\[ \t\]\\(%esp\\), %eax" { target ia32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]4\\(%esp\\), %edx" { target ia32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]8\\(%esp,%eax,4\\), %ecx" { target ia32 [...] diff --git a/gcc/testsuite/gcc.target/i386/pr66960-2.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..b9dbde2 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-2.c @@ -0,0 +1,33 @@ +/* { dg-do compile { target *-*-linux* } } */ +/* { dg-options "-O2 -fno-omit-frame-pointer" { target { lp64 } } } */ +/* { dg-options "-O2 -fno-omit-frame-pointer -maddress-mode=short" { target { x32 [...] +/* { dg-options "-O2 -fno-omit-frame-pointer -miamcu" { target { ia32 } } } */ + +extern char **environ; +extern void exit (int status); +extern int main (long argc, char **argv, char **envp); + +void +_start (void) +{ + void *argc_p = __builtin_stack_top (); + char **argv = (char **) (argc_p + sizeof (void *)); + long argc = *(long *) argc_p; + int status; + + environ = argv + argc + 1; + + status = main (argc, argv, environ); + + exit (status); +} + +/* { dg-final { scan-assembler "movq\[ \t\]8\\(%rbp\\), %rdi" { target lp64 } } } */ +/* { dg-final { scan-assembler "leaq\[ \t\]16\\(%rbp\\), %rsi" { target lp64 } } } */ +/* { dg-final { scan-assembler "leaq\[ \t\]24\\(%rbp,%rdi,8\\), %rdx" { target lp6 [...] +/* { dg-final { scan-assembler "movl\[ \t\]8\\(%ebp\\), %edi" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]12\\(%rbp\\), %esi" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]4\\(%rsi,%rdi,4\\), %edx" { target x32 [...] +/* { dg-final { scan-assembler "movl\[ \t\]4\\(%ebp\\), %eax" { target ia32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]8\\(%ebp\\), %edx" { target ia32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]12\\(%ebp,%eax,4\\), %ecx" { target ia3 [...] diff --git a/gcc/testsuite/gcc.target/i386/pr66960-3.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..48cf25e --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-3.c @@ -0,0 +1,17 @@ +/* { dg-do compile { target *-*-linux* } } */ +/* { dg-options "-O2 -mno-accumulate-outgoing-args" { target { lp64 } } } */ +/* { dg-options "-O2 -mno-accumulate-outgoing-args -maddress-mode=short" { target [...] +/* { dg-options "-O2 -mno-accumulate-outgoing-args -miamcu" { target { ia32 } } } */ + +extern void abort (void); +extern int check_int (int *i, int align); +typedef int aligned __attribute__((aligned(64))); + +void * +foo (void) +{ + aligned j; + if (check_int (&j, __alignof__(j)) != j) + abort (); + return __builtin_stack_top (); +} /* { dg-message "sorry, unimplemented: .__builtin_stack_top. not supported" } */ diff --git a/gcc/testsuite/gcc.target/i386/pr66960-4.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..44c0b26 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-4.c @@ -0,0 +1,21 @@ +/* { dg-do compile { target *-*-linux* } } */ +/* { dg-options "-O2 -maccumulate-outgoing-args" { target { lp64 } } } */ +/* { dg-options "-O2 -maccumulate-outgoing-args -maddress-mode=short" { target { x [...] +/* { dg-options "-O2 -maccumulate-outgoing-args -miamcu" { target { ia32 } } } */ + +extern void abort (void); +extern int check_int (int *i, int align); +typedef int aligned __attribute__((aligned(64))); + +void * +foo (void) +{ + aligned j; + if (check_int (&j, __alignof__(j)) != j) + abort (); + return __builtin_stack_top (); +} + +/* { dg-final { scan-assembler "leaq\[ \t\]8\\(%rbp\\), %rax" { target lp64 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]8\\(%rbp\\), %eax" { target x32 } } } */ +/* { dg-final { scan-assembler "leal\[ \t\]4\\(%ebp\\), %eax" { target ia32 } } } */ diff --git a/gcc/testsuite/gcc.target/i386/pr66960-5.c b/gcc/testsuite/gcc.target/i [...] new file mode 100644 index 0000000..d449437 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr66960-5.c @@ -0,0 +1,21 @@ +/* { dg-do link } */ +/* { dg-options "-O" } */ + +extern void link_error (void); + +__attribute__ ((noinline, noclone)) +void +foo (void) +{ + void **p = __builtin_stack_top (); + void *ra = __builtin_return_address (0); + if (*p != ra) + link_error (); +} + +int +main (void) +{ + foo (); + return 0; +} -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] branch trunk updated (d8cc4c5 -> 4757c55)

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a change to branch trunk in repository gcc. from d8cc4c5 2015-08-04 Paolo Carlini <paolo.carlini(a)oracle.com> new 4757c55 Compile IAMCU tests with -fno-pie -no-pie The 1 revisions listed above as "new" are entirely new to this repository and will be described in separate emails. The revisions listed as "adds" were already present in the repository and have only been added to this reference. Summary of changes: gcc/testsuite/ChangeLog | 6 ++++++ gcc/testsuite/gcc.target/i386/iamcu/abi-iamcu.exp | 2 +- 2 files changed, 7 insertions(+), 1 deletion(-) -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] branch trunk updated (cd33329 -> d8cc4c5)

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a change to branch trunk in repository gcc. from cd33329 [AArch64][14/14] Reuse target_option_current_node when passin [...] new d8cc4c5 2015-08-04 Paolo Carlini <paolo.carlini(a)oracle.com> The 1 revisions listed above as "new" are entirely new to this repository and will be described in separate emails. The revisions listed as "adds" were already present in the repository and have only been added to this reference. Summary of changes: gcc/testsuite/ChangeLog | 5 +++++ gcc/testsuite/g++.dg/cpp1y/var-templ34.C | 20 ++++++++++++++++++++ 2 files changed, 25 insertions(+) create mode 100644 gcc/testsuite/g++.dg/cpp1y/var-templ34.C -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] branch trunk updated (b0269e3 -> cd33329)

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a change to branch trunk in repository gcc. from b0269e3 [AArch64][9/14] Implement TARGET_CAN_INLINE_P new 26db532 [AArch64][10/14] Implement target pragmas new dad9014 [AArch64][11/14] Re-layout SIMD builtin types on builtin expansion new b65ae63 [AArch64][12/14] Target attributes and target pragmas tests new 5de59ee [doc][13/14] Document AArch64 target attributes and pragmas new cd33329 [AArch64][14/14] Reuse target_option_current_node when passin [...] The 5 revisions listed above as "new" are entirely new to this repository and will be described in separate emails. The revisions listed as "adds" were already present in the repository and have only been added to this reference. Summary of changes: gcc/ChangeLog | 51 +++++ gcc/config.gcc | 2 + gcc/config/aarch64/aarch64-builtins.c | 39 +++- gcc/config/aarch64/aarch64-c.c | 203 ++++++++++++++++ gcc/config/aarch64/aarch64-protos.h | 9 + gcc/config/aarch64/aarch64.c | 40 +++- gcc/config/aarch64/aarch64.h | 80 +------ gcc/config/aarch64/arm_acle.h | 10 +- gcc/config/aarch64/arm_neon.h | 19 +- gcc/config/aarch64/t-aarch64 | 5 + gcc/doc/extend.texi | 154 +++++++++++++ gcc/testsuite/ChangeLog | 27 +++ .../gcc.target/aarch64/arm_neon-nosimd-error.c | 11 - .../gcc.target/aarch64/pragma_cpp_predefs_1.c | 255 +++++++++++++++++++++ gcc/testsuite/gcc.target/aarch64/target_attr_1.c | 14 ++ gcc/testsuite/gcc.target/aarch64/target_attr_10.c | 16 ++ gcc/testsuite/gcc.target/aarch64/target_attr_11.c | 13 ++ gcc/testsuite/gcc.target/aarch64/target_attr_12.c | 13 ++ gcc/testsuite/gcc.target/aarch64/target_attr_13.c | 16 ++ gcc/testsuite/gcc.target/aarch64/target_attr_14.c | 20 ++ gcc/testsuite/gcc.target/aarch64/target_attr_15.c | 15 ++ gcc/testsuite/gcc.target/aarch64/target_attr_2.c | 39 ++++ gcc/testsuite/gcc.target/aarch64/target_attr_3.c | 34 +++ gcc/testsuite/gcc.target/aarch64/target_attr_4.c | 30 +++ gcc/testsuite/gcc.target/aarch64/target_attr_5.c | 20 ++ gcc/testsuite/gcc.target/aarch64/target_attr_6.c | 20 ++ gcc/testsuite/gcc.target/aarch64/target_attr_7.c | 24 ++ gcc/testsuite/gcc.target/aarch64/target_attr_8.c | 22 ++ gcc/testsuite/gcc.target/aarch64/target_attr_9.c | 22 ++ .../gcc.target/aarch64/target_attr_crypto_ice_1.c | 21 ++ 30 files changed, 1140 insertions(+), 104 deletions(-) create mode 100644 gcc/config/aarch64/aarch64-c.c delete mode 100644 gcc/testsuite/gcc.target/aarch64/arm_neon-nosimd-error.c create mode 100644 gcc/testsuite/gcc.target/aarch64/pragma_cpp_predefs_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_10.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_11.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_12.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_13.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_14.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_15.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_2.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_3.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_4.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_5.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_6.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_7.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_8.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_9.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_crypto_ice_1.c -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] branch master updated (b0269e3 -> cd33329)

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a change to branch master in repository gcc. from b0269e3 [AArch64][9/14] Implement TARGET_CAN_INLINE_P new 26db532 [AArch64][10/14] Implement target pragmas new dad9014 [AArch64][11/14] Re-layout SIMD builtin types on builtin expansion new b65ae63 [AArch64][12/14] Target attributes and target pragmas tests new 5de59ee [doc][13/14] Document AArch64 target attributes and pragmas new cd33329 [AArch64][14/14] Reuse target_option_current_node when passin [...] The 5 revisions listed above as "new" are entirely new to this repository and will be described in separate emails. The revisions listed as "adds" were already present in the repository and have only been added to this reference. Summary of changes: gcc/ChangeLog | 51 +++++ gcc/config.gcc | 2 + gcc/config/aarch64/aarch64-builtins.c | 39 +++- gcc/config/aarch64/aarch64-c.c | 203 ++++++++++++++++ gcc/config/aarch64/aarch64-protos.h | 9 + gcc/config/aarch64/aarch64.c | 40 +++- gcc/config/aarch64/aarch64.h | 80 +------ gcc/config/aarch64/arm_acle.h | 10 +- gcc/config/aarch64/arm_neon.h | 19 +- gcc/config/aarch64/t-aarch64 | 5 + gcc/doc/extend.texi | 154 +++++++++++++ gcc/testsuite/ChangeLog | 27 +++ .../gcc.target/aarch64/arm_neon-nosimd-error.c | 11 - .../gcc.target/aarch64/pragma_cpp_predefs_1.c | 255 +++++++++++++++++++++ gcc/testsuite/gcc.target/aarch64/target_attr_1.c | 14 ++ gcc/testsuite/gcc.target/aarch64/target_attr_10.c | 16 ++ gcc/testsuite/gcc.target/aarch64/target_attr_11.c | 13 ++ gcc/testsuite/gcc.target/aarch64/target_attr_12.c | 13 ++ gcc/testsuite/gcc.target/aarch64/target_attr_13.c | 16 ++ gcc/testsuite/gcc.target/aarch64/target_attr_14.c | 20 ++ gcc/testsuite/gcc.target/aarch64/target_attr_15.c | 15 ++ gcc/testsuite/gcc.target/aarch64/target_attr_2.c | 39 ++++ gcc/testsuite/gcc.target/aarch64/target_attr_3.c | 34 +++ gcc/testsuite/gcc.target/aarch64/target_attr_4.c | 30 +++ gcc/testsuite/gcc.target/aarch64/target_attr_5.c | 20 ++ gcc/testsuite/gcc.target/aarch64/target_attr_6.c | 20 ++ gcc/testsuite/gcc.target/aarch64/target_attr_7.c | 24 ++ gcc/testsuite/gcc.target/aarch64/target_attr_8.c | 22 ++ gcc/testsuite/gcc.target/aarch64/target_attr_9.c | 22 ++ .../gcc.target/aarch64/target_attr_crypto_ice_1.c | 21 ++ 30 files changed, 1140 insertions(+), 104 deletions(-) create mode 100644 gcc/config/aarch64/aarch64-c.c delete mode 100644 gcc/testsuite/gcc.target/aarch64/arm_neon-nosimd-error.c create mode 100644 gcc/testsuite/gcc.target/aarch64/pragma_cpp_predefs_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_1.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_10.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_11.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_12.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_13.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_14.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_15.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_2.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_3.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_4.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_5.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_6.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_7.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_8.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_9.c create mode 100644 gcc/testsuite/gcc.target/aarch64/target_attr_crypto_ice_1.c -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

[gcc] branch trunk updated (3f215f2 -> b0269e3)

by git

This is an automated email from the git hooks/post-receive script. unknown user pushed a change to branch trunk in repository gcc. from 3f215f2 [AArch64][5/14] Make flag_omit_leaf_frame_pointer intialize t [...] new a0db861 [AArch64][6/14] Implement TARGET_OPTION_SAVE/TARGET_OPTION_RESTORE new f59387a [AArch64][7/14] Implement TARGET_SET_CURRENT_FUNCTION new aadb8e1 [AArch64][8/14] Implement TARGET_OPTION_VALID_ATTRIBUTE_P new b0269e3 [AArch64][9/14] Implement TARGET_CAN_INLINE_P The 4 revisions listed above as "new" are entirely new to this repository and will be described in separate emails. The revisions listed as "adds" were already present in the repository and have only been added to this reference. Summary of changes: gcc/ChangeLog | 74 +++ gcc/common/config/aarch64/aarch64-common.c | 19 +- gcc/config/aarch64/aarch64-protos.h | 5 + gcc/config/aarch64/aarch64.c | 897 +++++++++++++++++++++++++++-- gcc/config/aarch64/aarch64.h | 9 +- gcc/config/aarch64/aarch64.opt | 24 +- 6 files changed, 968 insertions(+), 60 deletions(-) -- To stop receiving notification emails like this one, please contact the administrator of this repository.

9 years, 4 months

← Newer
1
...
50
51
52
53
54
55
56
...
61
Older →

Jump to page:

2024

2023

2022

2021

2020

2019

2018

2017

2016

2015

Tcwg-commits August 2015