diff options
author | Martin Liska <mliska@suse.cz> | 2022-01-14 16:56:44 +0100 |
---|---|---|
committer | Martin Liska <mliska@suse.cz> | 2022-01-17 22:12:04 +0100 |
commit | 5c69acb32329d49e58c26fa41ae74229a52b9106 (patch) | |
tree | ddb05f9d73afb6f998457d2ac4b720e3b3b60483 /gcc/c-family/c-omp.c | |
parent | 490e23032baaece71f2ec09fa1805064b150fbc2 (diff) | |
download | gcc-5c69acb32329d49e58c26fa41ae74229a52b9106.zip gcc-5c69acb32329d49e58c26fa41ae74229a52b9106.tar.gz gcc-5c69acb32329d49e58c26fa41ae74229a52b9106.tar.bz2 |
Rename .c files to .cc files.
gcc/ada/ChangeLog:
* adadecode.c: Moved to...
* adadecode.cc: ...here.
* affinity.c: Moved to...
* affinity.cc: ...here.
* argv-lynxos178-raven-cert.c: Moved to...
* argv-lynxos178-raven-cert.cc: ...here.
* argv.c: Moved to...
* argv.cc: ...here.
* aux-io.c: Moved to...
* aux-io.cc: ...here.
* cio.c: Moved to...
* cio.cc: ...here.
* cstreams.c: Moved to...
* cstreams.cc: ...here.
* env.c: Moved to...
* env.cc: ...here.
* exit.c: Moved to...
* exit.cc: ...here.
* expect.c: Moved to...
* expect.cc: ...here.
* final.c: Moved to...
* final.cc: ...here.
* gcc-interface/cuintp.c: Moved to...
* gcc-interface/cuintp.cc: ...here.
* gcc-interface/decl.c: Moved to...
* gcc-interface/decl.cc: ...here.
* gcc-interface/misc.c: Moved to...
* gcc-interface/misc.cc: ...here.
* gcc-interface/targtyps.c: Moved to...
* gcc-interface/targtyps.cc: ...here.
* gcc-interface/trans.c: Moved to...
* gcc-interface/trans.cc: ...here.
* gcc-interface/utils.c: Moved to...
* gcc-interface/utils.cc: ...here.
* gcc-interface/utils2.c: Moved to...
* gcc-interface/utils2.cc: ...here.
* init.c: Moved to...
* init.cc: ...here.
* initialize.c: Moved to...
* initialize.cc: ...here.
* libgnarl/thread.c: Moved to...
* libgnarl/thread.cc: ...here.
* link.c: Moved to...
* link.cc: ...here.
* locales.c: Moved to...
* locales.cc: ...here.
* mkdir.c: Moved to...
* mkdir.cc: ...here.
* raise.c: Moved to...
* raise.cc: ...here.
* rtfinal.c: Moved to...
* rtfinal.cc: ...here.
* rtinit.c: Moved to...
* rtinit.cc: ...here.
* seh_init.c: Moved to...
* seh_init.cc: ...here.
* sigtramp-armdroid.c: Moved to...
* sigtramp-armdroid.cc: ...here.
* sigtramp-ios.c: Moved to...
* sigtramp-ios.cc: ...here.
* sigtramp-qnx.c: Moved to...
* sigtramp-qnx.cc: ...here.
* sigtramp-vxworks.c: Moved to...
* sigtramp-vxworks.cc: ...here.
* socket.c: Moved to...
* socket.cc: ...here.
* tracebak.c: Moved to...
* tracebak.cc: ...here.
* version.c: Moved to...
* version.cc: ...here.
* vx_stack_info.c: Moved to...
* vx_stack_info.cc: ...here.
gcc/ChangeLog:
* adjust-alignment.c: Moved to...
* adjust-alignment.cc: ...here.
* alias.c: Moved to...
* alias.cc: ...here.
* alloc-pool.c: Moved to...
* alloc-pool.cc: ...here.
* asan.c: Moved to...
* asan.cc: ...here.
* attribs.c: Moved to...
* attribs.cc: ...here.
* auto-inc-dec.c: Moved to...
* auto-inc-dec.cc: ...here.
* auto-profile.c: Moved to...
* auto-profile.cc: ...here.
* bb-reorder.c: Moved to...
* bb-reorder.cc: ...here.
* bitmap.c: Moved to...
* bitmap.cc: ...here.
* btfout.c: Moved to...
* btfout.cc: ...here.
* builtins.c: Moved to...
* builtins.cc: ...here.
* caller-save.c: Moved to...
* caller-save.cc: ...here.
* calls.c: Moved to...
* calls.cc: ...here.
* ccmp.c: Moved to...
* ccmp.cc: ...here.
* cfg.c: Moved to...
* cfg.cc: ...here.
* cfganal.c: Moved to...
* cfganal.cc: ...here.
* cfgbuild.c: Moved to...
* cfgbuild.cc: ...here.
* cfgcleanup.c: Moved to...
* cfgcleanup.cc: ...here.
* cfgexpand.c: Moved to...
* cfgexpand.cc: ...here.
* cfghooks.c: Moved to...
* cfghooks.cc: ...here.
* cfgloop.c: Moved to...
* cfgloop.cc: ...here.
* cfgloopanal.c: Moved to...
* cfgloopanal.cc: ...here.
* cfgloopmanip.c: Moved to...
* cfgloopmanip.cc: ...here.
* cfgrtl.c: Moved to...
* cfgrtl.cc: ...here.
* cgraph.c: Moved to...
* cgraph.cc: ...here.
* cgraphbuild.c: Moved to...
* cgraphbuild.cc: ...here.
* cgraphclones.c: Moved to...
* cgraphclones.cc: ...here.
* cgraphunit.c: Moved to...
* cgraphunit.cc: ...here.
* collect-utils.c: Moved to...
* collect-utils.cc: ...here.
* collect2-aix.c: Moved to...
* collect2-aix.cc: ...here.
* collect2.c: Moved to...
* collect2.cc: ...here.
* combine-stack-adj.c: Moved to...
* combine-stack-adj.cc: ...here.
* combine.c: Moved to...
* combine.cc: ...here.
* common/common-targhooks.c: Moved to...
* common/common-targhooks.cc: ...here.
* common/config/aarch64/aarch64-common.c: Moved to...
* common/config/aarch64/aarch64-common.cc: ...here.
* common/config/alpha/alpha-common.c: Moved to...
* common/config/alpha/alpha-common.cc: ...here.
* common/config/arc/arc-common.c: Moved to...
* common/config/arc/arc-common.cc: ...here.
* common/config/arm/arm-common.c: Moved to...
* common/config/arm/arm-common.cc: ...here.
* common/config/avr/avr-common.c: Moved to...
* common/config/avr/avr-common.cc: ...here.
* common/config/bfin/bfin-common.c: Moved to...
* common/config/bfin/bfin-common.cc: ...here.
* common/config/bpf/bpf-common.c: Moved to...
* common/config/bpf/bpf-common.cc: ...here.
* common/config/c6x/c6x-common.c: Moved to...
* common/config/c6x/c6x-common.cc: ...here.
* common/config/cr16/cr16-common.c: Moved to...
* common/config/cr16/cr16-common.cc: ...here.
* common/config/cris/cris-common.c: Moved to...
* common/config/cris/cris-common.cc: ...here.
* common/config/csky/csky-common.c: Moved to...
* common/config/csky/csky-common.cc: ...here.
* common/config/default-common.c: Moved to...
* common/config/default-common.cc: ...here.
* common/config/epiphany/epiphany-common.c: Moved to...
* common/config/epiphany/epiphany-common.cc: ...here.
* common/config/fr30/fr30-common.c: Moved to...
* common/config/fr30/fr30-common.cc: ...here.
* common/config/frv/frv-common.c: Moved to...
* common/config/frv/frv-common.cc: ...here.
* common/config/gcn/gcn-common.c: Moved to...
* common/config/gcn/gcn-common.cc: ...here.
* common/config/h8300/h8300-common.c: Moved to...
* common/config/h8300/h8300-common.cc: ...here.
* common/config/i386/i386-common.c: Moved to...
* common/config/i386/i386-common.cc: ...here.
* common/config/ia64/ia64-common.c: Moved to...
* common/config/ia64/ia64-common.cc: ...here.
* common/config/iq2000/iq2000-common.c: Moved to...
* common/config/iq2000/iq2000-common.cc: ...here.
* common/config/lm32/lm32-common.c: Moved to...
* common/config/lm32/lm32-common.cc: ...here.
* common/config/m32r/m32r-common.c: Moved to...
* common/config/m32r/m32r-common.cc: ...here.
* common/config/m68k/m68k-common.c: Moved to...
* common/config/m68k/m68k-common.cc: ...here.
* common/config/mcore/mcore-common.c: Moved to...
* common/config/mcore/mcore-common.cc: ...here.
* common/config/microblaze/microblaze-common.c: Moved to...
* common/config/microblaze/microblaze-common.cc: ...here.
* common/config/mips/mips-common.c: Moved to...
* common/config/mips/mips-common.cc: ...here.
* common/config/mmix/mmix-common.c: Moved to...
* common/config/mmix/mmix-common.cc: ...here.
* common/config/mn10300/mn10300-common.c: Moved to...
* common/config/mn10300/mn10300-common.cc: ...here.
* common/config/msp430/msp430-common.c: Moved to...
* common/config/msp430/msp430-common.cc: ...here.
* common/config/nds32/nds32-common.c: Moved to...
* common/config/nds32/nds32-common.cc: ...here.
* common/config/nios2/nios2-common.c: Moved to...
* common/config/nios2/nios2-common.cc: ...here.
* common/config/nvptx/nvptx-common.c: Moved to...
* common/config/nvptx/nvptx-common.cc: ...here.
* common/config/or1k/or1k-common.c: Moved to...
* common/config/or1k/or1k-common.cc: ...here.
* common/config/pa/pa-common.c: Moved to...
* common/config/pa/pa-common.cc: ...here.
* common/config/pdp11/pdp11-common.c: Moved to...
* common/config/pdp11/pdp11-common.cc: ...here.
* common/config/pru/pru-common.c: Moved to...
* common/config/pru/pru-common.cc: ...here.
* common/config/riscv/riscv-common.c: Moved to...
* common/config/riscv/riscv-common.cc: ...here.
* common/config/rs6000/rs6000-common.c: Moved to...
* common/config/rs6000/rs6000-common.cc: ...here.
* common/config/rx/rx-common.c: Moved to...
* common/config/rx/rx-common.cc: ...here.
* common/config/s390/s390-common.c: Moved to...
* common/config/s390/s390-common.cc: ...here.
* common/config/sh/sh-common.c: Moved to...
* common/config/sh/sh-common.cc: ...here.
* common/config/sparc/sparc-common.c: Moved to...
* common/config/sparc/sparc-common.cc: ...here.
* common/config/tilegx/tilegx-common.c: Moved to...
* common/config/tilegx/tilegx-common.cc: ...here.
* common/config/tilepro/tilepro-common.c: Moved to...
* common/config/tilepro/tilepro-common.cc: ...here.
* common/config/v850/v850-common.c: Moved to...
* common/config/v850/v850-common.cc: ...here.
* common/config/vax/vax-common.c: Moved to...
* common/config/vax/vax-common.cc: ...here.
* common/config/visium/visium-common.c: Moved to...
* common/config/visium/visium-common.cc: ...here.
* common/config/xstormy16/xstormy16-common.c: Moved to...
* common/config/xstormy16/xstormy16-common.cc: ...here.
* common/config/xtensa/xtensa-common.c: Moved to...
* common/config/xtensa/xtensa-common.cc: ...here.
* compare-elim.c: Moved to...
* compare-elim.cc: ...here.
* config/aarch64/aarch64-bti-insert.c: Moved to...
* config/aarch64/aarch64-bti-insert.cc: ...here.
* config/aarch64/aarch64-builtins.c: Moved to...
* config/aarch64/aarch64-builtins.cc: ...here.
* config/aarch64/aarch64-c.c: Moved to...
* config/aarch64/aarch64-c.cc: ...here.
* config/aarch64/aarch64-d.c: Moved to...
* config/aarch64/aarch64-d.cc: ...here.
* config/aarch64/aarch64.c: Moved to...
* config/aarch64/aarch64.cc: ...here.
* config/aarch64/cortex-a57-fma-steering.c: Moved to...
* config/aarch64/cortex-a57-fma-steering.cc: ...here.
* config/aarch64/driver-aarch64.c: Moved to...
* config/aarch64/driver-aarch64.cc: ...here.
* config/aarch64/falkor-tag-collision-avoidance.c: Moved to...
* config/aarch64/falkor-tag-collision-avoidance.cc: ...here.
* config/aarch64/host-aarch64-darwin.c: Moved to...
* config/aarch64/host-aarch64-darwin.cc: ...here.
* config/alpha/alpha.c: Moved to...
* config/alpha/alpha.cc: ...here.
* config/alpha/driver-alpha.c: Moved to...
* config/alpha/driver-alpha.cc: ...here.
* config/arc/arc-c.c: Moved to...
* config/arc/arc-c.cc: ...here.
* config/arc/arc.c: Moved to...
* config/arc/arc.cc: ...here.
* config/arc/driver-arc.c: Moved to...
* config/arc/driver-arc.cc: ...here.
* config/arm/aarch-common.c: Moved to...
* config/arm/aarch-common.cc: ...here.
* config/arm/arm-builtins.c: Moved to...
* config/arm/arm-builtins.cc: ...here.
* config/arm/arm-c.c: Moved to...
* config/arm/arm-c.cc: ...here.
* config/arm/arm-d.c: Moved to...
* config/arm/arm-d.cc: ...here.
* config/arm/arm.c: Moved to...
* config/arm/arm.cc: ...here.
* config/arm/driver-arm.c: Moved to...
* config/arm/driver-arm.cc: ...here.
* config/avr/avr-c.c: Moved to...
* config/avr/avr-c.cc: ...here.
* config/avr/avr-devices.c: Moved to...
* config/avr/avr-devices.cc: ...here.
* config/avr/avr-log.c: Moved to...
* config/avr/avr-log.cc: ...here.
* config/avr/avr.c: Moved to...
* config/avr/avr.cc: ...here.
* config/avr/driver-avr.c: Moved to...
* config/avr/driver-avr.cc: ...here.
* config/avr/gen-avr-mmcu-specs.c: Moved to...
* config/avr/gen-avr-mmcu-specs.cc: ...here.
* config/avr/gen-avr-mmcu-texi.c: Moved to...
* config/avr/gen-avr-mmcu-texi.cc: ...here.
* config/bfin/bfin.c: Moved to...
* config/bfin/bfin.cc: ...here.
* config/bpf/bpf.c: Moved to...
* config/bpf/bpf.cc: ...here.
* config/bpf/coreout.c: Moved to...
* config/bpf/coreout.cc: ...here.
* config/c6x/c6x.c: Moved to...
* config/c6x/c6x.cc: ...here.
* config/cr16/cr16.c: Moved to...
* config/cr16/cr16.cc: ...here.
* config/cris/cris.c: Moved to...
* config/cris/cris.cc: ...here.
* config/csky/csky.c: Moved to...
* config/csky/csky.cc: ...here.
* config/darwin-c.c: Moved to...
* config/darwin-c.cc: ...here.
* config/darwin-d.c: Moved to...
* config/darwin-d.cc: ...here.
* config/darwin-driver.c: Moved to...
* config/darwin-driver.cc: ...here.
* config/darwin-f.c: Moved to...
* config/darwin-f.cc: ...here.
* config/darwin.c: Moved to...
* config/darwin.cc: ...here.
* config/default-c.c: Moved to...
* config/default-c.cc: ...here.
* config/default-d.c: Moved to...
* config/default-d.cc: ...here.
* config/dragonfly-d.c: Moved to...
* config/dragonfly-d.cc: ...here.
* config/epiphany/epiphany.c: Moved to...
* config/epiphany/epiphany.cc: ...here.
* config/epiphany/mode-switch-use.c: Moved to...
* config/epiphany/mode-switch-use.cc: ...here.
* config/epiphany/resolve-sw-modes.c: Moved to...
* config/epiphany/resolve-sw-modes.cc: ...here.
* config/fr30/fr30.c: Moved to...
* config/fr30/fr30.cc: ...here.
* config/freebsd-d.c: Moved to...
* config/freebsd-d.cc: ...here.
* config/frv/frv.c: Moved to...
* config/frv/frv.cc: ...here.
* config/ft32/ft32.c: Moved to...
* config/ft32/ft32.cc: ...here.
* config/gcn/driver-gcn.c: Moved to...
* config/gcn/driver-gcn.cc: ...here.
* config/gcn/gcn-run.c: Moved to...
* config/gcn/gcn-run.cc: ...here.
* config/gcn/gcn-tree.c: Moved to...
* config/gcn/gcn-tree.cc: ...here.
* config/gcn/gcn.c: Moved to...
* config/gcn/gcn.cc: ...here.
* config/gcn/mkoffload.c: Moved to...
* config/gcn/mkoffload.cc: ...here.
* config/glibc-c.c: Moved to...
* config/glibc-c.cc: ...here.
* config/glibc-d.c: Moved to...
* config/glibc-d.cc: ...here.
* config/h8300/h8300.c: Moved to...
* config/h8300/h8300.cc: ...here.
* config/host-darwin.c: Moved to...
* config/host-darwin.cc: ...here.
* config/host-hpux.c: Moved to...
* config/host-hpux.cc: ...here.
* config/host-linux.c: Moved to...
* config/host-linux.cc: ...here.
* config/host-netbsd.c: Moved to...
* config/host-netbsd.cc: ...here.
* config/host-openbsd.c: Moved to...
* config/host-openbsd.cc: ...here.
* config/host-solaris.c: Moved to...
* config/host-solaris.cc: ...here.
* config/i386/djgpp.c: Moved to...
* config/i386/djgpp.cc: ...here.
* config/i386/driver-i386.c: Moved to...
* config/i386/driver-i386.cc: ...here.
* config/i386/driver-mingw32.c: Moved to...
* config/i386/driver-mingw32.cc: ...here.
* config/i386/gnu-property.c: Moved to...
* config/i386/gnu-property.cc: ...here.
* config/i386/host-cygwin.c: Moved to...
* config/i386/host-cygwin.cc: ...here.
* config/i386/host-i386-darwin.c: Moved to...
* config/i386/host-i386-darwin.cc: ...here.
* config/i386/host-mingw32.c: Moved to...
* config/i386/host-mingw32.cc: ...here.
* config/i386/i386-builtins.c: Moved to...
* config/i386/i386-builtins.cc: ...here.
* config/i386/i386-c.c: Moved to...
* config/i386/i386-c.cc: ...here.
* config/i386/i386-d.c: Moved to...
* config/i386/i386-d.cc: ...here.
* config/i386/i386-expand.c: Moved to...
* config/i386/i386-expand.cc: ...here.
* config/i386/i386-features.c: Moved to...
* config/i386/i386-features.cc: ...here.
* config/i386/i386-options.c: Moved to...
* config/i386/i386-options.cc: ...here.
* config/i386/i386.c: Moved to...
* config/i386/i386.cc: ...here.
* config/i386/intelmic-mkoffload.c: Moved to...
* config/i386/intelmic-mkoffload.cc: ...here.
* config/i386/msformat-c.c: Moved to...
* config/i386/msformat-c.cc: ...here.
* config/i386/winnt-cxx.c: Moved to...
* config/i386/winnt-cxx.cc: ...here.
* config/i386/winnt-d.c: Moved to...
* config/i386/winnt-d.cc: ...here.
* config/i386/winnt-stubs.c: Moved to...
* config/i386/winnt-stubs.cc: ...here.
* config/i386/winnt.c: Moved to...
* config/i386/winnt.cc: ...here.
* config/i386/x86-tune-sched-atom.c: Moved to...
* config/i386/x86-tune-sched-atom.cc: ...here.
* config/i386/x86-tune-sched-bd.c: Moved to...
* config/i386/x86-tune-sched-bd.cc: ...here.
* config/i386/x86-tune-sched-core.c: Moved to...
* config/i386/x86-tune-sched-core.cc: ...here.
* config/i386/x86-tune-sched.c: Moved to...
* config/i386/x86-tune-sched.cc: ...here.
* config/ia64/ia64-c.c: Moved to...
* config/ia64/ia64-c.cc: ...here.
* config/ia64/ia64.c: Moved to...
* config/ia64/ia64.cc: ...here.
* config/iq2000/iq2000.c: Moved to...
* config/iq2000/iq2000.cc: ...here.
* config/linux.c: Moved to...
* config/linux.cc: ...here.
* config/lm32/lm32.c: Moved to...
* config/lm32/lm32.cc: ...here.
* config/m32c/m32c-pragma.c: Moved to...
* config/m32c/m32c-pragma.cc: ...here.
* config/m32c/m32c.c: Moved to...
* config/m32c/m32c.cc: ...here.
* config/m32r/m32r.c: Moved to...
* config/m32r/m32r.cc: ...here.
* config/m68k/m68k.c: Moved to...
* config/m68k/m68k.cc: ...here.
* config/mcore/mcore.c: Moved to...
* config/mcore/mcore.cc: ...here.
* config/microblaze/microblaze-c.c: Moved to...
* config/microblaze/microblaze-c.cc: ...here.
* config/microblaze/microblaze.c: Moved to...
* config/microblaze/microblaze.cc: ...here.
* config/mips/driver-native.c: Moved to...
* config/mips/driver-native.cc: ...here.
* config/mips/frame-header-opt.c: Moved to...
* config/mips/frame-header-opt.cc: ...here.
* config/mips/mips-d.c: Moved to...
* config/mips/mips-d.cc: ...here.
* config/mips/mips.c: Moved to...
* config/mips/mips.cc: ...here.
* config/mmix/mmix.c: Moved to...
* config/mmix/mmix.cc: ...here.
* config/mn10300/mn10300.c: Moved to...
* config/mn10300/mn10300.cc: ...here.
* config/moxie/moxie.c: Moved to...
* config/moxie/moxie.cc: ...here.
* config/msp430/driver-msp430.c: Moved to...
* config/msp430/driver-msp430.cc: ...here.
* config/msp430/msp430-c.c: Moved to...
* config/msp430/msp430-c.cc: ...here.
* config/msp430/msp430-devices.c: Moved to...
* config/msp430/msp430-devices.cc: ...here.
* config/msp430/msp430.c: Moved to...
* config/msp430/msp430.cc: ...here.
* config/nds32/nds32-cost.c: Moved to...
* config/nds32/nds32-cost.cc: ...here.
* config/nds32/nds32-fp-as-gp.c: Moved to...
* config/nds32/nds32-fp-as-gp.cc: ...here.
* config/nds32/nds32-intrinsic.c: Moved to...
* config/nds32/nds32-intrinsic.cc: ...here.
* config/nds32/nds32-isr.c: Moved to...
* config/nds32/nds32-isr.cc: ...here.
* config/nds32/nds32-md-auxiliary.c: Moved to...
* config/nds32/nds32-md-auxiliary.cc: ...here.
* config/nds32/nds32-memory-manipulation.c: Moved to...
* config/nds32/nds32-memory-manipulation.cc: ...here.
* config/nds32/nds32-pipelines-auxiliary.c: Moved to...
* config/nds32/nds32-pipelines-auxiliary.cc: ...here.
* config/nds32/nds32-predicates.c: Moved to...
* config/nds32/nds32-predicates.cc: ...here.
* config/nds32/nds32-relax-opt.c: Moved to...
* config/nds32/nds32-relax-opt.cc: ...here.
* config/nds32/nds32-utils.c: Moved to...
* config/nds32/nds32-utils.cc: ...here.
* config/nds32/nds32.c: Moved to...
* config/nds32/nds32.cc: ...here.
* config/netbsd-d.c: Moved to...
* config/netbsd-d.cc: ...here.
* config/netbsd.c: Moved to...
* config/netbsd.cc: ...here.
* config/nios2/nios2.c: Moved to...
* config/nios2/nios2.cc: ...here.
* config/nvptx/mkoffload.c: Moved to...
* config/nvptx/mkoffload.cc: ...here.
* config/nvptx/nvptx-c.c: Moved to...
* config/nvptx/nvptx-c.cc: ...here.
* config/nvptx/nvptx.c: Moved to...
* config/nvptx/nvptx.cc: ...here.
* config/openbsd-d.c: Moved to...
* config/openbsd-d.cc: ...here.
* config/or1k/or1k.c: Moved to...
* config/or1k/or1k.cc: ...here.
* config/pa/pa-d.c: Moved to...
* config/pa/pa-d.cc: ...here.
* config/pa/pa.c: Moved to...
* config/pa/pa.cc: ...here.
* config/pdp11/pdp11.c: Moved to...
* config/pdp11/pdp11.cc: ...here.
* config/pru/pru-passes.c: Moved to...
* config/pru/pru-passes.cc: ...here.
* config/pru/pru-pragma.c: Moved to...
* config/pru/pru-pragma.cc: ...here.
* config/pru/pru.c: Moved to...
* config/pru/pru.cc: ...here.
* config/riscv/riscv-builtins.c: Moved to...
* config/riscv/riscv-builtins.cc: ...here.
* config/riscv/riscv-c.c: Moved to...
* config/riscv/riscv-c.cc: ...here.
* config/riscv/riscv-d.c: Moved to...
* config/riscv/riscv-d.cc: ...here.
* config/riscv/riscv-shorten-memrefs.c: Moved to...
* config/riscv/riscv-shorten-memrefs.cc: ...here.
* config/riscv/riscv-sr.c: Moved to...
* config/riscv/riscv-sr.cc: ...here.
* config/riscv/riscv.c: Moved to...
* config/riscv/riscv.cc: ...here.
* config/rl78/rl78-c.c: Moved to...
* config/rl78/rl78-c.cc: ...here.
* config/rl78/rl78.c: Moved to...
* config/rl78/rl78.cc: ...here.
* config/rs6000/driver-rs6000.c: Moved to...
* config/rs6000/driver-rs6000.cc: ...here.
* config/rs6000/host-darwin.c: Moved to...
* config/rs6000/host-darwin.cc: ...here.
* config/rs6000/host-ppc64-darwin.c: Moved to...
* config/rs6000/host-ppc64-darwin.cc: ...here.
* config/rs6000/rbtree.c: Moved to...
* config/rs6000/rbtree.cc: ...here.
* config/rs6000/rs6000-c.c: Moved to...
* config/rs6000/rs6000-c.cc: ...here.
* config/rs6000/rs6000-call.c: Moved to...
* config/rs6000/rs6000-call.cc: ...here.
* config/rs6000/rs6000-d.c: Moved to...
* config/rs6000/rs6000-d.cc: ...here.
* config/rs6000/rs6000-gen-builtins.c: Moved to...
* config/rs6000/rs6000-gen-builtins.cc: ...here.
* config/rs6000/rs6000-linux.c: Moved to...
* config/rs6000/rs6000-linux.cc: ...here.
* config/rs6000/rs6000-logue.c: Moved to...
* config/rs6000/rs6000-logue.cc: ...here.
* config/rs6000/rs6000-p8swap.c: Moved to...
* config/rs6000/rs6000-p8swap.cc: ...here.
* config/rs6000/rs6000-pcrel-opt.c: Moved to...
* config/rs6000/rs6000-pcrel-opt.cc: ...here.
* config/rs6000/rs6000-string.c: Moved to...
* config/rs6000/rs6000-string.cc: ...here.
* config/rs6000/rs6000.c: Moved to...
* config/rs6000/rs6000.cc: ...here.
* config/rx/rx.c: Moved to...
* config/rx/rx.cc: ...here.
* config/s390/driver-native.c: Moved to...
* config/s390/driver-native.cc: ...here.
* config/s390/s390-c.c: Moved to...
* config/s390/s390-c.cc: ...here.
* config/s390/s390-d.c: Moved to...
* config/s390/s390-d.cc: ...here.
* config/s390/s390.c: Moved to...
* config/s390/s390.cc: ...here.
* config/sh/divtab-sh4-300.c: Moved to...
* config/sh/divtab-sh4-300.cc: ...here.
* config/sh/divtab-sh4.c: Moved to...
* config/sh/divtab-sh4.cc: ...here.
* config/sh/divtab.c: Moved to...
* config/sh/divtab.cc: ...here.
* config/sh/sh-c.c: Moved to...
* config/sh/sh-c.cc: ...here.
* config/sh/sh.c: Moved to...
* config/sh/sh.cc: ...here.
* config/sol2-c.c: Moved to...
* config/sol2-c.cc: ...here.
* config/sol2-cxx.c: Moved to...
* config/sol2-cxx.cc: ...here.
* config/sol2-d.c: Moved to...
* config/sol2-d.cc: ...here.
* config/sol2-stubs.c: Moved to...
* config/sol2-stubs.cc: ...here.
* config/sol2.c: Moved to...
* config/sol2.cc: ...here.
* config/sparc/driver-sparc.c: Moved to...
* config/sparc/driver-sparc.cc: ...here.
* config/sparc/sparc-c.c: Moved to...
* config/sparc/sparc-c.cc: ...here.
* config/sparc/sparc-d.c: Moved to...
* config/sparc/sparc-d.cc: ...here.
* config/sparc/sparc.c: Moved to...
* config/sparc/sparc.cc: ...here.
* config/stormy16/stormy16.c: Moved to...
* config/stormy16/stormy16.cc: ...here.
* config/tilegx/mul-tables.c: Moved to...
* config/tilegx/mul-tables.cc: ...here.
* config/tilegx/tilegx-c.c: Moved to...
* config/tilegx/tilegx-c.cc: ...here.
* config/tilegx/tilegx.c: Moved to...
* config/tilegx/tilegx.cc: ...here.
* config/tilepro/mul-tables.c: Moved to...
* config/tilepro/mul-tables.cc: ...here.
* config/tilepro/tilepro-c.c: Moved to...
* config/tilepro/tilepro-c.cc: ...here.
* config/tilepro/tilepro.c: Moved to...
* config/tilepro/tilepro.cc: ...here.
* config/v850/v850-c.c: Moved to...
* config/v850/v850-c.cc: ...here.
* config/v850/v850.c: Moved to...
* config/v850/v850.cc: ...here.
* config/vax/vax.c: Moved to...
* config/vax/vax.cc: ...here.
* config/visium/visium.c: Moved to...
* config/visium/visium.cc: ...here.
* config/vms/vms-c.c: Moved to...
* config/vms/vms-c.cc: ...here.
* config/vms/vms-f.c: Moved to...
* config/vms/vms-f.cc: ...here.
* config/vms/vms.c: Moved to...
* config/vms/vms.cc: ...here.
* config/vxworks-c.c: Moved to...
* config/vxworks-c.cc: ...here.
* config/vxworks.c: Moved to...
* config/vxworks.cc: ...here.
* config/winnt-c.c: Moved to...
* config/winnt-c.cc: ...here.
* config/xtensa/xtensa.c: Moved to...
* config/xtensa/xtensa.cc: ...here.
* context.c: Moved to...
* context.cc: ...here.
* convert.c: Moved to...
* convert.cc: ...here.
* coverage.c: Moved to...
* coverage.cc: ...here.
* cppbuiltin.c: Moved to...
* cppbuiltin.cc: ...here.
* cppdefault.c: Moved to...
* cppdefault.cc: ...here.
* cprop.c: Moved to...
* cprop.cc: ...here.
* cse.c: Moved to...
* cse.cc: ...here.
* cselib.c: Moved to...
* cselib.cc: ...here.
* ctfc.c: Moved to...
* ctfc.cc: ...here.
* ctfout.c: Moved to...
* ctfout.cc: ...here.
* data-streamer-in.c: Moved to...
* data-streamer-in.cc: ...here.
* data-streamer-out.c: Moved to...
* data-streamer-out.cc: ...here.
* data-streamer.c: Moved to...
* data-streamer.cc: ...here.
* dbgcnt.c: Moved to...
* dbgcnt.cc: ...here.
* dbxout.c: Moved to...
* dbxout.cc: ...here.
* dce.c: Moved to...
* dce.cc: ...here.
* ddg.c: Moved to...
* ddg.cc: ...here.
* debug.c: Moved to...
* debug.cc: ...here.
* df-core.c: Moved to...
* df-core.cc: ...here.
* df-problems.c: Moved to...
* df-problems.cc: ...here.
* df-scan.c: Moved to...
* df-scan.cc: ...here.
* dfp.c: Moved to...
* dfp.cc: ...here.
* diagnostic-color.c: Moved to...
* diagnostic-color.cc: ...here.
* diagnostic-show-locus.c: Moved to...
* diagnostic-show-locus.cc: ...here.
* diagnostic-spec.c: Moved to...
* diagnostic-spec.cc: ...here.
* diagnostic.c: Moved to...
* diagnostic.cc: ...here.
* dojump.c: Moved to...
* dojump.cc: ...here.
* dominance.c: Moved to...
* dominance.cc: ...here.
* domwalk.c: Moved to...
* domwalk.cc: ...here.
* double-int.c: Moved to...
* double-int.cc: ...here.
* dse.c: Moved to...
* dse.cc: ...here.
* dumpfile.c: Moved to...
* dumpfile.cc: ...here.
* dwarf2asm.c: Moved to...
* dwarf2asm.cc: ...here.
* dwarf2cfi.c: Moved to...
* dwarf2cfi.cc: ...here.
* dwarf2ctf.c: Moved to...
* dwarf2ctf.cc: ...here.
* dwarf2out.c: Moved to...
* dwarf2out.cc: ...here.
* early-remat.c: Moved to...
* early-remat.cc: ...here.
* edit-context.c: Moved to...
* edit-context.cc: ...here.
* emit-rtl.c: Moved to...
* emit-rtl.cc: ...here.
* errors.c: Moved to...
* errors.cc: ...here.
* et-forest.c: Moved to...
* et-forest.cc: ...here.
* except.c: Moved to...
* except.cc: ...here.
* explow.c: Moved to...
* explow.cc: ...here.
* expmed.c: Moved to...
* expmed.cc: ...here.
* expr.c: Moved to...
* expr.cc: ...here.
* fibonacci_heap.c: Moved to...
* fibonacci_heap.cc: ...here.
* file-find.c: Moved to...
* file-find.cc: ...here.
* file-prefix-map.c: Moved to...
* file-prefix-map.cc: ...here.
* final.c: Moved to...
* final.cc: ...here.
* fixed-value.c: Moved to...
* fixed-value.cc: ...here.
* fold-const-call.c: Moved to...
* fold-const-call.cc: ...here.
* fold-const.c: Moved to...
* fold-const.cc: ...here.
* fp-test.c: Moved to...
* fp-test.cc: ...here.
* function-tests.c: Moved to...
* function-tests.cc: ...here.
* function.c: Moved to...
* function.cc: ...here.
* fwprop.c: Moved to...
* fwprop.cc: ...here.
* gcc-ar.c: Moved to...
* gcc-ar.cc: ...here.
* gcc-main.c: Moved to...
* gcc-main.cc: ...here.
* gcc-rich-location.c: Moved to...
* gcc-rich-location.cc: ...here.
* gcc.c: Moved to...
* gcc.cc: ...here.
* gcov-dump.c: Moved to...
* gcov-dump.cc: ...here.
* gcov-io.c: Moved to...
* gcov-io.cc: ...here.
* gcov-tool.c: Moved to...
* gcov-tool.cc: ...here.
* gcov.c: Moved to...
* gcov.cc: ...here.
* gcse-common.c: Moved to...
* gcse-common.cc: ...here.
* gcse.c: Moved to...
* gcse.cc: ...here.
* genattr-common.c: Moved to...
* genattr-common.cc: ...here.
* genattr.c: Moved to...
* genattr.cc: ...here.
* genattrtab.c: Moved to...
* genattrtab.cc: ...here.
* genautomata.c: Moved to...
* genautomata.cc: ...here.
* gencfn-macros.c: Moved to...
* gencfn-macros.cc: ...here.
* gencheck.c: Moved to...
* gencheck.cc: ...here.
* genchecksum.c: Moved to...
* genchecksum.cc: ...here.
* gencodes.c: Moved to...
* gencodes.cc: ...here.
* genconditions.c: Moved to...
* genconditions.cc: ...here.
* genconfig.c: Moved to...
* genconfig.cc: ...here.
* genconstants.c: Moved to...
* genconstants.cc: ...here.
* genemit.c: Moved to...
* genemit.cc: ...here.
* genenums.c: Moved to...
* genenums.cc: ...here.
* generic-match-head.c: Moved to...
* generic-match-head.cc: ...here.
* genextract.c: Moved to...
* genextract.cc: ...here.
* genflags.c: Moved to...
* genflags.cc: ...here.
* gengenrtl.c: Moved to...
* gengenrtl.cc: ...here.
* gengtype-parse.c: Moved to...
* gengtype-parse.cc: ...here.
* gengtype-state.c: Moved to...
* gengtype-state.cc: ...here.
* gengtype.c: Moved to...
* gengtype.cc: ...here.
* genhooks.c: Moved to...
* genhooks.cc: ...here.
* genmatch.c: Moved to...
* genmatch.cc: ...here.
* genmddeps.c: Moved to...
* genmddeps.cc: ...here.
* genmddump.c: Moved to...
* genmddump.cc: ...here.
* genmodes.c: Moved to...
* genmodes.cc: ...here.
* genopinit.c: Moved to...
* genopinit.cc: ...here.
* genoutput.c: Moved to...
* genoutput.cc: ...here.
* genpeep.c: Moved to...
* genpeep.cc: ...here.
* genpreds.c: Moved to...
* genpreds.cc: ...here.
* genrecog.c: Moved to...
* genrecog.cc: ...here.
* gensupport.c: Moved to...
* gensupport.cc: ...here.
* gentarget-def.c: Moved to...
* gentarget-def.cc: ...here.
* genversion.c: Moved to...
* genversion.cc: ...here.
* ggc-common.c: Moved to...
* ggc-common.cc: ...here.
* ggc-none.c: Moved to...
* ggc-none.cc: ...here.
* ggc-page.c: Moved to...
* ggc-page.cc: ...here.
* ggc-tests.c: Moved to...
* ggc-tests.cc: ...here.
* gimple-builder.c: Moved to...
* gimple-builder.cc: ...here.
* gimple-expr.c: Moved to...
* gimple-expr.cc: ...here.
* gimple-fold.c: Moved to...
* gimple-fold.cc: ...here.
* gimple-iterator.c: Moved to...
* gimple-iterator.cc: ...here.
* gimple-laddress.c: Moved to...
* gimple-laddress.cc: ...here.
* gimple-loop-jam.c: Moved to...
* gimple-loop-jam.cc: ...here.
* gimple-low.c: Moved to...
* gimple-low.cc: ...here.
* gimple-match-head.c: Moved to...
* gimple-match-head.cc: ...here.
* gimple-pretty-print.c: Moved to...
* gimple-pretty-print.cc: ...here.
* gimple-ssa-backprop.c: Moved to...
* gimple-ssa-backprop.cc: ...here.
* gimple-ssa-evrp-analyze.c: Moved to...
* gimple-ssa-evrp-analyze.cc: ...here.
* gimple-ssa-evrp.c: Moved to...
* gimple-ssa-evrp.cc: ...here.
* gimple-ssa-isolate-paths.c: Moved to...
* gimple-ssa-isolate-paths.cc: ...here.
* gimple-ssa-nonnull-compare.c: Moved to...
* gimple-ssa-nonnull-compare.cc: ...here.
* gimple-ssa-split-paths.c: Moved to...
* gimple-ssa-split-paths.cc: ...here.
* gimple-ssa-sprintf.c: Moved to...
* gimple-ssa-sprintf.cc: ...here.
* gimple-ssa-store-merging.c: Moved to...
* gimple-ssa-store-merging.cc: ...here.
* gimple-ssa-strength-reduction.c: Moved to...
* gimple-ssa-strength-reduction.cc: ...here.
* gimple-ssa-warn-alloca.c: Moved to...
* gimple-ssa-warn-alloca.cc: ...here.
* gimple-ssa-warn-restrict.c: Moved to...
* gimple-ssa-warn-restrict.cc: ...here.
* gimple-streamer-in.c: Moved to...
* gimple-streamer-in.cc: ...here.
* gimple-streamer-out.c: Moved to...
* gimple-streamer-out.cc: ...here.
* gimple-walk.c: Moved to...
* gimple-walk.cc: ...here.
* gimple-warn-recursion.c: Moved to...
* gimple-warn-recursion.cc: ...here.
* gimple.c: Moved to...
* gimple.cc: ...here.
* gimplify-me.c: Moved to...
* gimplify-me.cc: ...here.
* gimplify.c: Moved to...
* gimplify.cc: ...here.
* godump.c: Moved to...
* godump.cc: ...here.
* graph.c: Moved to...
* graph.cc: ...here.
* graphds.c: Moved to...
* graphds.cc: ...here.
* graphite-dependences.c: Moved to...
* graphite-dependences.cc: ...here.
* graphite-isl-ast-to-gimple.c: Moved to...
* graphite-isl-ast-to-gimple.cc: ...here.
* graphite-optimize-isl.c: Moved to...
* graphite-optimize-isl.cc: ...here.
* graphite-poly.c: Moved to...
* graphite-poly.cc: ...here.
* graphite-scop-detection.c: Moved to...
* graphite-scop-detection.cc: ...here.
* graphite-sese-to-poly.c: Moved to...
* graphite-sese-to-poly.cc: ...here.
* graphite.c: Moved to...
* graphite.cc: ...here.
* haifa-sched.c: Moved to...
* haifa-sched.cc: ...here.
* hash-map-tests.c: Moved to...
* hash-map-tests.cc: ...here.
* hash-set-tests.c: Moved to...
* hash-set-tests.cc: ...here.
* hash-table.c: Moved to...
* hash-table.cc: ...here.
* hooks.c: Moved to...
* hooks.cc: ...here.
* host-default.c: Moved to...
* host-default.cc: ...here.
* hw-doloop.c: Moved to...
* hw-doloop.cc: ...here.
* hwint.c: Moved to...
* hwint.cc: ...here.
* ifcvt.c: Moved to...
* ifcvt.cc: ...here.
* inchash.c: Moved to...
* inchash.cc: ...here.
* incpath.c: Moved to...
* incpath.cc: ...here.
* init-regs.c: Moved to...
* init-regs.cc: ...here.
* input.c: Moved to...
* input.cc: ...here.
* internal-fn.c: Moved to...
* internal-fn.cc: ...here.
* intl.c: Moved to...
* intl.cc: ...here.
* ipa-comdats.c: Moved to...
* ipa-comdats.cc: ...here.
* ipa-cp.c: Moved to...
* ipa-cp.cc: ...here.
* ipa-devirt.c: Moved to...
* ipa-devirt.cc: ...here.
* ipa-fnsummary.c: Moved to...
* ipa-fnsummary.cc: ...here.
* ipa-icf-gimple.c: Moved to...
* ipa-icf-gimple.cc: ...here.
* ipa-icf.c: Moved to...
* ipa-icf.cc: ...here.
* ipa-inline-analysis.c: Moved to...
* ipa-inline-analysis.cc: ...here.
* ipa-inline-transform.c: Moved to...
* ipa-inline-transform.cc: ...here.
* ipa-inline.c: Moved to...
* ipa-inline.cc: ...here.
* ipa-modref-tree.c: Moved to...
* ipa-modref-tree.cc: ...here.
* ipa-modref.c: Moved to...
* ipa-modref.cc: ...here.
* ipa-param-manipulation.c: Moved to...
* ipa-param-manipulation.cc: ...here.
* ipa-polymorphic-call.c: Moved to...
* ipa-polymorphic-call.cc: ...here.
* ipa-predicate.c: Moved to...
* ipa-predicate.cc: ...here.
* ipa-profile.c: Moved to...
* ipa-profile.cc: ...here.
* ipa-prop.c: Moved to...
* ipa-prop.cc: ...here.
* ipa-pure-const.c: Moved to...
* ipa-pure-const.cc: ...here.
* ipa-ref.c: Moved to...
* ipa-ref.cc: ...here.
* ipa-reference.c: Moved to...
* ipa-reference.cc: ...here.
* ipa-split.c: Moved to...
* ipa-split.cc: ...here.
* ipa-sra.c: Moved to...
* ipa-sra.cc: ...here.
* ipa-utils.c: Moved to...
* ipa-utils.cc: ...here.
* ipa-visibility.c: Moved to...
* ipa-visibility.cc: ...here.
* ipa.c: Moved to...
* ipa.cc: ...here.
* ira-build.c: Moved to...
* ira-build.cc: ...here.
* ira-color.c: Moved to...
* ira-color.cc: ...here.
* ira-conflicts.c: Moved to...
* ira-conflicts.cc: ...here.
* ira-costs.c: Moved to...
* ira-costs.cc: ...here.
* ira-emit.c: Moved to...
* ira-emit.cc: ...here.
* ira-lives.c: Moved to...
* ira-lives.cc: ...here.
* ira.c: Moved to...
* ira.cc: ...here.
* jump.c: Moved to...
* jump.cc: ...here.
* langhooks.c: Moved to...
* langhooks.cc: ...here.
* lcm.c: Moved to...
* lcm.cc: ...here.
* lists.c: Moved to...
* lists.cc: ...here.
* loop-doloop.c: Moved to...
* loop-doloop.cc: ...here.
* loop-init.c: Moved to...
* loop-init.cc: ...here.
* loop-invariant.c: Moved to...
* loop-invariant.cc: ...here.
* loop-iv.c: Moved to...
* loop-iv.cc: ...here.
* loop-unroll.c: Moved to...
* loop-unroll.cc: ...here.
* lower-subreg.c: Moved to...
* lower-subreg.cc: ...here.
* lra-assigns.c: Moved to...
* lra-assigns.cc: ...here.
* lra-coalesce.c: Moved to...
* lra-coalesce.cc: ...here.
* lra-constraints.c: Moved to...
* lra-constraints.cc: ...here.
* lra-eliminations.c: Moved to...
* lra-eliminations.cc: ...here.
* lra-lives.c: Moved to...
* lra-lives.cc: ...here.
* lra-remat.c: Moved to...
* lra-remat.cc: ...here.
* lra-spills.c: Moved to...
* lra-spills.cc: ...here.
* lra.c: Moved to...
* lra.cc: ...here.
* lto-cgraph.c: Moved to...
* lto-cgraph.cc: ...here.
* lto-compress.c: Moved to...
* lto-compress.cc: ...here.
* lto-opts.c: Moved to...
* lto-opts.cc: ...here.
* lto-section-in.c: Moved to...
* lto-section-in.cc: ...here.
* lto-section-out.c: Moved to...
* lto-section-out.cc: ...here.
* lto-streamer-in.c: Moved to...
* lto-streamer-in.cc: ...here.
* lto-streamer-out.c: Moved to...
* lto-streamer-out.cc: ...here.
* lto-streamer.c: Moved to...
* lto-streamer.cc: ...here.
* lto-wrapper.c: Moved to...
* lto-wrapper.cc: ...here.
* main.c: Moved to...
* main.cc: ...here.
* mcf.c: Moved to...
* mcf.cc: ...here.
* mode-switching.c: Moved to...
* mode-switching.cc: ...here.
* modulo-sched.c: Moved to...
* modulo-sched.cc: ...here.
* multiple_target.c: Moved to...
* multiple_target.cc: ...here.
* omp-expand.c: Moved to...
* omp-expand.cc: ...here.
* omp-general.c: Moved to...
* omp-general.cc: ...here.
* omp-low.c: Moved to...
* omp-low.cc: ...here.
* omp-offload.c: Moved to...
* omp-offload.cc: ...here.
* omp-simd-clone.c: Moved to...
* omp-simd-clone.cc: ...here.
* opt-suggestions.c: Moved to...
* opt-suggestions.cc: ...here.
* optabs-libfuncs.c: Moved to...
* optabs-libfuncs.cc: ...here.
* optabs-query.c: Moved to...
* optabs-query.cc: ...here.
* optabs-tree.c: Moved to...
* optabs-tree.cc: ...here.
* optabs.c: Moved to...
* optabs.cc: ...here.
* opts-common.c: Moved to...
* opts-common.cc: ...here.
* opts-global.c: Moved to...
* opts-global.cc: ...here.
* opts.c: Moved to...
* opts.cc: ...here.
* passes.c: Moved to...
* passes.cc: ...here.
* plugin.c: Moved to...
* plugin.cc: ...here.
* postreload-gcse.c: Moved to...
* postreload-gcse.cc: ...here.
* postreload.c: Moved to...
* postreload.cc: ...here.
* predict.c: Moved to...
* predict.cc: ...here.
* prefix.c: Moved to...
* prefix.cc: ...here.
* pretty-print.c: Moved to...
* pretty-print.cc: ...here.
* print-rtl-function.c: Moved to...
* print-rtl-function.cc: ...here.
* print-rtl.c: Moved to...
* print-rtl.cc: ...here.
* print-tree.c: Moved to...
* print-tree.cc: ...here.
* profile-count.c: Moved to...
* profile-count.cc: ...here.
* profile.c: Moved to...
* profile.cc: ...here.
* read-md.c: Moved to...
* read-md.cc: ...here.
* read-rtl-function.c: Moved to...
* read-rtl-function.cc: ...here.
* read-rtl.c: Moved to...
* read-rtl.cc: ...here.
* real.c: Moved to...
* real.cc: ...here.
* realmpfr.c: Moved to...
* realmpfr.cc: ...here.
* recog.c: Moved to...
* recog.cc: ...here.
* ree.c: Moved to...
* ree.cc: ...here.
* reg-stack.c: Moved to...
* reg-stack.cc: ...here.
* regcprop.c: Moved to...
* regcprop.cc: ...here.
* reginfo.c: Moved to...
* reginfo.cc: ...here.
* regrename.c: Moved to...
* regrename.cc: ...here.
* regstat.c: Moved to...
* regstat.cc: ...here.
* reload.c: Moved to...
* reload.cc: ...here.
* reload1.c: Moved to...
* reload1.cc: ...here.
* reorg.c: Moved to...
* reorg.cc: ...here.
* resource.c: Moved to...
* resource.cc: ...here.
* rtl-error.c: Moved to...
* rtl-error.cc: ...here.
* rtl-tests.c: Moved to...
* rtl-tests.cc: ...here.
* rtl.c: Moved to...
* rtl.cc: ...here.
* rtlanal.c: Moved to...
* rtlanal.cc: ...here.
* rtlhash.c: Moved to...
* rtlhash.cc: ...here.
* rtlhooks.c: Moved to...
* rtlhooks.cc: ...here.
* rtx-vector-builder.c: Moved to...
* rtx-vector-builder.cc: ...here.
* run-rtl-passes.c: Moved to...
* run-rtl-passes.cc: ...here.
* sancov.c: Moved to...
* sancov.cc: ...here.
* sanopt.c: Moved to...
* sanopt.cc: ...here.
* sbitmap.c: Moved to...
* sbitmap.cc: ...here.
* sched-deps.c: Moved to...
* sched-deps.cc: ...here.
* sched-ebb.c: Moved to...
* sched-ebb.cc: ...here.
* sched-rgn.c: Moved to...
* sched-rgn.cc: ...here.
* sel-sched-dump.c: Moved to...
* sel-sched-dump.cc: ...here.
* sel-sched-ir.c: Moved to...
* sel-sched-ir.cc: ...here.
* sel-sched.c: Moved to...
* sel-sched.cc: ...here.
* selftest-diagnostic.c: Moved to...
* selftest-diagnostic.cc: ...here.
* selftest-rtl.c: Moved to...
* selftest-rtl.cc: ...here.
* selftest-run-tests.c: Moved to...
* selftest-run-tests.cc: ...here.
* selftest.c: Moved to...
* selftest.cc: ...here.
* sese.c: Moved to...
* sese.cc: ...here.
* shrink-wrap.c: Moved to...
* shrink-wrap.cc: ...here.
* simplify-rtx.c: Moved to...
* simplify-rtx.cc: ...here.
* sparseset.c: Moved to...
* sparseset.cc: ...here.
* spellcheck-tree.c: Moved to...
* spellcheck-tree.cc: ...here.
* spellcheck.c: Moved to...
* spellcheck.cc: ...here.
* sreal.c: Moved to...
* sreal.cc: ...here.
* stack-ptr-mod.c: Moved to...
* stack-ptr-mod.cc: ...here.
* statistics.c: Moved to...
* statistics.cc: ...here.
* stmt.c: Moved to...
* stmt.cc: ...here.
* stor-layout.c: Moved to...
* stor-layout.cc: ...here.
* store-motion.c: Moved to...
* store-motion.cc: ...here.
* streamer-hooks.c: Moved to...
* streamer-hooks.cc: ...here.
* stringpool.c: Moved to...
* stringpool.cc: ...here.
* substring-locations.c: Moved to...
* substring-locations.cc: ...here.
* symtab.c: Moved to...
* symtab.cc: ...here.
* target-globals.c: Moved to...
* target-globals.cc: ...here.
* targhooks.c: Moved to...
* targhooks.cc: ...here.
* timevar.c: Moved to...
* timevar.cc: ...here.
* toplev.c: Moved to...
* toplev.cc: ...here.
* tracer.c: Moved to...
* tracer.cc: ...here.
* trans-mem.c: Moved to...
* trans-mem.cc: ...here.
* tree-affine.c: Moved to...
* tree-affine.cc: ...here.
* tree-call-cdce.c: Moved to...
* tree-call-cdce.cc: ...here.
* tree-cfg.c: Moved to...
* tree-cfg.cc: ...here.
* tree-cfgcleanup.c: Moved to...
* tree-cfgcleanup.cc: ...here.
* tree-chrec.c: Moved to...
* tree-chrec.cc: ...here.
* tree-complex.c: Moved to...
* tree-complex.cc: ...here.
* tree-data-ref.c: Moved to...
* tree-data-ref.cc: ...here.
* tree-dfa.c: Moved to...
* tree-dfa.cc: ...here.
* tree-diagnostic.c: Moved to...
* tree-diagnostic.cc: ...here.
* tree-dump.c: Moved to...
* tree-dump.cc: ...here.
* tree-eh.c: Moved to...
* tree-eh.cc: ...here.
* tree-emutls.c: Moved to...
* tree-emutls.cc: ...here.
* tree-if-conv.c: Moved to...
* tree-if-conv.cc: ...here.
* tree-inline.c: Moved to...
* tree-inline.cc: ...here.
* tree-into-ssa.c: Moved to...
* tree-into-ssa.cc: ...here.
* tree-iterator.c: Moved to...
* tree-iterator.cc: ...here.
* tree-loop-distribution.c: Moved to...
* tree-loop-distribution.cc: ...here.
* tree-nested.c: Moved to...
* tree-nested.cc: ...here.
* tree-nrv.c: Moved to...
* tree-nrv.cc: ...here.
* tree-object-size.c: Moved to...
* tree-object-size.cc: ...here.
* tree-outof-ssa.c: Moved to...
* tree-outof-ssa.cc: ...here.
* tree-parloops.c: Moved to...
* tree-parloops.cc: ...here.
* tree-phinodes.c: Moved to...
* tree-phinodes.cc: ...here.
* tree-predcom.c: Moved to...
* tree-predcom.cc: ...here.
* tree-pretty-print.c: Moved to...
* tree-pretty-print.cc: ...here.
* tree-profile.c: Moved to...
* tree-profile.cc: ...here.
* tree-scalar-evolution.c: Moved to...
* tree-scalar-evolution.cc: ...here.
* tree-sra.c: Moved to...
* tree-sra.cc: ...here.
* tree-ssa-address.c: Moved to...
* tree-ssa-address.cc: ...here.
* tree-ssa-alias.c: Moved to...
* tree-ssa-alias.cc: ...here.
* tree-ssa-ccp.c: Moved to...
* tree-ssa-ccp.cc: ...here.
* tree-ssa-coalesce.c: Moved to...
* tree-ssa-coalesce.cc: ...here.
* tree-ssa-copy.c: Moved to...
* tree-ssa-copy.cc: ...here.
* tree-ssa-dce.c: Moved to...
* tree-ssa-dce.cc: ...here.
* tree-ssa-dom.c: Moved to...
* tree-ssa-dom.cc: ...here.
* tree-ssa-dse.c: Moved to...
* tree-ssa-dse.cc: ...here.
* tree-ssa-forwprop.c: Moved to...
* tree-ssa-forwprop.cc: ...here.
* tree-ssa-ifcombine.c: Moved to...
* tree-ssa-ifcombine.cc: ...here.
* tree-ssa-live.c: Moved to...
* tree-ssa-live.cc: ...here.
* tree-ssa-loop-ch.c: Moved to...
* tree-ssa-loop-ch.cc: ...here.
* tree-ssa-loop-im.c: Moved to...
* tree-ssa-loop-im.cc: ...here.
* tree-ssa-loop-ivcanon.c: Moved to...
* tree-ssa-loop-ivcanon.cc: ...here.
* tree-ssa-loop-ivopts.c: Moved to...
* tree-ssa-loop-ivopts.cc: ...here.
* tree-ssa-loop-manip.c: Moved to...
* tree-ssa-loop-manip.cc: ...here.
* tree-ssa-loop-niter.c: Moved to...
* tree-ssa-loop-niter.cc: ...here.
* tree-ssa-loop-prefetch.c: Moved to...
* tree-ssa-loop-prefetch.cc: ...here.
* tree-ssa-loop-split.c: Moved to...
* tree-ssa-loop-split.cc: ...here.
* tree-ssa-loop-unswitch.c: Moved to...
* tree-ssa-loop-unswitch.cc: ...here.
* tree-ssa-loop.c: Moved to...
* tree-ssa-loop.cc: ...here.
* tree-ssa-math-opts.c: Moved to...
* tree-ssa-math-opts.cc: ...here.
* tree-ssa-operands.c: Moved to...
* tree-ssa-operands.cc: ...here.
* tree-ssa-phiopt.c: Moved to...
* tree-ssa-phiopt.cc: ...here.
* tree-ssa-phiprop.c: Moved to...
* tree-ssa-phiprop.cc: ...here.
* tree-ssa-pre.c: Moved to...
* tree-ssa-pre.cc: ...here.
* tree-ssa-propagate.c: Moved to...
* tree-ssa-propagate.cc: ...here.
* tree-ssa-reassoc.c: Moved to...
* tree-ssa-reassoc.cc: ...here.
* tree-ssa-sccvn.c: Moved to...
* tree-ssa-sccvn.cc: ...here.
* tree-ssa-scopedtables.c: Moved to...
* tree-ssa-scopedtables.cc: ...here.
* tree-ssa-sink.c: Moved to...
* tree-ssa-sink.cc: ...here.
* tree-ssa-strlen.c: Moved to...
* tree-ssa-strlen.cc: ...here.
* tree-ssa-structalias.c: Moved to...
* tree-ssa-structalias.cc: ...here.
* tree-ssa-tail-merge.c: Moved to...
* tree-ssa-tail-merge.cc: ...here.
* tree-ssa-ter.c: Moved to...
* tree-ssa-ter.cc: ...here.
* tree-ssa-threadbackward.c: Moved to...
* tree-ssa-threadbackward.cc: ...here.
* tree-ssa-threadedge.c: Moved to...
* tree-ssa-threadedge.cc: ...here.
* tree-ssa-threadupdate.c: Moved to...
* tree-ssa-threadupdate.cc: ...here.
* tree-ssa-uncprop.c: Moved to...
* tree-ssa-uncprop.cc: ...here.
* tree-ssa-uninit.c: Moved to...
* tree-ssa-uninit.cc: ...here.
* tree-ssa.c: Moved to...
* tree-ssa.cc: ...here.
* tree-ssanames.c: Moved to...
* tree-ssanames.cc: ...here.
* tree-stdarg.c: Moved to...
* tree-stdarg.cc: ...here.
* tree-streamer-in.c: Moved to...
* tree-streamer-in.cc: ...here.
* tree-streamer-out.c: Moved to...
* tree-streamer-out.cc: ...here.
* tree-streamer.c: Moved to...
* tree-streamer.cc: ...here.
* tree-switch-conversion.c: Moved to...
* tree-switch-conversion.cc: ...here.
* tree-tailcall.c: Moved to...
* tree-tailcall.cc: ...here.
* tree-vect-data-refs.c: Moved to...
* tree-vect-data-refs.cc: ...here.
* tree-vect-generic.c: Moved to...
* tree-vect-generic.cc: ...here.
* tree-vect-loop-manip.c: Moved to...
* tree-vect-loop-manip.cc: ...here.
* tree-vect-loop.c: Moved to...
* tree-vect-loop.cc: ...here.
* tree-vect-patterns.c: Moved to...
* tree-vect-patterns.cc: ...here.
* tree-vect-slp-patterns.c: Moved to...
* tree-vect-slp-patterns.cc: ...here.
* tree-vect-slp.c: Moved to...
* tree-vect-slp.cc: ...here.
* tree-vect-stmts.c: Moved to...
* tree-vect-stmts.cc: ...here.
* tree-vector-builder.c: Moved to...
* tree-vector-builder.cc: ...here.
* tree-vectorizer.c: Moved to...
* tree-vectorizer.cc: ...here.
* tree-vrp.c: Moved to...
* tree-vrp.cc: ...here.
* tree.c: Moved to...
* tree.cc: ...here.
* tsan.c: Moved to...
* tsan.cc: ...here.
* typed-splay-tree.c: Moved to...
* typed-splay-tree.cc: ...here.
* ubsan.c: Moved to...
* ubsan.cc: ...here.
* valtrack.c: Moved to...
* valtrack.cc: ...here.
* value-prof.c: Moved to...
* value-prof.cc: ...here.
* var-tracking.c: Moved to...
* var-tracking.cc: ...here.
* varasm.c: Moved to...
* varasm.cc: ...here.
* varpool.c: Moved to...
* varpool.cc: ...here.
* vec-perm-indices.c: Moved to...
* vec-perm-indices.cc: ...here.
* vec.c: Moved to...
* vec.cc: ...here.
* vmsdbgout.c: Moved to...
* vmsdbgout.cc: ...here.
* vr-values.c: Moved to...
* vr-values.cc: ...here.
* vtable-verify.c: Moved to...
* vtable-verify.cc: ...here.
* web.c: Moved to...
* web.cc: ...here.
* xcoffout.c: Moved to...
* xcoffout.cc: ...here.
gcc/c-family/ChangeLog:
* c-ada-spec.c: Moved to...
* c-ada-spec.cc: ...here.
* c-attribs.c: Moved to...
* c-attribs.cc: ...here.
* c-common.c: Moved to...
* c-common.cc: ...here.
* c-cppbuiltin.c: Moved to...
* c-cppbuiltin.cc: ...here.
* c-dump.c: Moved to...
* c-dump.cc: ...here.
* c-format.c: Moved to...
* c-format.cc: ...here.
* c-gimplify.c: Moved to...
* c-gimplify.cc: ...here.
* c-indentation.c: Moved to...
* c-indentation.cc: ...here.
* c-lex.c: Moved to...
* c-lex.cc: ...here.
* c-omp.c: Moved to...
* c-omp.cc: ...here.
* c-opts.c: Moved to...
* c-opts.cc: ...here.
* c-pch.c: Moved to...
* c-pch.cc: ...here.
* c-ppoutput.c: Moved to...
* c-ppoutput.cc: ...here.
* c-pragma.c: Moved to...
* c-pragma.cc: ...here.
* c-pretty-print.c: Moved to...
* c-pretty-print.cc: ...here.
* c-semantics.c: Moved to...
* c-semantics.cc: ...here.
* c-ubsan.c: Moved to...
* c-ubsan.cc: ...here.
* c-warn.c: Moved to...
* c-warn.cc: ...here.
* cppspec.c: Moved to...
* cppspec.cc: ...here.
* stub-objc.c: Moved to...
* stub-objc.cc: ...here.
gcc/c/ChangeLog:
* c-aux-info.c: Moved to...
* c-aux-info.cc: ...here.
* c-convert.c: Moved to...
* c-convert.cc: ...here.
* c-decl.c: Moved to...
* c-decl.cc: ...here.
* c-errors.c: Moved to...
* c-errors.cc: ...here.
* c-fold.c: Moved to...
* c-fold.cc: ...here.
* c-lang.c: Moved to...
* c-lang.cc: ...here.
* c-objc-common.c: Moved to...
* c-objc-common.cc: ...here.
* c-parser.c: Moved to...
* c-parser.cc: ...here.
* c-typeck.c: Moved to...
* c-typeck.cc: ...here.
* gccspec.c: Moved to...
* gccspec.cc: ...here.
* gimple-parser.c: Moved to...
* gimple-parser.cc: ...here.
gcc/cp/ChangeLog:
* call.c: Moved to...
* call.cc: ...here.
* class.c: Moved to...
* class.cc: ...here.
* constexpr.c: Moved to...
* constexpr.cc: ...here.
* cp-gimplify.c: Moved to...
* cp-gimplify.cc: ...here.
* cp-lang.c: Moved to...
* cp-lang.cc: ...here.
* cp-objcp-common.c: Moved to...
* cp-objcp-common.cc: ...here.
* cp-ubsan.c: Moved to...
* cp-ubsan.cc: ...here.
* cvt.c: Moved to...
* cvt.cc: ...here.
* cxx-pretty-print.c: Moved to...
* cxx-pretty-print.cc: ...here.
* decl.c: Moved to...
* decl.cc: ...here.
* decl2.c: Moved to...
* decl2.cc: ...here.
* dump.c: Moved to...
* dump.cc: ...here.
* error.c: Moved to...
* error.cc: ...here.
* except.c: Moved to...
* except.cc: ...here.
* expr.c: Moved to...
* expr.cc: ...here.
* friend.c: Moved to...
* friend.cc: ...here.
* g++spec.c: Moved to...
* g++spec.cc: ...here.
* init.c: Moved to...
* init.cc: ...here.
* lambda.c: Moved to...
* lambda.cc: ...here.
* lex.c: Moved to...
* lex.cc: ...here.
* mangle.c: Moved to...
* mangle.cc: ...here.
* method.c: Moved to...
* method.cc: ...here.
* name-lookup.c: Moved to...
* name-lookup.cc: ...here.
* optimize.c: Moved to...
* optimize.cc: ...here.
* parser.c: Moved to...
* parser.cc: ...here.
* pt.c: Moved to...
* pt.cc: ...here.
* ptree.c: Moved to...
* ptree.cc: ...here.
* rtti.c: Moved to...
* rtti.cc: ...here.
* search.c: Moved to...
* search.cc: ...here.
* semantics.c: Moved to...
* semantics.cc: ...here.
* tree.c: Moved to...
* tree.cc: ...here.
* typeck.c: Moved to...
* typeck.cc: ...here.
* typeck2.c: Moved to...
* typeck2.cc: ...here.
* vtable-class-hierarchy.c: Moved to...
* vtable-class-hierarchy.cc: ...here.
gcc/fortran/ChangeLog:
* arith.c: Moved to...
* arith.cc: ...here.
* array.c: Moved to...
* array.cc: ...here.
* bbt.c: Moved to...
* bbt.cc: ...here.
* check.c: Moved to...
* check.cc: ...here.
* class.c: Moved to...
* class.cc: ...here.
* constructor.c: Moved to...
* constructor.cc: ...here.
* convert.c: Moved to...
* convert.cc: ...here.
* cpp.c: Moved to...
* cpp.cc: ...here.
* data.c: Moved to...
* data.cc: ...here.
* decl.c: Moved to...
* decl.cc: ...here.
* dependency.c: Moved to...
* dependency.cc: ...here.
* dump-parse-tree.c: Moved to...
* dump-parse-tree.cc: ...here.
* error.c: Moved to...
* error.cc: ...here.
* expr.c: Moved to...
* expr.cc: ...here.
* f95-lang.c: Moved to...
* f95-lang.cc: ...here.
* frontend-passes.c: Moved to...
* frontend-passes.cc: ...here.
* gfortranspec.c: Moved to...
* gfortranspec.cc: ...here.
* interface.c: Moved to...
* interface.cc: ...here.
* intrinsic.c: Moved to...
* intrinsic.cc: ...here.
* io.c: Moved to...
* io.cc: ...here.
* iresolve.c: Moved to...
* iresolve.cc: ...here.
* match.c: Moved to...
* match.cc: ...here.
* matchexp.c: Moved to...
* matchexp.cc: ...here.
* misc.c: Moved to...
* misc.cc: ...here.
* module.c: Moved to...
* module.cc: ...here.
* openmp.c: Moved to...
* openmp.cc: ...here.
* options.c: Moved to...
* options.cc: ...here.
* parse.c: Moved to...
* parse.cc: ...here.
* primary.c: Moved to...
* primary.cc: ...here.
* resolve.c: Moved to...
* resolve.cc: ...here.
* scanner.c: Moved to...
* scanner.cc: ...here.
* simplify.c: Moved to...
* simplify.cc: ...here.
* st.c: Moved to...
* st.cc: ...here.
* symbol.c: Moved to...
* symbol.cc: ...here.
* target-memory.c: Moved to...
* target-memory.cc: ...here.
* trans-array.c: Moved to...
* trans-array.cc: ...here.
* trans-common.c: Moved to...
* trans-common.cc: ...here.
* trans-const.c: Moved to...
* trans-const.cc: ...here.
* trans-decl.c: Moved to...
* trans-decl.cc: ...here.
* trans-expr.c: Moved to...
* trans-expr.cc: ...here.
* trans-intrinsic.c: Moved to...
* trans-intrinsic.cc: ...here.
* trans-io.c: Moved to...
* trans-io.cc: ...here.
* trans-openmp.c: Moved to...
* trans-openmp.cc: ...here.
* trans-stmt.c: Moved to...
* trans-stmt.cc: ...here.
* trans-types.c: Moved to...
* trans-types.cc: ...here.
* trans.c: Moved to...
* trans.cc: ...here.
gcc/go/ChangeLog:
* go-backend.c: Moved to...
* go-backend.cc: ...here.
* go-lang.c: Moved to...
* go-lang.cc: ...here.
* gospec.c: Moved to...
* gospec.cc: ...here.
gcc/jit/ChangeLog:
* dummy-frontend.c: Moved to...
* dummy-frontend.cc: ...here.
* jit-builtins.c: Moved to...
* jit-builtins.cc: ...here.
* jit-logging.c: Moved to...
* jit-logging.cc: ...here.
* jit-playback.c: Moved to...
* jit-playback.cc: ...here.
* jit-recording.c: Moved to...
* jit-recording.cc: ...here.
* jit-result.c: Moved to...
* jit-result.cc: ...here.
* jit-spec.c: Moved to...
* jit-spec.cc: ...here.
* jit-tempdir.c: Moved to...
* jit-tempdir.cc: ...here.
* jit-w32.c: Moved to...
* jit-w32.cc: ...here.
* libgccjit.c: Moved to...
* libgccjit.cc: ...here.
gcc/lto/ChangeLog:
* common.c: Moved to...
* common.cc: ...here.
* lto-common.c: Moved to...
* lto-common.cc: ...here.
* lto-dump.c: Moved to...
* lto-dump.cc: ...here.
* lto-lang.c: Moved to...
* lto-lang.cc: ...here.
* lto-object.c: Moved to...
* lto-object.cc: ...here.
* lto-partition.c: Moved to...
* lto-partition.cc: ...here.
* lto-symtab.c: Moved to...
* lto-symtab.cc: ...here.
* lto.c: Moved to...
* lto.cc: ...here.
gcc/objc/ChangeLog:
* objc-act.c: Moved to...
* objc-act.cc: ...here.
* objc-encoding.c: Moved to...
* objc-encoding.cc: ...here.
* objc-gnu-runtime-abi-01.c: Moved to...
* objc-gnu-runtime-abi-01.cc: ...here.
* objc-lang.c: Moved to...
* objc-lang.cc: ...here.
* objc-map.c: Moved to...
* objc-map.cc: ...here.
* objc-next-runtime-abi-01.c: Moved to...
* objc-next-runtime-abi-01.cc: ...here.
* objc-next-runtime-abi-02.c: Moved to...
* objc-next-runtime-abi-02.cc: ...here.
* objc-runtime-shared-support.c: Moved to...
* objc-runtime-shared-support.cc: ...here.
gcc/objcp/ChangeLog:
* objcp-decl.c: Moved to...
* objcp-decl.cc: ...here.
* objcp-lang.c: Moved to...
* objcp-lang.cc: ...here.
libcpp/ChangeLog:
* charset.c: Moved to...
* charset.cc: ...here.
* directives.c: Moved to...
* directives.cc: ...here.
* errors.c: Moved to...
* errors.cc: ...here.
* expr.c: Moved to...
* expr.cc: ...here.
* files.c: Moved to...
* files.cc: ...here.
* identifiers.c: Moved to...
* identifiers.cc: ...here.
* init.c: Moved to...
* init.cc: ...here.
* lex.c: Moved to...
* lex.cc: ...here.
* line-map.c: Moved to...
* line-map.cc: ...here.
* macro.c: Moved to...
* macro.cc: ...here.
* makeucnid.c: Moved to...
* makeucnid.cc: ...here.
* mkdeps.c: Moved to...
* mkdeps.cc: ...here.
* pch.c: Moved to...
* pch.cc: ...here.
* symtab.c: Moved to...
* symtab.cc: ...here.
* traditional.c: Moved to...
* traditional.cc: ...here.
Diffstat (limited to 'gcc/c-family/c-omp.c')
-rw-r--r-- | gcc/c-family/c-omp.c | 3265 |
1 files changed, 0 insertions, 3265 deletions
diff --git a/gcc/c-family/c-omp.c b/gcc/c-family/c-omp.c deleted file mode 100644 index 400fd4e..0000000 --- a/gcc/c-family/c-omp.c +++ /dev/null @@ -1,3265 +0,0 @@ -/* This file contains routines to construct OpenACC and OpenMP constructs, - called from parsing in the C and C++ front ends. - - Copyright (C) 2005-2022 Free Software Foundation, Inc. - Contributed by Richard Henderson <rth@redhat.com>, - Diego Novillo <dnovillo@redhat.com>. - -This file is part of GCC. - -GCC is free software; you can redistribute it and/or modify it under -the terms of the GNU General Public License as published by the Free -Software Foundation; either version 3, or (at your option) any later -version. - -GCC is distributed in the hope that it will be useful, but WITHOUT ANY -WARRANTY; without even the implied warranty of MERCHANTABILITY or -FITNESS FOR A PARTICULAR PURPOSE. See the GNU General Public License -for more details. - -You should have received a copy of the GNU General Public License -along with GCC; see the file COPYING3. If not see -<http://www.gnu.org/licenses/>. */ - -#include "config.h" -#include "system.h" -#include "coretypes.h" -#include "options.h" -#include "c-common.h" -#include "gimple-expr.h" -#include "c-pragma.h" -#include "stringpool.h" -#include "omp-general.h" -#include "gomp-constants.h" -#include "memmodel.h" -#include "attribs.h" -#include "gimplify.h" -#include "langhooks.h" -#include "bitmap.h" -#include "gimple-fold.h" - - -/* Complete a #pragma oacc wait construct. LOC is the location of - the #pragma. */ - -tree -c_finish_oacc_wait (location_t loc, tree parms, tree clauses) -{ - const int nparms = list_length (parms); - tree stmt, t; - vec<tree, va_gc> *args; - - vec_alloc (args, nparms + 2); - stmt = builtin_decl_explicit (BUILT_IN_GOACC_WAIT); - - if (omp_find_clause (clauses, OMP_CLAUSE_ASYNC)) - t = OMP_CLAUSE_ASYNC_EXPR (clauses); - else - t = build_int_cst (integer_type_node, GOMP_ASYNC_SYNC); - - args->quick_push (t); - args->quick_push (build_int_cst (integer_type_node, nparms)); - - for (t = parms; t; t = TREE_CHAIN (t)) - { - if (TREE_CODE (OMP_CLAUSE_WAIT_EXPR (t)) == INTEGER_CST) - args->quick_push (build_int_cst (integer_type_node, - TREE_INT_CST_LOW (OMP_CLAUSE_WAIT_EXPR (t)))); - else - args->quick_push (OMP_CLAUSE_WAIT_EXPR (t)); - } - - stmt = build_call_expr_loc_vec (loc, stmt, args); - - vec_free (args); - - return stmt; -} - -/* Complete a #pragma omp master construct. STMT is the structured-block - that follows the pragma. LOC is the location of the #pragma. */ - -tree -c_finish_omp_master (location_t loc, tree stmt) -{ - tree t = add_stmt (build1 (OMP_MASTER, void_type_node, stmt)); - SET_EXPR_LOCATION (t, loc); - return t; -} - -/* Complete a #pragma omp masked construct. BODY is the structured-block - that follows the pragma. LOC is the location of the #pragma. */ - -tree -c_finish_omp_masked (location_t loc, tree body, tree clauses) -{ - tree stmt = make_node (OMP_MASKED); - TREE_TYPE (stmt) = void_type_node; - OMP_MASKED_BODY (stmt) = body; - OMP_MASKED_CLAUSES (stmt) = clauses; - SET_EXPR_LOCATION (stmt, loc); - return add_stmt (stmt); -} - -/* Complete a #pragma omp taskgroup construct. BODY is the structured-block - that follows the pragma. LOC is the location of the #pragma. */ - -tree -c_finish_omp_taskgroup (location_t loc, tree body, tree clauses) -{ - tree stmt = make_node (OMP_TASKGROUP); - TREE_TYPE (stmt) = void_type_node; - OMP_TASKGROUP_BODY (stmt) = body; - OMP_TASKGROUP_CLAUSES (stmt) = clauses; - SET_EXPR_LOCATION (stmt, loc); - return add_stmt (stmt); -} - -/* Complete a #pragma omp critical construct. BODY is the structured-block - that follows the pragma, NAME is the identifier in the pragma, or null - if it was omitted. LOC is the location of the #pragma. */ - -tree -c_finish_omp_critical (location_t loc, tree body, tree name, tree clauses) -{ - gcc_assert (!clauses || OMP_CLAUSE_CODE (clauses) == OMP_CLAUSE_HINT); - if (name == NULL_TREE - && clauses != NULL_TREE - && integer_nonzerop (OMP_CLAUSE_HINT_EXPR (clauses))) - { - error_at (OMP_CLAUSE_LOCATION (clauses), - "%<#pragma omp critical%> with %<hint%> clause requires " - "a name, except when %<omp_sync_hint_none%> is used"); - return error_mark_node; - } - - tree stmt = make_node (OMP_CRITICAL); - TREE_TYPE (stmt) = void_type_node; - OMP_CRITICAL_BODY (stmt) = body; - OMP_CRITICAL_NAME (stmt) = name; - OMP_CRITICAL_CLAUSES (stmt) = clauses; - SET_EXPR_LOCATION (stmt, loc); - return add_stmt (stmt); -} - -/* Complete a #pragma omp ordered construct. STMT is the structured-block - that follows the pragma. LOC is the location of the #pragma. */ - -tree -c_finish_omp_ordered (location_t loc, tree clauses, tree stmt) -{ - tree t = make_node (OMP_ORDERED); - TREE_TYPE (t) = void_type_node; - OMP_ORDERED_BODY (t) = stmt; - if (!flag_openmp /* flag_openmp_simd */ - && (OMP_CLAUSE_CODE (clauses) != OMP_CLAUSE_SIMD - || OMP_CLAUSE_CHAIN (clauses))) - clauses = build_omp_clause (loc, OMP_CLAUSE_SIMD); - OMP_ORDERED_CLAUSES (t) = clauses; - SET_EXPR_LOCATION (t, loc); - return add_stmt (t); -} - - -/* Complete a #pragma omp barrier construct. LOC is the location of - the #pragma. */ - -void -c_finish_omp_barrier (location_t loc) -{ - tree x; - - x = builtin_decl_explicit (BUILT_IN_GOMP_BARRIER); - x = build_call_expr_loc (loc, x, 0); - add_stmt (x); -} - - -/* Complete a #pragma omp taskwait construct. LOC is the location of the - pragma. */ - -void -c_finish_omp_taskwait (location_t loc) -{ - tree x; - - x = builtin_decl_explicit (BUILT_IN_GOMP_TASKWAIT); - x = build_call_expr_loc (loc, x, 0); - add_stmt (x); -} - - -/* Complete a #pragma omp taskyield construct. LOC is the location of the - pragma. */ - -void -c_finish_omp_taskyield (location_t loc) -{ - tree x; - - x = builtin_decl_explicit (BUILT_IN_GOMP_TASKYIELD); - x = build_call_expr_loc (loc, x, 0); - add_stmt (x); -} - - -/* Complete a #pragma omp atomic construct. For CODE OMP_ATOMIC - the expression to be implemented atomically is LHS opcode= RHS. - For OMP_ATOMIC_READ V = LHS, for OMP_ATOMIC_CAPTURE_{NEW,OLD} LHS - opcode= RHS with the new or old content of LHS returned. - LOC is the location of the atomic statement. The value returned - is either error_mark_node (if the construct was erroneous) or an - OMP_ATOMIC* node which should be added to the current statement - tree with add_stmt. If TEST is set, avoid calling save_expr - or create_tmp_var*. */ - -tree -c_finish_omp_atomic (location_t loc, enum tree_code code, - enum tree_code opcode, tree lhs, tree rhs, - tree v, tree lhs1, tree rhs1, tree r, bool swapped, - enum omp_memory_order memory_order, bool weak, - bool test) -{ - tree x, type, addr, pre = NULL_TREE, rtmp = NULL_TREE, vtmp = NULL_TREE; - HOST_WIDE_INT bitpos = 0, bitsize = 0; - enum tree_code orig_opcode = opcode; - - if (lhs == error_mark_node || rhs == error_mark_node - || v == error_mark_node || lhs1 == error_mark_node - || rhs1 == error_mark_node || r == error_mark_node) - return error_mark_node; - - /* ??? According to one reading of the OpenMP spec, complex type are - supported, but there are no atomic stores for any architecture. - But at least icc 9.0 doesn't support complex types here either. - And lets not even talk about vector types... */ - type = TREE_TYPE (lhs); - if (!INTEGRAL_TYPE_P (type) - && !POINTER_TYPE_P (type) - && !SCALAR_FLOAT_TYPE_P (type)) - { - error_at (loc, "invalid expression type for %<#pragma omp atomic%>"); - return error_mark_node; - } - if (TYPE_ATOMIC (type)) - { - error_at (loc, "%<_Atomic%> expression in %<#pragma omp atomic%>"); - return error_mark_node; - } - if (r && r != void_list_node && !INTEGRAL_TYPE_P (TREE_TYPE (r))) - { - error_at (loc, "%<#pragma omp atomic compare capture%> with non-integral " - "comparison result"); - return error_mark_node; - } - - if (opcode == RDIV_EXPR) - opcode = TRUNC_DIV_EXPR; - - /* ??? Validate that rhs does not overlap lhs. */ - tree blhs = NULL; - if (TREE_CODE (lhs) == COMPONENT_REF - && TREE_CODE (TREE_OPERAND (lhs, 1)) == FIELD_DECL - && DECL_C_BIT_FIELD (TREE_OPERAND (lhs, 1)) - && DECL_BIT_FIELD_REPRESENTATIVE (TREE_OPERAND (lhs, 1))) - { - tree field = TREE_OPERAND (lhs, 1); - tree repr = DECL_BIT_FIELD_REPRESENTATIVE (field); - if (tree_fits_uhwi_p (DECL_FIELD_OFFSET (field)) - && tree_fits_uhwi_p (DECL_FIELD_OFFSET (repr))) - bitpos = (tree_to_uhwi (DECL_FIELD_OFFSET (field)) - - tree_to_uhwi (DECL_FIELD_OFFSET (repr))) * BITS_PER_UNIT; - else - bitpos = 0; - bitpos += (tree_to_uhwi (DECL_FIELD_BIT_OFFSET (field)) - - tree_to_uhwi (DECL_FIELD_BIT_OFFSET (repr))); - gcc_assert (tree_fits_shwi_p (DECL_SIZE (field))); - bitsize = tree_to_shwi (DECL_SIZE (field)); - blhs = lhs; - type = TREE_TYPE (repr); - lhs = build3 (COMPONENT_REF, TREE_TYPE (repr), TREE_OPERAND (lhs, 0), - repr, TREE_OPERAND (lhs, 2)); - } - - /* Take and save the address of the lhs. From then on we'll reference it - via indirection. */ - addr = build_unary_op (loc, ADDR_EXPR, lhs, false); - if (addr == error_mark_node) - return error_mark_node; - if (!test) - addr = save_expr (addr); - if (!test - && TREE_CODE (addr) != SAVE_EXPR - && (TREE_CODE (addr) != ADDR_EXPR - || !VAR_P (TREE_OPERAND (addr, 0)))) - { - /* Make sure LHS is simple enough so that goa_lhs_expr_p can recognize - it even after unsharing function body. */ - tree var = create_tmp_var_raw (TREE_TYPE (addr)); - DECL_CONTEXT (var) = current_function_decl; - addr = build4 (TARGET_EXPR, TREE_TYPE (addr), var, addr, NULL, NULL); - } - tree orig_lhs = lhs; - lhs = build_indirect_ref (loc, addr, RO_NULL); - tree new_lhs = lhs; - - if (code == OMP_ATOMIC_READ) - { - x = build1 (OMP_ATOMIC_READ, type, addr); - SET_EXPR_LOCATION (x, loc); - OMP_ATOMIC_MEMORY_ORDER (x) = memory_order; - gcc_assert (!weak); - if (blhs) - x = build3_loc (loc, BIT_FIELD_REF, TREE_TYPE (blhs), x, - bitsize_int (bitsize), bitsize_int (bitpos)); - return build_modify_expr (loc, v, NULL_TREE, NOP_EXPR, - loc, x, NULL_TREE); - } - - /* There are lots of warnings, errors, and conversions that need to happen - in the course of interpreting a statement. Use the normal mechanisms - to do this, and then take it apart again. */ - if (blhs) - { - lhs = build3_loc (loc, BIT_FIELD_REF, TREE_TYPE (blhs), lhs, - bitsize_int (bitsize), bitsize_int (bitpos)); - if (opcode == COND_EXPR) - { - bool save = in_late_binary_op; - in_late_binary_op = true; - std::swap (rhs, rhs1); - rhs1 = build_binary_op (loc, EQ_EXPR, lhs, rhs1, true); - in_late_binary_op = save; - } - else if (swapped) - rhs = build_binary_op (loc, opcode, rhs, lhs, true); - else if (opcode != NOP_EXPR) - rhs = build_binary_op (loc, opcode, lhs, rhs, true); - opcode = NOP_EXPR; - } - else if (opcode == COND_EXPR) - { - bool save = in_late_binary_op; - in_late_binary_op = true; - std::swap (rhs, rhs1); - rhs1 = build_binary_op (loc, EQ_EXPR, lhs, rhs1, true); - in_late_binary_op = save; - opcode = NOP_EXPR; - } - else if (swapped) - { - rhs = build_binary_op (loc, opcode, rhs, lhs, true); - opcode = NOP_EXPR; - } - bool save = in_late_binary_op; - in_late_binary_op = true; - x = build_modify_expr (loc, blhs ? blhs : lhs, NULL_TREE, opcode, - loc, rhs, NULL_TREE); - in_late_binary_op = save; - if (x == error_mark_node) - return error_mark_node; - if (TREE_CODE (x) == COMPOUND_EXPR) - { - pre = TREE_OPERAND (x, 0); - gcc_assert (TREE_CODE (pre) == SAVE_EXPR || tree_invariant_p (pre)); - x = TREE_OPERAND (x, 1); - } - gcc_assert (TREE_CODE (x) == MODIFY_EXPR); - rhs = TREE_OPERAND (x, 1); - - if (blhs) - rhs = build3_loc (loc, BIT_INSERT_EXPR, type, new_lhs, - rhs, bitsize_int (bitpos)); - if (orig_opcode == COND_EXPR) - { - if (error_operand_p (rhs1)) - return error_mark_node; - gcc_assert (TREE_CODE (rhs1) == EQ_EXPR); - tree cmptype = TREE_TYPE (TREE_OPERAND (rhs1, 0)); - if (SCALAR_FLOAT_TYPE_P (cmptype) && !test) - { - bool clear_padding = false; - HOST_WIDE_INT non_padding_start = 0; - HOST_WIDE_INT non_padding_end = 0; - if (BITS_PER_UNIT == 8 - && CHAR_BIT == 8 - && clear_padding_type_may_have_padding_p (cmptype)) - { - HOST_WIDE_INT sz = int_size_in_bytes (cmptype), i; - gcc_assert (sz > 0); - unsigned char *buf = XALLOCAVEC (unsigned char, sz); - memset (buf, ~0, sz); - clear_type_padding_in_mask (cmptype, buf); - for (i = 0; i < sz; i++) - if (buf[i] != (unsigned char) ~0) - { - clear_padding = true; - break; - } - if (clear_padding && buf[i] == 0) - { - /* Try to optimize. In the common case where - non-padding bits are all continuous and start - and end at a byte boundary, we can just adjust - the memcmp call arguments and don't need to - emit __builtin_clear_padding calls. */ - if (i == 0) - { - for (i = 0; i < sz; i++) - if (buf[i] != 0) - break; - if (i < sz && buf[i] == (unsigned char) ~0) - { - non_padding_start = i; - for (; i < sz; i++) - if (buf[i] != (unsigned char) ~0) - break; - } - else - i = 0; - } - if (i != 0) - { - non_padding_end = i; - for (; i < sz; i++) - if (buf[i] != 0) - { - non_padding_start = 0; - non_padding_end = 0; - break; - } - } - } - } - tree inttype = NULL_TREE; - if (!clear_padding && tree_fits_uhwi_p (TYPE_SIZE (cmptype))) - { - HOST_WIDE_INT prec = tree_to_uhwi (TYPE_SIZE (cmptype)); - inttype = c_common_type_for_size (prec, 1); - if (inttype - && (!tree_int_cst_equal (TYPE_SIZE (cmptype), - TYPE_SIZE (inttype)) - || TYPE_PRECISION (inttype) != prec)) - inttype = NULL_TREE; - } - if (inttype) - { - TREE_OPERAND (rhs1, 0) - = build1_loc (loc, VIEW_CONVERT_EXPR, inttype, - TREE_OPERAND (rhs1, 0)); - TREE_OPERAND (rhs1, 1) - = build1_loc (loc, VIEW_CONVERT_EXPR, inttype, - TREE_OPERAND (rhs1, 1)); - } - else - { - tree pcmptype = build_pointer_type (cmptype); - tree tmp1 = create_tmp_var_raw (cmptype); - TREE_ADDRESSABLE (tmp1) = 1; - DECL_CONTEXT (tmp1) = current_function_decl; - tmp1 = build4 (TARGET_EXPR, cmptype, tmp1, - TREE_OPERAND (rhs1, 0), NULL, NULL); - tmp1 = build1 (ADDR_EXPR, pcmptype, tmp1); - tree tmp2 = create_tmp_var_raw (cmptype); - TREE_ADDRESSABLE (tmp2) = 1; - DECL_CONTEXT (tmp2) = current_function_decl; - tmp2 = build4 (TARGET_EXPR, cmptype, tmp2, - TREE_OPERAND (rhs1, 1), NULL, NULL); - tmp2 = build1 (ADDR_EXPR, pcmptype, tmp2); - if (non_padding_start) - { - tmp1 = build2 (POINTER_PLUS_EXPR, pcmptype, tmp1, - size_int (non_padding_start)); - tmp2 = build2 (POINTER_PLUS_EXPR, pcmptype, tmp2, - size_int (non_padding_start)); - } - tree fndecl = builtin_decl_explicit (BUILT_IN_MEMCMP); - rhs1 = build_call_expr_loc (loc, fndecl, 3, tmp1, tmp2, - non_padding_end - ? size_int (non_padding_end - - non_padding_start) - : TYPE_SIZE_UNIT (cmptype)); - rhs1 = build2 (EQ_EXPR, boolean_type_node, rhs1, - integer_zero_node); - if (clear_padding && non_padding_end == 0) - { - fndecl = builtin_decl_explicit (BUILT_IN_CLEAR_PADDING); - tree cp1 = build_call_expr_loc (loc, fndecl, 1, tmp1); - tree cp2 = build_call_expr_loc (loc, fndecl, 1, tmp2); - rhs1 = omit_two_operands_loc (loc, boolean_type_node, - rhs1, cp2, cp1); - } - } - } - if (r && test) - rtmp = rhs1; - else if (r) - { - tree var = create_tmp_var_raw (boolean_type_node); - DECL_CONTEXT (var) = current_function_decl; - rtmp = build4 (TARGET_EXPR, boolean_type_node, var, - boolean_false_node, NULL, NULL); - save = in_late_binary_op; - in_late_binary_op = true; - x = build_modify_expr (loc, var, NULL_TREE, NOP_EXPR, - loc, rhs1, NULL_TREE); - in_late_binary_op = save; - if (x == error_mark_node) - return error_mark_node; - gcc_assert (TREE_CODE (x) == MODIFY_EXPR - && TREE_OPERAND (x, 0) == var); - TREE_OPERAND (x, 0) = rtmp; - rhs1 = omit_one_operand_loc (loc, boolean_type_node, x, rtmp); - } - rhs = build3_loc (loc, COND_EXPR, type, rhs1, rhs, new_lhs); - rhs1 = NULL_TREE; - } - - /* Punt the actual generation of atomic operations to common code. */ - if (code == OMP_ATOMIC) - type = void_type_node; - x = build2 (code, type, addr, rhs); - SET_EXPR_LOCATION (x, loc); - OMP_ATOMIC_MEMORY_ORDER (x) = memory_order; - OMP_ATOMIC_WEAK (x) = weak; - - /* Generally it is hard to prove lhs1 and lhs are the same memory - location, just diagnose different variables. */ - if (rhs1 - && VAR_P (rhs1) - && VAR_P (orig_lhs) - && rhs1 != orig_lhs - && !test) - { - if (code == OMP_ATOMIC) - error_at (loc, "%<#pragma omp atomic update%> uses two different " - "variables for memory"); - else - error_at (loc, "%<#pragma omp atomic capture%> uses two different " - "variables for memory"); - return error_mark_node; - } - - if (lhs1 - && lhs1 != orig_lhs - && TREE_CODE (lhs1) == COMPONENT_REF - && TREE_CODE (TREE_OPERAND (lhs1, 1)) == FIELD_DECL - && DECL_C_BIT_FIELD (TREE_OPERAND (lhs1, 1)) - && DECL_BIT_FIELD_REPRESENTATIVE (TREE_OPERAND (lhs1, 1))) - { - tree field = TREE_OPERAND (lhs1, 1); - tree repr = DECL_BIT_FIELD_REPRESENTATIVE (field); - lhs1 = build3 (COMPONENT_REF, TREE_TYPE (repr), TREE_OPERAND (lhs1, 0), - repr, TREE_OPERAND (lhs1, 2)); - } - if (rhs1 - && rhs1 != orig_lhs - && TREE_CODE (rhs1) == COMPONENT_REF - && TREE_CODE (TREE_OPERAND (rhs1, 1)) == FIELD_DECL - && DECL_C_BIT_FIELD (TREE_OPERAND (rhs1, 1)) - && DECL_BIT_FIELD_REPRESENTATIVE (TREE_OPERAND (rhs1, 1))) - { - tree field = TREE_OPERAND (rhs1, 1); - tree repr = DECL_BIT_FIELD_REPRESENTATIVE (field); - rhs1 = build3 (COMPONENT_REF, TREE_TYPE (repr), TREE_OPERAND (rhs1, 0), - repr, TREE_OPERAND (rhs1, 2)); - } - - if (code != OMP_ATOMIC) - { - /* Generally it is hard to prove lhs1 and lhs are the same memory - location, just diagnose different variables. */ - if (lhs1 && VAR_P (lhs1) && VAR_P (orig_lhs)) - { - if (lhs1 != orig_lhs && !test) - { - error_at (loc, "%<#pragma omp atomic capture%> uses two " - "different variables for memory"); - return error_mark_node; - } - } - if (blhs) - x = build3_loc (loc, BIT_FIELD_REF, TREE_TYPE (blhs), x, - bitsize_int (bitsize), bitsize_int (bitpos)); - if (r && !test) - { - vtmp = create_tmp_var_raw (TREE_TYPE (x)); - DECL_CONTEXT (vtmp) = current_function_decl; - } - else - vtmp = v; - x = build_modify_expr (loc, vtmp, NULL_TREE, NOP_EXPR, - loc, x, NULL_TREE); - if (x == error_mark_node) - return error_mark_node; - type = TREE_TYPE (x); - if (r && !test) - { - vtmp = build4 (TARGET_EXPR, TREE_TYPE (vtmp), vtmp, - build_zero_cst (TREE_TYPE (vtmp)), NULL, NULL); - gcc_assert (TREE_CODE (x) == MODIFY_EXPR - && TREE_OPERAND (x, 0) == TARGET_EXPR_SLOT (vtmp)); - TREE_OPERAND (x, 0) = vtmp; - } - if (rhs1 && rhs1 != orig_lhs) - { - tree rhs1addr = build_unary_op (loc, ADDR_EXPR, rhs1, false); - if (rhs1addr == error_mark_node) - return error_mark_node; - x = omit_one_operand_loc (loc, type, x, rhs1addr); - } - if (lhs1 && lhs1 != orig_lhs) - { - tree lhs1addr = build_unary_op (loc, ADDR_EXPR, lhs1, false); - if (lhs1addr == error_mark_node) - return error_mark_node; - if (code == OMP_ATOMIC_CAPTURE_OLD) - x = omit_one_operand_loc (loc, type, x, lhs1addr); - else - { - if (!test) - x = save_expr (x); - x = omit_two_operands_loc (loc, type, x, x, lhs1addr); - } - } - } - else if (rhs1 && rhs1 != orig_lhs) - { - tree rhs1addr = build_unary_op (loc, ADDR_EXPR, rhs1, false); - if (rhs1addr == error_mark_node) - return error_mark_node; - x = omit_one_operand_loc (loc, type, x, rhs1addr); - } - - if (pre) - x = omit_one_operand_loc (loc, type, x, pre); - if (r && r != void_list_node) - { - in_late_binary_op = true; - tree x2 = build_modify_expr (loc, r, NULL_TREE, NOP_EXPR, - loc, rtmp, NULL_TREE); - in_late_binary_op = save; - if (x2 == error_mark_node) - return error_mark_node; - x = omit_one_operand_loc (loc, TREE_TYPE (x2), x2, x); - } - if (v && vtmp != v) - { - in_late_binary_op = true; - tree x2 = build_modify_expr (loc, v, NULL_TREE, NOP_EXPR, - loc, vtmp, NULL_TREE); - in_late_binary_op = save; - if (x2 == error_mark_node) - return error_mark_node; - x2 = build3_loc (loc, COND_EXPR, void_type_node, rtmp, - void_node, x2); - x = omit_one_operand_loc (loc, TREE_TYPE (x2), x2, x); - } - return x; -} - - -/* Return true if TYPE is the implementation's omp_depend_t. */ - -bool -c_omp_depend_t_p (tree type) -{ - type = TYPE_MAIN_VARIANT (type); - return (TREE_CODE (type) == RECORD_TYPE - && TYPE_NAME (type) - && ((TREE_CODE (TYPE_NAME (type)) == TYPE_DECL - ? DECL_NAME (TYPE_NAME (type)) : TYPE_NAME (type)) - == get_identifier ("omp_depend_t")) - && (!TYPE_CONTEXT (type) - || TREE_CODE (TYPE_CONTEXT (type)) == TRANSLATION_UNIT_DECL) - && COMPLETE_TYPE_P (type) - && TREE_CODE (TYPE_SIZE (type)) == INTEGER_CST - && !compare_tree_int (TYPE_SIZE (type), - 2 * tree_to_uhwi (TYPE_SIZE (ptr_type_node)))); -} - - -/* Complete a #pragma omp depobj construct. LOC is the location of the - #pragma. */ - -void -c_finish_omp_depobj (location_t loc, tree depobj, - enum omp_clause_depend_kind kind, tree clause) -{ - tree t = NULL_TREE; - if (!error_operand_p (depobj)) - { - if (!c_omp_depend_t_p (TREE_TYPE (depobj))) - { - error_at (EXPR_LOC_OR_LOC (depobj, loc), - "type of %<depobj%> expression is not %<omp_depend_t%>"); - depobj = error_mark_node; - } - else if (TYPE_READONLY (TREE_TYPE (depobj))) - { - error_at (EXPR_LOC_OR_LOC (depobj, loc), - "%<const%> qualified %<depobj%> expression"); - depobj = error_mark_node; - } - } - else - depobj = error_mark_node; - - if (clause == error_mark_node) - return; - - if (clause) - { - gcc_assert (TREE_CODE (clause) == OMP_CLAUSE - && OMP_CLAUSE_CODE (clause) == OMP_CLAUSE_DEPEND); - if (OMP_CLAUSE_CHAIN (clause)) - error_at (OMP_CLAUSE_LOCATION (clause), - "more than one locator in %<depend%> clause on %<depobj%> " - "construct"); - switch (OMP_CLAUSE_DEPEND_KIND (clause)) - { - case OMP_CLAUSE_DEPEND_DEPOBJ: - error_at (OMP_CLAUSE_LOCATION (clause), - "%<depobj%> dependence type specified in %<depend%> " - "clause on %<depobj%> construct"); - return; - case OMP_CLAUSE_DEPEND_SOURCE: - case OMP_CLAUSE_DEPEND_SINK: - error_at (OMP_CLAUSE_LOCATION (clause), - "%<depend(%s)%> is only allowed in %<omp ordered%>", - OMP_CLAUSE_DEPEND_KIND (clause) == OMP_CLAUSE_DEPEND_SOURCE - ? "source" : "sink"); - return; - case OMP_CLAUSE_DEPEND_IN: - case OMP_CLAUSE_DEPEND_OUT: - case OMP_CLAUSE_DEPEND_INOUT: - case OMP_CLAUSE_DEPEND_MUTEXINOUTSET: - kind = OMP_CLAUSE_DEPEND_KIND (clause); - t = OMP_CLAUSE_DECL (clause); - gcc_assert (t); - if (TREE_CODE (t) == TREE_LIST - && TREE_PURPOSE (t) - && TREE_CODE (TREE_PURPOSE (t)) == TREE_VEC) - { - error_at (OMP_CLAUSE_LOCATION (clause), - "%<iterator%> modifier may not be specified on " - "%<depobj%> construct"); - return; - } - if (TREE_CODE (t) == COMPOUND_EXPR) - { - tree t1 = build_fold_addr_expr (TREE_OPERAND (t, 1)); - t = build2 (COMPOUND_EXPR, TREE_TYPE (t1), TREE_OPERAND (t, 0), - t1); - } - else - t = build_fold_addr_expr (t); - break; - default: - gcc_unreachable (); - } - } - else - gcc_assert (kind != OMP_CLAUSE_DEPEND_SOURCE); - - if (depobj == error_mark_node) - return; - - depobj = build_fold_addr_expr_loc (EXPR_LOC_OR_LOC (depobj, loc), depobj); - tree dtype - = build_pointer_type_for_mode (ptr_type_node, TYPE_MODE (ptr_type_node), - true); - depobj = fold_convert (dtype, depobj); - tree r; - if (clause) - { - depobj = save_expr (depobj); - r = build_indirect_ref (loc, depobj, RO_UNARY_STAR); - add_stmt (build2 (MODIFY_EXPR, void_type_node, r, t)); - } - int k; - switch (kind) - { - case OMP_CLAUSE_DEPEND_IN: - k = GOMP_DEPEND_IN; - break; - case OMP_CLAUSE_DEPEND_OUT: - k = GOMP_DEPEND_OUT; - break; - case OMP_CLAUSE_DEPEND_INOUT: - k = GOMP_DEPEND_INOUT; - break; - case OMP_CLAUSE_DEPEND_MUTEXINOUTSET: - k = GOMP_DEPEND_MUTEXINOUTSET; - break; - case OMP_CLAUSE_DEPEND_LAST: - k = -1; - break; - default: - gcc_unreachable (); - } - t = build_int_cst (ptr_type_node, k); - depobj = build2_loc (loc, POINTER_PLUS_EXPR, TREE_TYPE (depobj), depobj, - TYPE_SIZE_UNIT (ptr_type_node)); - r = build_indirect_ref (loc, depobj, RO_UNARY_STAR); - add_stmt (build2 (MODIFY_EXPR, void_type_node, r, t)); -} - - -/* Complete a #pragma omp flush construct. We don't do anything with - the variable list that the syntax allows. LOC is the location of - the #pragma. */ - -void -c_finish_omp_flush (location_t loc, int mo) -{ - tree x; - - if (mo == MEMMODEL_LAST || mo == MEMMODEL_SEQ_CST) - { - x = builtin_decl_explicit (BUILT_IN_SYNC_SYNCHRONIZE); - x = build_call_expr_loc (loc, x, 0); - } - else - { - x = builtin_decl_explicit (BUILT_IN_ATOMIC_THREAD_FENCE); - x = build_call_expr_loc (loc, x, 1, - build_int_cst (integer_type_node, mo)); - } - add_stmt (x); -} - - -/* Check and canonicalize OMP_FOR increment expression. - Helper function for c_finish_omp_for. */ - -static tree -check_omp_for_incr_expr (location_t loc, tree exp, tree decl) -{ - tree t; - - if (!INTEGRAL_TYPE_P (TREE_TYPE (exp)) - || TYPE_PRECISION (TREE_TYPE (exp)) < TYPE_PRECISION (TREE_TYPE (decl))) - return error_mark_node; - - if (exp == decl) - return build_int_cst (TREE_TYPE (exp), 0); - - switch (TREE_CODE (exp)) - { - CASE_CONVERT: - t = check_omp_for_incr_expr (loc, TREE_OPERAND (exp, 0), decl); - if (t != error_mark_node) - return fold_convert_loc (loc, TREE_TYPE (exp), t); - break; - case MINUS_EXPR: - t = check_omp_for_incr_expr (loc, TREE_OPERAND (exp, 0), decl); - if (t != error_mark_node) - return fold_build2_loc (loc, MINUS_EXPR, - TREE_TYPE (exp), t, TREE_OPERAND (exp, 1)); - break; - case PLUS_EXPR: - t = check_omp_for_incr_expr (loc, TREE_OPERAND (exp, 0), decl); - if (t != error_mark_node) - return fold_build2_loc (loc, PLUS_EXPR, - TREE_TYPE (exp), t, TREE_OPERAND (exp, 1)); - t = check_omp_for_incr_expr (loc, TREE_OPERAND (exp, 1), decl); - if (t != error_mark_node) - return fold_build2_loc (loc, PLUS_EXPR, - TREE_TYPE (exp), TREE_OPERAND (exp, 0), t); - break; - case COMPOUND_EXPR: - { - /* cp_build_modify_expr forces preevaluation of the RHS to make - sure that it is evaluated before the lvalue-rvalue conversion - is applied to the LHS. Reconstruct the original expression. */ - tree op0 = TREE_OPERAND (exp, 0); - if (TREE_CODE (op0) == TARGET_EXPR - && !VOID_TYPE_P (TREE_TYPE (op0))) - { - tree op1 = TREE_OPERAND (exp, 1); - tree temp = TARGET_EXPR_SLOT (op0); - if (BINARY_CLASS_P (op1) - && TREE_OPERAND (op1, 1) == temp) - { - op1 = copy_node (op1); - TREE_OPERAND (op1, 1) = TARGET_EXPR_INITIAL (op0); - return check_omp_for_incr_expr (loc, op1, decl); - } - } - break; - } - default: - break; - } - - return error_mark_node; -} - -/* If the OMP_FOR increment expression in INCR is of pointer type, - canonicalize it into an expression handled by gimplify_omp_for() - and return it. DECL is the iteration variable. */ - -static tree -c_omp_for_incr_canonicalize_ptr (location_t loc, tree decl, tree incr) -{ - if (POINTER_TYPE_P (TREE_TYPE (decl)) - && TREE_OPERAND (incr, 1)) - { - tree t = fold_convert_loc (loc, - sizetype, TREE_OPERAND (incr, 1)); - - if (TREE_CODE (incr) == POSTDECREMENT_EXPR - || TREE_CODE (incr) == PREDECREMENT_EXPR) - t = fold_build1_loc (loc, NEGATE_EXPR, sizetype, t); - t = fold_build_pointer_plus (decl, t); - incr = build2 (MODIFY_EXPR, void_type_node, decl, t); - } - return incr; -} - -/* Validate and generate OMP_FOR. - DECLV is a vector of iteration variables, for each collapsed loop. - - ORIG_DECLV, if non-NULL, is a vector with the original iteration - variables (prior to any transformations, by say, C++ iterators). - - INITV, CONDV and INCRV are vectors containing initialization - expressions, controlling predicates and increment expressions. - BODY is the body of the loop and PRE_BODY statements that go before - the loop. */ - -tree -c_finish_omp_for (location_t locus, enum tree_code code, tree declv, - tree orig_declv, tree initv, tree condv, tree incrv, - tree body, tree pre_body, bool final_p) -{ - location_t elocus; - bool fail = false; - int i; - - gcc_assert (TREE_VEC_LENGTH (declv) == TREE_VEC_LENGTH (initv)); - gcc_assert (TREE_VEC_LENGTH (declv) == TREE_VEC_LENGTH (condv)); - gcc_assert (TREE_VEC_LENGTH (declv) == TREE_VEC_LENGTH (incrv)); - for (i = 0; i < TREE_VEC_LENGTH (declv); i++) - { - tree decl = TREE_VEC_ELT (declv, i); - tree init = TREE_VEC_ELT (initv, i); - tree cond = TREE_VEC_ELT (condv, i); - tree incr = TREE_VEC_ELT (incrv, i); - - elocus = locus; - if (EXPR_HAS_LOCATION (init)) - elocus = EXPR_LOCATION (init); - - /* Validate the iteration variable. */ - if (!INTEGRAL_TYPE_P (TREE_TYPE (decl)) - && TREE_CODE (TREE_TYPE (decl)) != POINTER_TYPE) - { - error_at (elocus, "invalid type for iteration variable %qE", decl); - fail = true; - } - else if (TYPE_ATOMIC (TREE_TYPE (decl))) - { - error_at (elocus, "%<_Atomic%> iteration variable %qE", decl); - fail = true; - /* _Atomic iterator confuses stuff too much, so we risk ICE - trying to diagnose it further. */ - continue; - } - - /* In the case of "for (int i = 0...)", init will be a decl. It should - have a DECL_INITIAL that we can turn into an assignment. */ - if (init == decl) - { - elocus = DECL_SOURCE_LOCATION (decl); - - init = DECL_INITIAL (decl); - if (init == NULL) - { - error_at (elocus, "%qE is not initialized", decl); - init = integer_zero_node; - fail = true; - } - DECL_INITIAL (decl) = NULL_TREE; - - init = build_modify_expr (elocus, decl, NULL_TREE, NOP_EXPR, - /* FIXME diagnostics: This should - be the location of the INIT. */ - elocus, - init, - NULL_TREE); - } - if (init != error_mark_node) - { - gcc_assert (TREE_CODE (init) == MODIFY_EXPR); - gcc_assert (TREE_OPERAND (init, 0) == decl); - } - - if (cond == NULL_TREE) - { - error_at (elocus, "missing controlling predicate"); - fail = true; - } - else - { - bool cond_ok = false; - - /* E.g. C sizeof (vla) could add COMPOUND_EXPRs with - evaluation of the vla VAR_DECL. We need to readd - them to the non-decl operand. See PR45784. */ - while (TREE_CODE (cond) == COMPOUND_EXPR) - cond = TREE_OPERAND (cond, 1); - - if (EXPR_HAS_LOCATION (cond)) - elocus = EXPR_LOCATION (cond); - - if (TREE_CODE (cond) == LT_EXPR - || TREE_CODE (cond) == LE_EXPR - || TREE_CODE (cond) == GT_EXPR - || TREE_CODE (cond) == GE_EXPR - || TREE_CODE (cond) == NE_EXPR - || TREE_CODE (cond) == EQ_EXPR) - { - tree op0 = TREE_OPERAND (cond, 0); - tree op1 = TREE_OPERAND (cond, 1); - - /* 2.5.1. The comparison in the condition is computed in - the type of DECL, otherwise the behavior is undefined. - - For example: - long n; int i; - i < n; - - according to ISO will be evaluated as: - (long)i < n; - - We want to force: - i < (int)n; */ - if (TREE_CODE (op0) == NOP_EXPR - && decl == TREE_OPERAND (op0, 0)) - { - TREE_OPERAND (cond, 0) = TREE_OPERAND (op0, 0); - TREE_OPERAND (cond, 1) - = fold_build1_loc (elocus, NOP_EXPR, TREE_TYPE (decl), - TREE_OPERAND (cond, 1)); - } - else if (TREE_CODE (op1) == NOP_EXPR - && decl == TREE_OPERAND (op1, 0)) - { - TREE_OPERAND (cond, 1) = TREE_OPERAND (op1, 0); - TREE_OPERAND (cond, 0) - = fold_build1_loc (elocus, NOP_EXPR, TREE_TYPE (decl), - TREE_OPERAND (cond, 0)); - } - - if (decl == TREE_OPERAND (cond, 0)) - cond_ok = true; - else if (decl == TREE_OPERAND (cond, 1)) - { - TREE_SET_CODE (cond, - swap_tree_comparison (TREE_CODE (cond))); - TREE_OPERAND (cond, 1) = TREE_OPERAND (cond, 0); - TREE_OPERAND (cond, 0) = decl; - cond_ok = true; - } - - if (TREE_CODE (cond) == NE_EXPR - || TREE_CODE (cond) == EQ_EXPR) - { - if (!INTEGRAL_TYPE_P (TREE_TYPE (decl))) - { - if (code == OACC_LOOP || TREE_CODE (cond) == EQ_EXPR) - cond_ok = false; - } - else if (operand_equal_p (TREE_OPERAND (cond, 1), - TYPE_MIN_VALUE (TREE_TYPE (decl)), - 0)) - TREE_SET_CODE (cond, TREE_CODE (cond) == NE_EXPR - ? GT_EXPR : LE_EXPR); - else if (operand_equal_p (TREE_OPERAND (cond, 1), - TYPE_MAX_VALUE (TREE_TYPE (decl)), - 0)) - TREE_SET_CODE (cond, TREE_CODE (cond) == NE_EXPR - ? LT_EXPR : GE_EXPR); - else if (code == OACC_LOOP || TREE_CODE (cond) == EQ_EXPR) - cond_ok = false; - } - - if (cond_ok && TREE_VEC_ELT (condv, i) != cond) - { - tree ce = NULL_TREE, *pce = &ce; - tree type = TREE_TYPE (TREE_OPERAND (cond, 1)); - for (tree c = TREE_VEC_ELT (condv, i); c != cond; - c = TREE_OPERAND (c, 1)) - { - *pce = build2 (COMPOUND_EXPR, type, TREE_OPERAND (c, 0), - TREE_OPERAND (cond, 1)); - pce = &TREE_OPERAND (*pce, 1); - } - TREE_OPERAND (cond, 1) = ce; - TREE_VEC_ELT (condv, i) = cond; - } - } - - if (!cond_ok) - { - error_at (elocus, "invalid controlling predicate"); - fail = true; - } - } - - if (incr == NULL_TREE) - { - error_at (elocus, "missing increment expression"); - fail = true; - } - else - { - bool incr_ok = false; - - if (EXPR_HAS_LOCATION (incr)) - elocus = EXPR_LOCATION (incr); - - /* Check all the valid increment expressions: v++, v--, ++v, --v, - v = v + incr, v = incr + v and v = v - incr. */ - switch (TREE_CODE (incr)) - { - case POSTINCREMENT_EXPR: - case PREINCREMENT_EXPR: - case POSTDECREMENT_EXPR: - case PREDECREMENT_EXPR: - if (TREE_OPERAND (incr, 0) != decl) - break; - - incr_ok = true; - if (!fail - && TREE_CODE (cond) == NE_EXPR - && TREE_CODE (TREE_TYPE (decl)) == POINTER_TYPE - && TYPE_SIZE_UNIT (TREE_TYPE (TREE_TYPE (decl))) - && (TREE_CODE (TYPE_SIZE_UNIT (TREE_TYPE (TREE_TYPE (decl)))) - != INTEGER_CST)) - { - /* For pointer to VLA, transform != into < or > - depending on whether incr is increment or decrement. */ - if (TREE_CODE (incr) == PREINCREMENT_EXPR - || TREE_CODE (incr) == POSTINCREMENT_EXPR) - TREE_SET_CODE (cond, LT_EXPR); - else - TREE_SET_CODE (cond, GT_EXPR); - } - incr = c_omp_for_incr_canonicalize_ptr (elocus, decl, incr); - break; - - case COMPOUND_EXPR: - if (TREE_CODE (TREE_OPERAND (incr, 0)) != SAVE_EXPR - || TREE_CODE (TREE_OPERAND (incr, 1)) != MODIFY_EXPR) - break; - incr = TREE_OPERAND (incr, 1); - /* FALLTHRU */ - case MODIFY_EXPR: - if (TREE_OPERAND (incr, 0) != decl) - break; - if (TREE_OPERAND (incr, 1) == decl) - break; - if (TREE_CODE (TREE_OPERAND (incr, 1)) == PLUS_EXPR - && (TREE_OPERAND (TREE_OPERAND (incr, 1), 0) == decl - || TREE_OPERAND (TREE_OPERAND (incr, 1), 1) == decl)) - incr_ok = true; - else if ((TREE_CODE (TREE_OPERAND (incr, 1)) == MINUS_EXPR - || (TREE_CODE (TREE_OPERAND (incr, 1)) - == POINTER_PLUS_EXPR)) - && TREE_OPERAND (TREE_OPERAND (incr, 1), 0) == decl) - incr_ok = true; - else - { - tree t = check_omp_for_incr_expr (elocus, - TREE_OPERAND (incr, 1), - decl); - if (t != error_mark_node) - { - incr_ok = true; - t = build2 (PLUS_EXPR, TREE_TYPE (decl), decl, t); - incr = build2 (MODIFY_EXPR, void_type_node, decl, t); - } - } - if (!fail - && incr_ok - && TREE_CODE (cond) == NE_EXPR) - { - tree i = TREE_OPERAND (incr, 1); - i = TREE_OPERAND (i, TREE_OPERAND (i, 0) == decl); - i = c_fully_fold (i, false, NULL); - if (!final_p - && TREE_CODE (i) != INTEGER_CST) - ; - else if (TREE_CODE (TREE_TYPE (decl)) == POINTER_TYPE) - { - tree unit - = TYPE_SIZE_UNIT (TREE_TYPE (TREE_TYPE (decl))); - if (unit) - { - enum tree_code ccode = GT_EXPR; - unit = c_fully_fold (unit, false, NULL); - i = fold_convert (TREE_TYPE (unit), i); - if (operand_equal_p (unit, i, 0)) - ccode = LT_EXPR; - if (ccode == GT_EXPR) - { - i = fold_unary (NEGATE_EXPR, TREE_TYPE (i), i); - if (i == NULL_TREE - || !operand_equal_p (unit, i, 0)) - { - error_at (elocus, - "increment is not constant 1 or " - "-1 for %<!=%> condition"); - fail = true; - } - } - if (TREE_CODE (unit) != INTEGER_CST) - /* For pointer to VLA, transform != into < or > - depending on whether the pointer is - incremented or decremented in each - iteration. */ - TREE_SET_CODE (cond, ccode); - } - } - else - { - if (!integer_onep (i) && !integer_minus_onep (i)) - { - error_at (elocus, - "increment is not constant 1 or -1 for" - " %<!=%> condition"); - fail = true; - } - } - } - break; - - default: - break; - } - if (!incr_ok) - { - error_at (elocus, "invalid increment expression"); - fail = true; - } - } - - TREE_VEC_ELT (initv, i) = init; - TREE_VEC_ELT (incrv, i) = incr; - } - - if (fail) - return NULL; - else - { - tree t = make_node (code); - - TREE_TYPE (t) = void_type_node; - OMP_FOR_INIT (t) = initv; - OMP_FOR_COND (t) = condv; - OMP_FOR_INCR (t) = incrv; - OMP_FOR_BODY (t) = body; - OMP_FOR_PRE_BODY (t) = pre_body; - OMP_FOR_ORIG_DECLS (t) = orig_declv; - - SET_EXPR_LOCATION (t, locus); - return t; - } -} - -/* Type for passing data in between c_omp_check_loop_iv and - c_omp_check_loop_iv_r. */ - -struct c_omp_check_loop_iv_data -{ - tree declv; - bool fail; - bool maybe_nonrect; - location_t stmt_loc; - location_t expr_loc; - int kind; - int idx; - walk_tree_lh lh; - hash_set<tree> *ppset; -}; - -/* Return -1 if DECL is not a loop iterator in loop nest D, otherwise - return the index of the loop in which it is an iterator. - Return TREE_VEC_LENGTH (d->declv) if it is a C++ range for iterator. */ - -static int -c_omp_is_loop_iterator (tree decl, struct c_omp_check_loop_iv_data *d) -{ - for (int i = 0; i < TREE_VEC_LENGTH (d->declv); i++) - if (decl == TREE_VEC_ELT (d->declv, i) - || (TREE_CODE (TREE_VEC_ELT (d->declv, i)) == TREE_LIST - && decl == TREE_PURPOSE (TREE_VEC_ELT (d->declv, i)))) - return i; - else if (TREE_CODE (TREE_VEC_ELT (d->declv, i)) == TREE_LIST - && TREE_CHAIN (TREE_VEC_ELT (d->declv, i)) - && (TREE_CODE (TREE_CHAIN (TREE_VEC_ELT (d->declv, i))) - == TREE_VEC) - && decl == TREE_VEC_ELT (TREE_CHAIN (TREE_VEC_ELT (d->declv, - i)), 2)) - return TREE_VEC_LENGTH (d->declv); - return -1; -} - -/* Helper function called via walk_tree, to diagnose uses - of associated loop IVs inside of lb, b and incr expressions - of OpenMP loops. */ - -static tree -c_omp_check_loop_iv_r (tree *tp, int *walk_subtrees, void *data) -{ - struct c_omp_check_loop_iv_data *d - = (struct c_omp_check_loop_iv_data *) data; - if (DECL_P (*tp)) - { - int idx = c_omp_is_loop_iterator (*tp, d); - if (idx == -1) - return NULL_TREE; - - if ((d->kind & 4) && idx < d->idx) - { - d->maybe_nonrect = true; - return NULL_TREE; - } - - if (d->ppset->add (*tp)) - return NULL_TREE; - - location_t loc = d->expr_loc; - if (loc == UNKNOWN_LOCATION) - loc = d->stmt_loc; - - switch (d->kind & 3) - { - case 0: - error_at (loc, "initializer expression refers to " - "iteration variable %qD", *tp); - break; - case 1: - error_at (loc, "condition expression refers to " - "iteration variable %qD", *tp); - break; - case 2: - error_at (loc, "increment expression refers to " - "iteration variable %qD", *tp); - break; - } - d->fail = true; - } - else if ((d->kind & 4) - && TREE_CODE (*tp) != TREE_VEC - && TREE_CODE (*tp) != PLUS_EXPR - && TREE_CODE (*tp) != MINUS_EXPR - && TREE_CODE (*tp) != MULT_EXPR - && TREE_CODE (*tp) != POINTER_PLUS_EXPR - && !CONVERT_EXPR_P (*tp)) - { - *walk_subtrees = 0; - d->kind &= 3; - walk_tree_1 (tp, c_omp_check_loop_iv_r, data, NULL, d->lh); - d->kind |= 4; - return NULL_TREE; - } - else if (d->ppset->add (*tp)) - *walk_subtrees = 0; - /* Don't walk dtors added by C++ wrap_cleanups_r. */ - else if (TREE_CODE (*tp) == TRY_CATCH_EXPR - && TRY_CATCH_IS_CLEANUP (*tp)) - { - *walk_subtrees = 0; - return walk_tree_1 (&TREE_OPERAND (*tp, 0), c_omp_check_loop_iv_r, data, - NULL, d->lh); - } - - return NULL_TREE; -} - -/* Check the allowed expressions for non-rectangular loop nest lb and b - expressions. Return the outer var decl referenced in the expression. */ - -static tree -c_omp_check_nonrect_loop_iv (tree *tp, struct c_omp_check_loop_iv_data *d, - walk_tree_lh lh) -{ - d->maybe_nonrect = false; - if (d->fail) - return NULL_TREE; - - hash_set<tree> pset; - hash_set<tree> *ppset = d->ppset; - d->ppset = &pset; - - tree t = *tp; - if (TREE_CODE (t) == TREE_VEC - && TREE_VEC_LENGTH (t) == 3 - && DECL_P (TREE_VEC_ELT (t, 0)) - && c_omp_is_loop_iterator (TREE_VEC_ELT (t, 0), d) >= 0) - { - d->kind &= 3; - walk_tree_1 (&TREE_VEC_ELT (t, 1), c_omp_check_loop_iv_r, d, NULL, lh); - walk_tree_1 (&TREE_VEC_ELT (t, 1), c_omp_check_loop_iv_r, d, NULL, lh); - d->ppset = ppset; - return d->fail ? NULL_TREE : TREE_VEC_ELT (t, 0); - } - - while (CONVERT_EXPR_P (t)) - t = TREE_OPERAND (t, 0); - - tree a1 = t, a2 = integer_zero_node; - bool neg_a1 = false, neg_a2 = false; - switch (TREE_CODE (t)) - { - case PLUS_EXPR: - case MINUS_EXPR: - a1 = TREE_OPERAND (t, 0); - a2 = TREE_OPERAND (t, 1); - while (CONVERT_EXPR_P (a1)) - a1 = TREE_OPERAND (a1, 0); - while (CONVERT_EXPR_P (a2)) - a2 = TREE_OPERAND (a2, 0); - if (DECL_P (a1) && c_omp_is_loop_iterator (a1, d) >= 0) - { - a2 = TREE_OPERAND (t, 1); - if (TREE_CODE (t) == MINUS_EXPR) - neg_a2 = true; - t = a1; - break; - } - if (DECL_P (a2) && c_omp_is_loop_iterator (a2, d) >= 0) - { - a1 = TREE_OPERAND (t, 0); - if (TREE_CODE (t) == MINUS_EXPR) - neg_a1 = true; - t = a2; - a2 = a1; - break; - } - if (TREE_CODE (a1) == MULT_EXPR && TREE_CODE (a2) == MULT_EXPR) - { - tree o1 = TREE_OPERAND (a1, 0); - tree o2 = TREE_OPERAND (a1, 1); - while (CONVERT_EXPR_P (o1)) - o1 = TREE_OPERAND (o1, 0); - while (CONVERT_EXPR_P (o2)) - o2 = TREE_OPERAND (o2, 0); - if ((DECL_P (o1) && c_omp_is_loop_iterator (o1, d) >= 0) - || (DECL_P (o2) && c_omp_is_loop_iterator (o2, d) >= 0)) - { - a2 = TREE_OPERAND (t, 1); - if (TREE_CODE (t) == MINUS_EXPR) - neg_a2 = true; - t = a1; - break; - } - } - if (TREE_CODE (a2) == MULT_EXPR) - { - a1 = TREE_OPERAND (t, 0); - if (TREE_CODE (t) == MINUS_EXPR) - neg_a1 = true; - t = a2; - a2 = a1; - break; - } - if (TREE_CODE (a1) == MULT_EXPR) - { - a2 = TREE_OPERAND (t, 1); - if (TREE_CODE (t) == MINUS_EXPR) - neg_a2 = true; - t = a1; - break; - } - a2 = integer_zero_node; - break; - case POINTER_PLUS_EXPR: - a1 = TREE_OPERAND (t, 0); - a2 = TREE_OPERAND (t, 1); - while (CONVERT_EXPR_P (a1)) - a1 = TREE_OPERAND (a1, 0); - if (DECL_P (a1) && c_omp_is_loop_iterator (a1, d) >= 0) - { - a2 = TREE_OPERAND (t, 1); - t = a1; - break; - } - break; - default: - break; - } - - a1 = integer_one_node; - if (TREE_CODE (t) == MULT_EXPR) - { - tree o1 = TREE_OPERAND (t, 0); - tree o2 = TREE_OPERAND (t, 1); - while (CONVERT_EXPR_P (o1)) - o1 = TREE_OPERAND (o1, 0); - while (CONVERT_EXPR_P (o2)) - o2 = TREE_OPERAND (o2, 0); - if (DECL_P (o1) && c_omp_is_loop_iterator (o1, d) >= 0) - { - a1 = TREE_OPERAND (t, 1); - t = o1; - } - else if (DECL_P (o2) && c_omp_is_loop_iterator (o2, d) >= 0) - { - a1 = TREE_OPERAND (t, 0); - t = o2; - } - } - - d->kind &= 3; - tree ret = NULL_TREE; - if (DECL_P (t) && c_omp_is_loop_iterator (t, d) >= 0) - { - location_t loc = d->expr_loc; - if (loc == UNKNOWN_LOCATION) - loc = d->stmt_loc; - if (!lang_hooks.types_compatible_p (TREE_TYPE (*tp), TREE_TYPE (t))) - { - if (d->kind == 0) - error_at (loc, "outer iteration variable %qD used in initializer" - " expression has type other than %qT", - t, TREE_TYPE (*tp)); - else - error_at (loc, "outer iteration variable %qD used in condition" - " expression has type other than %qT", - t, TREE_TYPE (*tp)); - d->fail = true; - } - else if (!INTEGRAL_TYPE_P (TREE_TYPE (a1))) - { - error_at (loc, "outer iteration variable %qD multiplier expression" - " %qE is not integral", t, a1); - d->fail = true; - } - else if (!INTEGRAL_TYPE_P (TREE_TYPE (a2))) - { - error_at (loc, "outer iteration variable %qD addend expression" - " %qE is not integral", t, a2); - d->fail = true; - } - else - { - walk_tree_1 (&a1, c_omp_check_loop_iv_r, d, NULL, lh); - walk_tree_1 (&a2, c_omp_check_loop_iv_r, d, NULL, lh); - } - if (!d->fail) - { - a1 = fold_convert (TREE_TYPE (*tp), a1); - a2 = fold_convert (TREE_TYPE (*tp), a2); - if (neg_a1) - a1 = fold_build1 (NEGATE_EXPR, TREE_TYPE (a1), a1); - if (neg_a2) - a2 = fold_build1 (NEGATE_EXPR, TREE_TYPE (a2), a2); - ret = t; - *tp = make_tree_vec (3); - TREE_VEC_ELT (*tp, 0) = t; - TREE_VEC_ELT (*tp, 1) = a1; - TREE_VEC_ELT (*tp, 2) = a2; - } - } - else - walk_tree_1 (&t, c_omp_check_loop_iv_r, d, NULL, lh); - - d->ppset = ppset; - return ret; -} - -/* Diagnose invalid references to loop iterators in lb, b and incr - expressions. */ - -bool -c_omp_check_loop_iv (tree stmt, tree declv, walk_tree_lh lh) -{ - hash_set<tree> pset; - struct c_omp_check_loop_iv_data data; - int i; - - data.declv = declv; - data.fail = false; - data.maybe_nonrect = false; - data.stmt_loc = EXPR_LOCATION (stmt); - data.lh = lh; - data.ppset = &pset; - for (i = 0; i < TREE_VEC_LENGTH (OMP_FOR_INIT (stmt)); i++) - { - tree init = TREE_VEC_ELT (OMP_FOR_INIT (stmt), i); - gcc_assert (TREE_CODE (init) == MODIFY_EXPR); - tree decl = TREE_OPERAND (init, 0); - tree cond = TREE_VEC_ELT (OMP_FOR_COND (stmt), i); - gcc_assert (COMPARISON_CLASS_P (cond)); - gcc_assert (TREE_OPERAND (cond, 0) == decl); - tree incr = TREE_VEC_ELT (OMP_FOR_INCR (stmt), i); - data.expr_loc = EXPR_LOCATION (TREE_OPERAND (init, 1)); - tree vec_outer1 = NULL_TREE, vec_outer2 = NULL_TREE; - int kind = 0; - if (i > 0 - && (unsigned) c_omp_is_loop_iterator (decl, &data) < (unsigned) i) - { - location_t loc = data.expr_loc; - if (loc == UNKNOWN_LOCATION) - loc = data.stmt_loc; - error_at (loc, "the same loop iteration variables %qD used in " - "multiple associated loops", decl); - data.fail = true; - } - /* Handle non-rectangular loop nests. */ - if (TREE_CODE (stmt) != OACC_LOOP && i > 0) - kind = 4; - data.kind = kind; - data.idx = i; - walk_tree_1 (&TREE_OPERAND (init, 1), - c_omp_check_loop_iv_r, &data, NULL, lh); - if (data.maybe_nonrect) - vec_outer1 = c_omp_check_nonrect_loop_iv (&TREE_OPERAND (init, 1), - &data, lh); - /* Don't warn for C++ random access iterators here, the - expression then involves the subtraction and always refers - to the original value. The C++ FE needs to warn on those - earlier. */ - if (decl == TREE_VEC_ELT (declv, i) - || (TREE_CODE (TREE_VEC_ELT (declv, i)) == TREE_LIST - && decl == TREE_PURPOSE (TREE_VEC_ELT (declv, i)))) - { - data.expr_loc = EXPR_LOCATION (cond); - data.kind = kind | 1; - walk_tree_1 (&TREE_OPERAND (cond, 1), - c_omp_check_loop_iv_r, &data, NULL, lh); - if (data.maybe_nonrect) - vec_outer2 = c_omp_check_nonrect_loop_iv (&TREE_OPERAND (cond, 1), - &data, lh); - } - if (vec_outer1 && vec_outer2 && vec_outer1 != vec_outer2) - { - location_t loc = data.expr_loc; - if (loc == UNKNOWN_LOCATION) - loc = data.stmt_loc; - error_at (loc, "two different outer iteration variables %qD and %qD" - " used in a single loop", vec_outer1, vec_outer2); - data.fail = true; - } - if (vec_outer1 || vec_outer2) - OMP_FOR_NON_RECTANGULAR (stmt) = 1; - if (TREE_CODE (incr) == MODIFY_EXPR) - { - gcc_assert (TREE_OPERAND (incr, 0) == decl); - incr = TREE_OPERAND (incr, 1); - data.kind = 2; - if (TREE_CODE (incr) == PLUS_EXPR - && TREE_OPERAND (incr, 1) == decl) - { - data.expr_loc = EXPR_LOCATION (TREE_OPERAND (incr, 0)); - walk_tree_1 (&TREE_OPERAND (incr, 0), - c_omp_check_loop_iv_r, &data, NULL, lh); - } - else - { - data.expr_loc = EXPR_LOCATION (TREE_OPERAND (incr, 1)); - walk_tree_1 (&TREE_OPERAND (incr, 1), - c_omp_check_loop_iv_r, &data, NULL, lh); - } - } - } - return !data.fail; -} - -/* Similar, but allows to check the init or cond expressions individually. */ - -bool -c_omp_check_loop_iv_exprs (location_t stmt_loc, enum tree_code code, - tree declv, int i, tree decl, tree init, tree cond, - walk_tree_lh lh) -{ - hash_set<tree> pset; - struct c_omp_check_loop_iv_data data; - int kind = (code != OACC_LOOP && i > 0) ? 4 : 0; - - data.declv = declv; - data.fail = false; - data.maybe_nonrect = false; - data.stmt_loc = stmt_loc; - data.lh = lh; - data.ppset = &pset; - data.idx = i; - if (i > 0 - && (unsigned) c_omp_is_loop_iterator (decl, &data) < (unsigned) i) - { - error_at (stmt_loc, "the same loop iteration variables %qD used in " - "multiple associated loops", decl); - data.fail = true; - } - if (init) - { - data.expr_loc = EXPR_LOCATION (init); - data.kind = kind; - walk_tree_1 (&init, - c_omp_check_loop_iv_r, &data, NULL, lh); - } - if (cond) - { - gcc_assert (COMPARISON_CLASS_P (cond)); - data.expr_loc = EXPR_LOCATION (init); - data.kind = kind | 1; - if (TREE_OPERAND (cond, 0) == decl) - walk_tree_1 (&TREE_OPERAND (cond, 1), - c_omp_check_loop_iv_r, &data, NULL, lh); - else - walk_tree_1 (&TREE_OPERAND (cond, 0), - c_omp_check_loop_iv_r, &data, NULL, lh); - } - return !data.fail; -} - -/* This function splits clauses for OpenACC combined loop - constructs. OpenACC combined loop constructs are: - #pragma acc kernels loop - #pragma acc parallel loop */ - -tree -c_oacc_split_loop_clauses (tree clauses, tree *not_loop_clauses, - bool is_parallel) -{ - tree next, loop_clauses, nc; - - loop_clauses = *not_loop_clauses = NULL_TREE; - for (; clauses ; clauses = next) - { - next = OMP_CLAUSE_CHAIN (clauses); - - switch (OMP_CLAUSE_CODE (clauses)) - { - /* Loop clauses. */ - case OMP_CLAUSE_COLLAPSE: - case OMP_CLAUSE_TILE: - case OMP_CLAUSE_GANG: - case OMP_CLAUSE_WORKER: - case OMP_CLAUSE_VECTOR: - case OMP_CLAUSE_AUTO: - case OMP_CLAUSE_SEQ: - case OMP_CLAUSE_INDEPENDENT: - case OMP_CLAUSE_PRIVATE: - OMP_CLAUSE_CHAIN (clauses) = loop_clauses; - loop_clauses = clauses; - break; - - /* Reductions must be duplicated on both constructs. */ - case OMP_CLAUSE_REDUCTION: - if (is_parallel) - { - nc = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_REDUCTION); - OMP_CLAUSE_DECL (nc) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_REDUCTION_CODE (nc) - = OMP_CLAUSE_REDUCTION_CODE (clauses); - OMP_CLAUSE_CHAIN (nc) = *not_loop_clauses; - *not_loop_clauses = nc; - } - - OMP_CLAUSE_CHAIN (clauses) = loop_clauses; - loop_clauses = clauses; - break; - - /* Parallel/kernels clauses. */ - default: - OMP_CLAUSE_CHAIN (clauses) = *not_loop_clauses; - *not_loop_clauses = clauses; - break; - } - } - - return loop_clauses; -} - -/* This function attempts to split or duplicate clauses for OpenMP - combined/composite constructs. Right now there are 30 different - constructs. CODE is the innermost construct in the combined construct, - and MASK allows to determine which constructs are combined together, - as every construct has at least one clause that no other construct - has (except for OMP_SECTIONS, but that can be only combined with parallel, - and OMP_MASTER, which doesn't have any clauses at all). - OpenMP combined/composite constructs are: - #pragma omp distribute parallel for - #pragma omp distribute parallel for simd - #pragma omp distribute simd - #pragma omp for simd - #pragma omp masked taskloop - #pragma omp masked taskloop simd - #pragma omp master taskloop - #pragma omp master taskloop simd - #pragma omp parallel for - #pragma omp parallel for simd - #pragma omp parallel loop - #pragma omp parallel masked - #pragma omp parallel masked taskloop - #pragma omp parallel masked taskloop simd - #pragma omp parallel master - #pragma omp parallel master taskloop - #pragma omp parallel master taskloop simd - #pragma omp parallel sections - #pragma omp target parallel - #pragma omp target parallel for - #pragma omp target parallel for simd - #pragma omp target parallel loop - #pragma omp target teams - #pragma omp target teams distribute - #pragma omp target teams distribute parallel for - #pragma omp target teams distribute parallel for simd - #pragma omp target teams distribute simd - #pragma omp target teams loop - #pragma omp target simd - #pragma omp taskloop simd - #pragma omp teams distribute - #pragma omp teams distribute parallel for - #pragma omp teams distribute parallel for simd - #pragma omp teams distribute simd - #pragma omp teams loop */ - -void -c_omp_split_clauses (location_t loc, enum tree_code code, - omp_clause_mask mask, tree clauses, tree *cclauses) -{ - tree next, c; - enum c_omp_clause_split s; - int i; - bool has_dup_allocate = false; - - for (i = 0; i < C_OMP_CLAUSE_SPLIT_COUNT; i++) - cclauses[i] = NULL; - /* Add implicit nowait clause on - #pragma omp parallel {for,for simd,sections}. */ - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_THREADS)) != 0) - switch (code) - { - case OMP_FOR: - case OMP_SIMD: - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_SCHEDULE)) != 0) - cclauses[C_OMP_CLAUSE_SPLIT_FOR] - = build_omp_clause (loc, OMP_CLAUSE_NOWAIT); - break; - case OMP_SECTIONS: - cclauses[C_OMP_CLAUSE_SPLIT_SECTIONS] - = build_omp_clause (loc, OMP_CLAUSE_NOWAIT); - break; - default: - break; - } - - for (; clauses ; clauses = next) - { - next = OMP_CLAUSE_CHAIN (clauses); - - switch (OMP_CLAUSE_CODE (clauses)) - { - /* First the clauses that are unique to some constructs. */ - case OMP_CLAUSE_DEVICE: - case OMP_CLAUSE_MAP: - case OMP_CLAUSE_IS_DEVICE_PTR: - case OMP_CLAUSE_DEFAULTMAP: - case OMP_CLAUSE_DEPEND: - s = C_OMP_CLAUSE_SPLIT_TARGET; - break; - case OMP_CLAUSE_NUM_TEAMS: - s = C_OMP_CLAUSE_SPLIT_TEAMS; - break; - case OMP_CLAUSE_DIST_SCHEDULE: - s = C_OMP_CLAUSE_SPLIT_DISTRIBUTE; - break; - case OMP_CLAUSE_COPYIN: - case OMP_CLAUSE_NUM_THREADS: - case OMP_CLAUSE_PROC_BIND: - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - break; - case OMP_CLAUSE_ORDERED: - s = C_OMP_CLAUSE_SPLIT_FOR; - break; - case OMP_CLAUSE_SCHEDULE: - s = C_OMP_CLAUSE_SPLIT_FOR; - if (code != OMP_SIMD) - OMP_CLAUSE_SCHEDULE_SIMD (clauses) = 0; - break; - case OMP_CLAUSE_SAFELEN: - case OMP_CLAUSE_SIMDLEN: - case OMP_CLAUSE_ALIGNED: - case OMP_CLAUSE_NONTEMPORAL: - s = C_OMP_CLAUSE_SPLIT_SIMD; - break; - case OMP_CLAUSE_GRAINSIZE: - case OMP_CLAUSE_NUM_TASKS: - case OMP_CLAUSE_FINAL: - case OMP_CLAUSE_UNTIED: - case OMP_CLAUSE_MERGEABLE: - case OMP_CLAUSE_NOGROUP: - case OMP_CLAUSE_PRIORITY: - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - break; - case OMP_CLAUSE_BIND: - s = C_OMP_CLAUSE_SPLIT_LOOP; - break; - case OMP_CLAUSE_FILTER: - s = C_OMP_CLAUSE_SPLIT_MASKED; - break; - /* Duplicate this to all of taskloop, distribute, for, simd and - loop. */ - case OMP_CLAUSE_COLLAPSE: - if (code == OMP_SIMD) - { - if ((mask & ((OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_SCHEDULE) - | (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE) - | (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NOGROUP))) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_COLLAPSE); - OMP_CLAUSE_COLLAPSE_EXPR (c) - = OMP_CLAUSE_COLLAPSE_EXPR (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_SIMD]; - cclauses[C_OMP_CLAUSE_SPLIT_SIMD] = c; - } - else - { - /* This must be #pragma omp target simd */ - s = C_OMP_CLAUSE_SPLIT_SIMD; - break; - } - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_SCHEDULE)) != 0) - { - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE)) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_COLLAPSE); - OMP_CLAUSE_COLLAPSE_EXPR (c) - = OMP_CLAUSE_COLLAPSE_EXPR (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_FOR]; - cclauses[C_OMP_CLAUSE_SPLIT_FOR] = c; - s = C_OMP_CLAUSE_SPLIT_DISTRIBUTE; - } - else - s = C_OMP_CLAUSE_SPLIT_FOR; - } - else if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NOGROUP)) - != 0) - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - else if (code == OMP_LOOP) - s = C_OMP_CLAUSE_SPLIT_LOOP; - else - s = C_OMP_CLAUSE_SPLIT_DISTRIBUTE; - break; - /* Private clause is supported on all constructs but master/masked, - it is enough to put it on the innermost one other than - master/masked. For #pragma omp {for,sections} put it on parallel - though, as that's what we did for OpenMP 3.1. */ - case OMP_CLAUSE_PRIVATE: - switch (code) - { - case OMP_SIMD: s = C_OMP_CLAUSE_SPLIT_SIMD; break; - case OMP_FOR: case OMP_SECTIONS: - case OMP_PARALLEL: s = C_OMP_CLAUSE_SPLIT_PARALLEL; break; - case OMP_DISTRIBUTE: s = C_OMP_CLAUSE_SPLIT_DISTRIBUTE; break; - case OMP_TEAMS: s = C_OMP_CLAUSE_SPLIT_TEAMS; break; - case OMP_MASTER: s = C_OMP_CLAUSE_SPLIT_PARALLEL; break; - case OMP_MASKED: s = C_OMP_CLAUSE_SPLIT_PARALLEL; break; - case OMP_TASKLOOP: s = C_OMP_CLAUSE_SPLIT_TASKLOOP; break; - case OMP_LOOP: s = C_OMP_CLAUSE_SPLIT_LOOP; break; - default: gcc_unreachable (); - } - break; - /* Firstprivate clause is supported on all constructs but - simd, master, masked and loop. Put it on the outermost of those - and duplicate on teams and parallel. */ - case OMP_CLAUSE_FIRSTPRIVATE: - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP)) - != 0) - { - if (code == OMP_SIMD - && (mask & ((OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS) - | (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_TEAMS))) == 0) - { - /* This must be #pragma omp target simd. */ - s = C_OMP_CLAUSE_SPLIT_TARGET; - OMP_CLAUSE_FIRSTPRIVATE_IMPLICIT (clauses) = 1; - OMP_CLAUSE_FIRSTPRIVATE_IMPLICIT_TARGET (clauses) = 1; - break; - } - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_FIRSTPRIVATE); - /* firstprivate should not be applied to target if it is - also lastprivate or on the combined/composite construct, - or if it is mentioned in map clause. OMP_CLAUSE_DECLs - may need to go through FE handling though (instantiation, - C++ non-static data members, array section lowering), so - add the clause with OMP_CLAUSE_FIRSTPRIVATE_IMPLICIT and - let *finish_omp_clauses and the gimplifier handle it - right. */ - OMP_CLAUSE_FIRSTPRIVATE_IMPLICIT (c) = 1; - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TARGET]; - cclauses[C_OMP_CLAUSE_SPLIT_TARGET] = c; - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_THREADS)) - != 0) - { - if ((mask & ((OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_TEAMS) - | (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE))) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_FIRSTPRIVATE); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_PARALLEL]; - cclauses[C_OMP_CLAUSE_SPLIT_PARALLEL] = c; - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_TEAMS)) != 0) - s = C_OMP_CLAUSE_SPLIT_TEAMS; - else - s = C_OMP_CLAUSE_SPLIT_DISTRIBUTE; - } - else if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NOGROUP)) != 0) - /* This must be - #pragma omp parallel mas{ked,ter} taskloop{, simd}. */ - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - else - /* This must be - #pragma omp parallel{, for{, simd}, sections,loop} - or - #pragma omp target parallel. */ - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - } - else if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_TEAMS)) - != 0) - { - /* This must be one of - #pragma omp {,target }teams {distribute,loop} - #pragma omp target teams - #pragma omp {,target }teams distribute simd. */ - gcc_assert (code == OMP_DISTRIBUTE - || code == OMP_LOOP - || code == OMP_TEAMS - || code == OMP_SIMD); - s = C_OMP_CLAUSE_SPLIT_TEAMS; - } - else if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE)) != 0) - { - /* This must be #pragma omp distribute simd. */ - gcc_assert (code == OMP_SIMD); - s = C_OMP_CLAUSE_SPLIT_DISTRIBUTE; - } - else if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NOGROUP)) != 0) - { - /* This must be - #pragma omp {,{,parallel }mas{ked,ter} }taskloop simd - or - #pragma omp {,parallel }mas{ked,ter} taskloop. */ - gcc_assert (code == OMP_SIMD || code == OMP_TASKLOOP); - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - } - else - { - /* This must be #pragma omp for simd. */ - gcc_assert (code == OMP_SIMD); - s = C_OMP_CLAUSE_SPLIT_FOR; - } - break; - /* Lastprivate is allowed on distribute, for, sections, taskloop, loop - and simd. In parallel {for{, simd},sections} we actually want to - put it on parallel rather than for or sections. */ - case OMP_CLAUSE_LASTPRIVATE: - if (code == OMP_DISTRIBUTE) - { - s = C_OMP_CLAUSE_SPLIT_DISTRIBUTE; - break; - } - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE)) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_LASTPRIVATE); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_DISTRIBUTE]; - OMP_CLAUSE_LASTPRIVATE_CONDITIONAL (c) - = OMP_CLAUSE_LASTPRIVATE_CONDITIONAL (clauses); - cclauses[C_OMP_CLAUSE_SPLIT_DISTRIBUTE] = c; - } - if (code == OMP_FOR || code == OMP_SECTIONS) - { - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_THREADS)) - != 0) - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - else - s = C_OMP_CLAUSE_SPLIT_FOR; - break; - } - if (code == OMP_TASKLOOP) - { - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - break; - } - if (code == OMP_LOOP) - { - s = C_OMP_CLAUSE_SPLIT_LOOP; - break; - } - gcc_assert (code == OMP_SIMD); - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_SCHEDULE)) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_LASTPRIVATE); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_LASTPRIVATE_CONDITIONAL (c) - = OMP_CLAUSE_LASTPRIVATE_CONDITIONAL (clauses); - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_THREADS)) - != 0) - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - else - s = C_OMP_CLAUSE_SPLIT_FOR; - OMP_CLAUSE_CHAIN (c) = cclauses[s]; - cclauses[s] = c; - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NOGROUP)) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_LASTPRIVATE); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_LASTPRIVATE_CONDITIONAL (c) - = OMP_CLAUSE_LASTPRIVATE_CONDITIONAL (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TASKLOOP]; - cclauses[C_OMP_CLAUSE_SPLIT_TASKLOOP] = c; - } - s = C_OMP_CLAUSE_SPLIT_SIMD; - break; - /* Shared and default clauses are allowed on parallel, teams and - taskloop. */ - case OMP_CLAUSE_SHARED: - case OMP_CLAUSE_DEFAULT: - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NOGROUP)) - != 0) - { - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_THREADS)) - != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_CODE (clauses)); - if (OMP_CLAUSE_CODE (clauses) == OMP_CLAUSE_SHARED) - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - else - OMP_CLAUSE_DEFAULT_KIND (c) - = OMP_CLAUSE_DEFAULT_KIND (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_PARALLEL]; - cclauses[C_OMP_CLAUSE_SPLIT_PARALLEL] = c; - } - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - break; - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_TEAMS)) - != 0) - { - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_THREADS)) - == 0) - { - s = C_OMP_CLAUSE_SPLIT_TEAMS; - break; - } - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_CODE (clauses)); - if (OMP_CLAUSE_CODE (clauses) == OMP_CLAUSE_SHARED) - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - else - OMP_CLAUSE_DEFAULT_KIND (c) - = OMP_CLAUSE_DEFAULT_KIND (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TEAMS]; - cclauses[C_OMP_CLAUSE_SPLIT_TEAMS] = c; - } - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - break; - /* order clauses are allowed on distribute, for, simd and loop. */ - case OMP_CLAUSE_ORDER: - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE)) != 0) - { - if (code == OMP_DISTRIBUTE) - { - s = C_OMP_CLAUSE_SPLIT_DISTRIBUTE; - break; - } - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_ORDER); - OMP_CLAUSE_ORDER_UNCONSTRAINED (c) - = OMP_CLAUSE_ORDER_UNCONSTRAINED (clauses); - OMP_CLAUSE_ORDER_REPRODUCIBLE (c) - = OMP_CLAUSE_ORDER_REPRODUCIBLE (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_DISTRIBUTE]; - cclauses[C_OMP_CLAUSE_SPLIT_DISTRIBUTE] = c; - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_SCHEDULE)) != 0) - { - if (code == OMP_SIMD) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_ORDER); - OMP_CLAUSE_ORDER_UNCONSTRAINED (c) - = OMP_CLAUSE_ORDER_UNCONSTRAINED (clauses); - OMP_CLAUSE_ORDER_REPRODUCIBLE (c) - = OMP_CLAUSE_ORDER_REPRODUCIBLE (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_FOR]; - cclauses[C_OMP_CLAUSE_SPLIT_FOR] = c; - s = C_OMP_CLAUSE_SPLIT_SIMD; - } - else - s = C_OMP_CLAUSE_SPLIT_FOR; - } - else if (code == OMP_LOOP) - s = C_OMP_CLAUSE_SPLIT_LOOP; - else - s = C_OMP_CLAUSE_SPLIT_SIMD; - break; - /* Reduction is allowed on simd, for, parallel, sections, taskloop, - teams and loop. Duplicate it on all of them, but omit on for or - sections if parallel is present (unless inscan, in that case - omit on parallel). If taskloop or loop is combined with - parallel, omit it on parallel. */ - case OMP_CLAUSE_REDUCTION: - if (OMP_CLAUSE_REDUCTION_TASK (clauses)) - { - if (code == OMP_SIMD || code == OMP_LOOP) - { - error_at (OMP_CLAUSE_LOCATION (clauses), - "invalid %<task%> reduction modifier on construct " - "combined with %<simd%> or %<loop%>"); - OMP_CLAUSE_REDUCTION_TASK (clauses) = 0; - } - else if (code != OMP_SECTIONS - && (mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS)) == 0 - && (mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_SCHEDULE)) == 0) - { - error_at (OMP_CLAUSE_LOCATION (clauses), - "invalid %<task%> reduction modifier on construct " - "not combined with %<parallel%>, %<for%> or " - "%<sections%>"); - OMP_CLAUSE_REDUCTION_TASK (clauses) = 0; - } - } - if (OMP_CLAUSE_REDUCTION_INSCAN (clauses) - && ((mask & ((OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE) - | (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP))) - != 0)) - { - error_at (OMP_CLAUSE_LOCATION (clauses), - "%<inscan%> %<reduction%> clause on construct other " - "than %<for%>, %<simd%>, %<for simd%>, " - "%<parallel for%>, %<parallel for simd%>"); - OMP_CLAUSE_REDUCTION_INSCAN (clauses) = 0; - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP)) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_MAP); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_SET_MAP_KIND (c, GOMP_MAP_TOFROM); - OMP_CLAUSE_MAP_IMPLICIT (c) = 1; - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TARGET]; - cclauses[C_OMP_CLAUSE_SPLIT_TARGET] = c; - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_SCHEDULE)) != 0) - { - if (code == OMP_SIMD) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_REDUCTION); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_REDUCTION_CODE (c) - = OMP_CLAUSE_REDUCTION_CODE (clauses); - OMP_CLAUSE_REDUCTION_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_INSCAN (c) - = OMP_CLAUSE_REDUCTION_INSCAN (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_SIMD]; - cclauses[C_OMP_CLAUSE_SPLIT_SIMD] = c; - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_TEAMS)) - != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_REDUCTION); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_REDUCTION_CODE (c) - = OMP_CLAUSE_REDUCTION_CODE (clauses); - OMP_CLAUSE_REDUCTION_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_INSCAN (c) - = OMP_CLAUSE_REDUCTION_INSCAN (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TEAMS]; - cclauses[C_OMP_CLAUSE_SPLIT_TEAMS] = c; - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - } - else if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS)) != 0 - && !OMP_CLAUSE_REDUCTION_INSCAN (clauses)) - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - else - s = C_OMP_CLAUSE_SPLIT_FOR; - } - else if (code == OMP_SECTIONS - || code == OMP_PARALLEL - || code == OMP_MASTER - || code == OMP_MASKED) - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - else if (code == OMP_TASKLOOP) - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - else if (code == OMP_LOOP) - s = C_OMP_CLAUSE_SPLIT_LOOP; - else if (code == OMP_SIMD) - { - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NOGROUP)) - != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_REDUCTION); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_REDUCTION_CODE (c) - = OMP_CLAUSE_REDUCTION_CODE (clauses); - OMP_CLAUSE_REDUCTION_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_INSCAN (c) - = OMP_CLAUSE_REDUCTION_INSCAN (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TASKLOOP]; - cclauses[C_OMP_CLAUSE_SPLIT_TASKLOOP] = c; - } - else if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_TEAMS)) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_REDUCTION); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_REDUCTION_CODE (c) - = OMP_CLAUSE_REDUCTION_CODE (clauses); - OMP_CLAUSE_REDUCTION_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_INSCAN (c) - = OMP_CLAUSE_REDUCTION_INSCAN (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TEAMS]; - cclauses[C_OMP_CLAUSE_SPLIT_TEAMS] = c; - } - s = C_OMP_CLAUSE_SPLIT_SIMD; - } - else - s = C_OMP_CLAUSE_SPLIT_TEAMS; - break; - case OMP_CLAUSE_IN_REDUCTION: - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP)) != 0) - { - /* When on target, map(always, tofrom: item) is added as - well. For non-combined target it is added in the FEs. */ - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_MAP); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_SET_MAP_KIND (c, GOMP_MAP_ALWAYS_TOFROM); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TARGET]; - cclauses[C_OMP_CLAUSE_SPLIT_TARGET] = c; - s = C_OMP_CLAUSE_SPLIT_TARGET; - break; - } - /* in_reduction on taskloop simd becomes reduction on the simd - and keeps being in_reduction on taskloop. */ - if (code == OMP_SIMD) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_REDUCTION); - OMP_CLAUSE_DECL (c) = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_REDUCTION_CODE (c) - = OMP_CLAUSE_REDUCTION_CODE (clauses); - OMP_CLAUSE_REDUCTION_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_PLACEHOLDER (clauses); - OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (c) - = OMP_CLAUSE_REDUCTION_DECL_PLACEHOLDER (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_SIMD]; - cclauses[C_OMP_CLAUSE_SPLIT_SIMD] = c; - } - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - break; - case OMP_CLAUSE_IF: - if (OMP_CLAUSE_IF_MODIFIER (clauses) != ERROR_MARK) - { - s = C_OMP_CLAUSE_SPLIT_COUNT; - switch (OMP_CLAUSE_IF_MODIFIER (clauses)) - { - case OMP_PARALLEL: - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS)) != 0) - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - break; - case OMP_SIMD: - if (code == OMP_SIMD) - s = C_OMP_CLAUSE_SPLIT_SIMD; - break; - case OMP_TASKLOOP: - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NOGROUP)) - != 0) - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - break; - case OMP_TARGET: - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP)) - != 0) - s = C_OMP_CLAUSE_SPLIT_TARGET; - break; - default: - break; - } - if (s != C_OMP_CLAUSE_SPLIT_COUNT) - break; - /* Error-recovery here, invalid if-modifier specified, add the - clause to just one construct. */ - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP)) != 0) - s = C_OMP_CLAUSE_SPLIT_TARGET; - else if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS)) != 0) - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - else if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NOGROUP)) != 0) - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - else if (code == OMP_SIMD) - s = C_OMP_CLAUSE_SPLIT_SIMD; - else - gcc_unreachable (); - break; - } - /* Otherwise, duplicate if clause to all constructs. */ - if (code == OMP_SIMD) - { - if ((mask & ((OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP) - | (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS) - | (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NOGROUP))) - != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_IF); - OMP_CLAUSE_IF_MODIFIER (c) - = OMP_CLAUSE_IF_MODIFIER (clauses); - OMP_CLAUSE_IF_EXPR (c) = OMP_CLAUSE_IF_EXPR (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_SIMD]; - cclauses[C_OMP_CLAUSE_SPLIT_SIMD] = c; - } - else - { - s = C_OMP_CLAUSE_SPLIT_SIMD; - break; - } - } - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NOGROUP)) - != 0) - { - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS)) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_IF); - OMP_CLAUSE_IF_MODIFIER (c) - = OMP_CLAUSE_IF_MODIFIER (clauses); - OMP_CLAUSE_IF_EXPR (c) = OMP_CLAUSE_IF_EXPR (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TASKLOOP]; - cclauses[C_OMP_CLAUSE_SPLIT_TASKLOOP] = c; - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - } - else - s = C_OMP_CLAUSE_SPLIT_TASKLOOP; - } - else if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS)) != 0) - { - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_MAP)) != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_IF); - OMP_CLAUSE_IF_MODIFIER (c) - = OMP_CLAUSE_IF_MODIFIER (clauses); - OMP_CLAUSE_IF_EXPR (c) = OMP_CLAUSE_IF_EXPR (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TARGET]; - cclauses[C_OMP_CLAUSE_SPLIT_TARGET] = c; - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - } - else - s = C_OMP_CLAUSE_SPLIT_PARALLEL; - } - else - s = C_OMP_CLAUSE_SPLIT_TARGET; - break; - case OMP_CLAUSE_LINEAR: - /* Linear clause is allowed on simd and for. Put it on the - innermost construct. */ - if (code == OMP_SIMD) - s = C_OMP_CLAUSE_SPLIT_SIMD; - else - s = C_OMP_CLAUSE_SPLIT_FOR; - break; - case OMP_CLAUSE_NOWAIT: - /* Nowait clause is allowed on target, for and sections, but - is not allowed on parallel for or parallel sections. Therefore, - put it on target construct if present, because that can only - be combined with parallel for{, simd} and not with for{, simd}, - otherwise to the worksharing construct. */ - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP)) - != 0) - s = C_OMP_CLAUSE_SPLIT_TARGET; - else - s = C_OMP_CLAUSE_SPLIT_FOR; - break; - /* thread_limit is allowed on target and teams. Distribute it - to all. */ - case OMP_CLAUSE_THREAD_LIMIT: - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP)) - != 0) - { - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_TEAMS)) - != 0) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_THREAD_LIMIT); - OMP_CLAUSE_THREAD_LIMIT_EXPR (c) - = OMP_CLAUSE_THREAD_LIMIT_EXPR (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[C_OMP_CLAUSE_SPLIT_TARGET]; - cclauses[C_OMP_CLAUSE_SPLIT_TARGET] = c; - } - else - { - s = C_OMP_CLAUSE_SPLIT_TARGET; - break; - } - } - s = C_OMP_CLAUSE_SPLIT_TEAMS; - break; - /* Allocate clause is allowed on target, teams, distribute, parallel, - for, sections and taskloop. Distribute it to all. */ - case OMP_CLAUSE_ALLOCATE: - s = C_OMP_CLAUSE_SPLIT_COUNT; - for (i = 0; i < C_OMP_CLAUSE_SPLIT_COUNT; i++) - { - switch (i) - { - case C_OMP_CLAUSE_SPLIT_TARGET: - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_MAP)) == 0) - continue; - break; - case C_OMP_CLAUSE_SPLIT_TEAMS: - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_TEAMS)) == 0) - continue; - break; - case C_OMP_CLAUSE_SPLIT_DISTRIBUTE: - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE)) == 0) - continue; - break; - case C_OMP_CLAUSE_SPLIT_PARALLEL: - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NUM_THREADS)) == 0) - continue; - break; - case C_OMP_CLAUSE_SPLIT_FOR: - STATIC_ASSERT (C_OMP_CLAUSE_SPLIT_SECTIONS - == C_OMP_CLAUSE_SPLIT_FOR - && (C_OMP_CLAUSE_SPLIT_TASKLOOP - == C_OMP_CLAUSE_SPLIT_FOR) - && (C_OMP_CLAUSE_SPLIT_LOOP - == C_OMP_CLAUSE_SPLIT_FOR)); - if (code == OMP_SECTIONS) - break; - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_SCHEDULE)) != 0) - break; - if ((mask & (OMP_CLAUSE_MASK_1 - << PRAGMA_OMP_CLAUSE_NOGROUP)) != 0) - break; - continue; - case C_OMP_CLAUSE_SPLIT_SIMD: - continue; - default: - gcc_unreachable (); - } - if (s != C_OMP_CLAUSE_SPLIT_COUNT) - { - c = build_omp_clause (OMP_CLAUSE_LOCATION (clauses), - OMP_CLAUSE_ALLOCATE); - OMP_CLAUSE_DECL (c) - = OMP_CLAUSE_DECL (clauses); - OMP_CLAUSE_ALLOCATE_ALLOCATOR (c) - = OMP_CLAUSE_ALLOCATE_ALLOCATOR (clauses); - OMP_CLAUSE_ALLOCATE_ALIGN (c) - = OMP_CLAUSE_ALLOCATE_ALIGN (clauses); - OMP_CLAUSE_CHAIN (c) = cclauses[s]; - cclauses[s] = c; - has_dup_allocate = true; - } - s = (enum c_omp_clause_split) i; - } - gcc_assert (s != C_OMP_CLAUSE_SPLIT_COUNT); - break; - default: - gcc_unreachable (); - } - OMP_CLAUSE_CHAIN (clauses) = cclauses[s]; - cclauses[s] = clauses; - } - - if (has_dup_allocate) - { - bool need_prune = false; - bitmap_obstack_initialize (NULL); - for (i = 0; i < C_OMP_CLAUSE_SPLIT_SIMD - (code == OMP_LOOP); i++) - if (cclauses[i]) - { - bitmap_head allocate_head; - bitmap_initialize (&allocate_head, &bitmap_default_obstack); - for (c = cclauses[i]; c; c = OMP_CLAUSE_CHAIN (c)) - if (OMP_CLAUSE_CODE (c) == OMP_CLAUSE_ALLOCATE - && DECL_P (OMP_CLAUSE_DECL (c))) - bitmap_set_bit (&allocate_head, - DECL_UID (OMP_CLAUSE_DECL (c))); - for (c = cclauses[i]; c; c = OMP_CLAUSE_CHAIN (c)) - switch (OMP_CLAUSE_CODE (c)) - { - case OMP_CLAUSE_REDUCTION: - case OMP_CLAUSE_IN_REDUCTION: - case OMP_CLAUSE_TASK_REDUCTION: - if (TREE_CODE (OMP_CLAUSE_DECL (c)) == MEM_REF) - { - tree t = TREE_OPERAND (OMP_CLAUSE_DECL (c), 0); - if (TREE_CODE (t) == POINTER_PLUS_EXPR) - t = TREE_OPERAND (t, 0); - if (TREE_CODE (t) == ADDR_EXPR - || TREE_CODE (t) == INDIRECT_REF) - t = TREE_OPERAND (t, 0); - if (DECL_P (t)) - bitmap_clear_bit (&allocate_head, DECL_UID (t)); - break; - } - else if (TREE_CODE (OMP_CLAUSE_DECL (c)) == TREE_LIST) - { - tree t; - for (t = OMP_CLAUSE_DECL (c); - TREE_CODE (t) == TREE_LIST; t = TREE_CHAIN (t)) - ; - if (DECL_P (t)) - bitmap_clear_bit (&allocate_head, DECL_UID (t)); - break; - } - /* FALLTHRU */ - case OMP_CLAUSE_PRIVATE: - case OMP_CLAUSE_FIRSTPRIVATE: - case OMP_CLAUSE_LASTPRIVATE: - case OMP_CLAUSE_LINEAR: - if (DECL_P (OMP_CLAUSE_DECL (c))) - bitmap_clear_bit (&allocate_head, - DECL_UID (OMP_CLAUSE_DECL (c))); - break; - default: - break; - } - for (c = cclauses[i]; c; c = OMP_CLAUSE_CHAIN (c)) - if (OMP_CLAUSE_CODE (c) == OMP_CLAUSE_ALLOCATE - && DECL_P (OMP_CLAUSE_DECL (c)) - && bitmap_bit_p (&allocate_head, - DECL_UID (OMP_CLAUSE_DECL (c)))) - { - /* Mark allocate clauses which don't have corresponding - explicit data sharing clause. */ - OMP_CLAUSE_ALLOCATE_COMBINED (c) = 1; - need_prune = true; - } - } - bitmap_obstack_release (NULL); - if (need_prune) - { - /* At least one allocate clause has been marked. Walk all the - duplicated allocate clauses in sync. If it is marked in all - constituent constructs, diagnose it as invalid and remove - them. Otherwise, remove all marked inner clauses inside - a construct that doesn't have them marked. Keep the outer - marked ones, because some clause duplication is done only - during gimplification. */ - tree *p[C_OMP_CLAUSE_SPLIT_COUNT]; - for (i = 0; i < C_OMP_CLAUSE_SPLIT_COUNT; i++) - if (cclauses[i] == NULL_TREE - || i == C_OMP_CLAUSE_SPLIT_SIMD - || (i == C_OMP_CLAUSE_SPLIT_LOOP && code == OMP_LOOP)) - p[i] = NULL; - else - p[i] = &cclauses[i]; - do - { - int j = -1; - tree seen = NULL_TREE; - for (i = C_OMP_CLAUSE_SPLIT_COUNT - 1; i >= 0; i--) - if (p[i]) - { - while (*p[i] - && OMP_CLAUSE_CODE (*p[i]) != OMP_CLAUSE_ALLOCATE) - p[i] = &OMP_CLAUSE_CHAIN (*p[i]); - if (*p[i] == NULL_TREE) - { - i = C_OMP_CLAUSE_SPLIT_COUNT; - break; - } - if (!OMP_CLAUSE_ALLOCATE_COMBINED (*p[i]) && j == -1) - j = i; - seen = *p[i]; - } - if (i == C_OMP_CLAUSE_SPLIT_COUNT) - break; - if (j == -1) - error_at (OMP_CLAUSE_LOCATION (seen), - "%qD specified in %<allocate%> clause but not in " - "an explicit privatization clause", - OMP_CLAUSE_DECL (seen)); - for (i = 0; i < C_OMP_CLAUSE_SPLIT_COUNT; i++) - if (p[i]) - { - if (i > j) - /* Remove. */ - *p[i] = OMP_CLAUSE_CHAIN (*p[i]); - else - /* Keep. */ - p[i] = &OMP_CLAUSE_CHAIN (*p[i]); - } - } - while (1); - } - } - - if (!flag_checking) - return; - - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_MAP)) == 0) - gcc_assert (cclauses[C_OMP_CLAUSE_SPLIT_TARGET] == NULL_TREE); - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_TEAMS)) == 0) - gcc_assert (cclauses[C_OMP_CLAUSE_SPLIT_TEAMS] == NULL_TREE); - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_DIST_SCHEDULE)) == 0 - && (mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_FILTER)) == 0) - gcc_assert (cclauses[C_OMP_CLAUSE_SPLIT_DISTRIBUTE] == NULL_TREE); - if ((mask & (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NUM_THREADS)) == 0) - gcc_assert (cclauses[C_OMP_CLAUSE_SPLIT_PARALLEL] == NULL_TREE); - if ((mask & ((OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_SCHEDULE) - | (OMP_CLAUSE_MASK_1 << PRAGMA_OMP_CLAUSE_NOGROUP))) == 0 - && code != OMP_SECTIONS - && code != OMP_LOOP) - gcc_assert (cclauses[C_OMP_CLAUSE_SPLIT_FOR] == NULL_TREE); - if (code != OMP_SIMD) - gcc_assert (cclauses[C_OMP_CLAUSE_SPLIT_SIMD] == NULL_TREE); -} - - -/* qsort callback to compare #pragma omp declare simd clauses. */ - -static int -c_omp_declare_simd_clause_cmp (const void *p, const void *q) -{ - tree a = *(const tree *) p; - tree b = *(const tree *) q; - if (OMP_CLAUSE_CODE (a) != OMP_CLAUSE_CODE (b)) - { - if (OMP_CLAUSE_CODE (a) > OMP_CLAUSE_CODE (b)) - return -1; - return 1; - } - if (OMP_CLAUSE_CODE (a) != OMP_CLAUSE_SIMDLEN - && OMP_CLAUSE_CODE (a) != OMP_CLAUSE_INBRANCH - && OMP_CLAUSE_CODE (a) != OMP_CLAUSE_NOTINBRANCH) - { - int c = tree_to_shwi (OMP_CLAUSE_DECL (a)); - int d = tree_to_shwi (OMP_CLAUSE_DECL (b)); - if (c < d) - return 1; - if (c > d) - return -1; - } - return 0; -} - -/* Change PARM_DECLs in OMP_CLAUSE_DECL of #pragma omp declare simd - CLAUSES on FNDECL into argument indexes and sort them. */ - -tree -c_omp_declare_simd_clauses_to_numbers (tree parms, tree clauses) -{ - tree c; - vec<tree> clvec = vNULL; - - for (c = clauses; c; c = OMP_CLAUSE_CHAIN (c)) - { - if (OMP_CLAUSE_CODE (c) != OMP_CLAUSE_SIMDLEN - && OMP_CLAUSE_CODE (c) != OMP_CLAUSE_INBRANCH - && OMP_CLAUSE_CODE (c) != OMP_CLAUSE_NOTINBRANCH) - { - tree decl = OMP_CLAUSE_DECL (c); - tree arg; - int idx; - for (arg = parms, idx = 0; arg; - arg = TREE_CHAIN (arg), idx++) - if (arg == decl) - break; - if (arg == NULL_TREE) - { - error_at (OMP_CLAUSE_LOCATION (c), - "%qD is not a function argument", decl); - continue; - } - OMP_CLAUSE_DECL (c) = build_int_cst (integer_type_node, idx); - if (OMP_CLAUSE_CODE (c) == OMP_CLAUSE_LINEAR - && OMP_CLAUSE_LINEAR_VARIABLE_STRIDE (c)) - { - decl = OMP_CLAUSE_LINEAR_STEP (c); - for (arg = parms, idx = 0; arg; - arg = TREE_CHAIN (arg), idx++) - if (arg == decl) - break; - if (arg == NULL_TREE) - { - error_at (OMP_CLAUSE_LOCATION (c), - "%qD is not a function argument", decl); - continue; - } - OMP_CLAUSE_LINEAR_STEP (c) - = build_int_cst (integer_type_node, idx); - } - } - clvec.safe_push (c); - } - if (!clvec.is_empty ()) - { - unsigned int len = clvec.length (), i; - clvec.qsort (c_omp_declare_simd_clause_cmp); - clauses = clvec[0]; - for (i = 0; i < len; i++) - OMP_CLAUSE_CHAIN (clvec[i]) = (i < len - 1) ? clvec[i + 1] : NULL_TREE; - } - else - clauses = NULL_TREE; - clvec.release (); - return clauses; -} - -/* Change argument indexes in CLAUSES of FNDECL back to PARM_DECLs. */ - -void -c_omp_declare_simd_clauses_to_decls (tree fndecl, tree clauses) -{ - tree c; - - for (c = clauses; c; c = OMP_CLAUSE_CHAIN (c)) - if (OMP_CLAUSE_CODE (c) != OMP_CLAUSE_SIMDLEN - && OMP_CLAUSE_CODE (c) != OMP_CLAUSE_INBRANCH - && OMP_CLAUSE_CODE (c) != OMP_CLAUSE_NOTINBRANCH) - { - int idx = tree_to_shwi (OMP_CLAUSE_DECL (c)), i; - tree arg; - for (arg = DECL_ARGUMENTS (fndecl), i = 0; arg; - arg = TREE_CHAIN (arg), i++) - if (i == idx) - break; - gcc_assert (arg); - OMP_CLAUSE_DECL (c) = arg; - if (OMP_CLAUSE_CODE (c) == OMP_CLAUSE_LINEAR - && OMP_CLAUSE_LINEAR_VARIABLE_STRIDE (c)) - { - idx = tree_to_shwi (OMP_CLAUSE_LINEAR_STEP (c)); - for (arg = DECL_ARGUMENTS (fndecl), i = 0; arg; - arg = TREE_CHAIN (arg), i++) - if (i == idx) - break; - gcc_assert (arg); - OMP_CLAUSE_LINEAR_STEP (c) = arg; - } - } -} - -/* Return true for __func__ and similar function-local predefined - variables (which are in OpenMP predetermined shared, allowed in - shared/firstprivate clauses). */ - -bool -c_omp_predefined_variable (tree decl) -{ - if (VAR_P (decl) - && DECL_ARTIFICIAL (decl) - && TREE_STATIC (decl) - && DECL_NAME (decl)) - { - if (TREE_READONLY (decl) - && (DECL_NAME (decl) == ridpointers[RID_C99_FUNCTION_NAME] - || DECL_NAME (decl) == ridpointers[RID_FUNCTION_NAME] - || DECL_NAME (decl) == ridpointers[RID_PRETTY_FUNCTION_NAME])) - return true; - /* For UBSan handle the same also ubsan_create_data created - variables. There is no magic flag for those, but user variables - shouldn't be DECL_ARTIFICIAL or have TYPE_ARTIFICIAL type with - such names. */ - if ((flag_sanitize & (SANITIZE_UNDEFINED - | SANITIZE_UNDEFINED_NONDEFAULT)) != 0 - && DECL_IGNORED_P (decl) - && !TREE_READONLY (decl) - && TREE_CODE (DECL_NAME (decl)) == IDENTIFIER_NODE - && TREE_CODE (TREE_TYPE (decl)) == RECORD_TYPE - && TYPE_ARTIFICIAL (TREE_TYPE (decl)) - && TYPE_NAME (TREE_TYPE (decl)) - && TREE_CODE (TYPE_NAME (TREE_TYPE (decl))) == TYPE_DECL - && DECL_NAME (TYPE_NAME (TREE_TYPE (decl))) - && (TREE_CODE (DECL_NAME (TYPE_NAME (TREE_TYPE (decl)))) - == IDENTIFIER_NODE)) - { - tree id1 = DECL_NAME (decl); - tree id2 = DECL_NAME (TYPE_NAME (TREE_TYPE (decl))); - if (IDENTIFIER_LENGTH (id1) >= sizeof ("ubsan_data") - 1 - && IDENTIFIER_LENGTH (id2) >= sizeof ("__ubsan__data") - && !memcmp (IDENTIFIER_POINTER (id2), "__ubsan_", - sizeof ("__ubsan_") - 1) - && !memcmp (IDENTIFIER_POINTER (id2) + IDENTIFIER_LENGTH (id2) - - sizeof ("_data") + 1, "_data", - sizeof ("_data") - 1) - && strstr (IDENTIFIER_POINTER (id1), "ubsan_data")) - return true; - } - } - return false; -} - -/* OMP_CLAUSE_DEFAULT_UNSPECIFIED unless OpenMP sharing attribute of DECL - is predetermined. */ - -enum omp_clause_default_kind -c_omp_predetermined_sharing (tree decl) -{ - /* Predetermine artificial variables holding integral values, those - are usually result of gimplify_one_sizepos or SAVE_EXPR - gimplification. */ - if (VAR_P (decl) - && DECL_ARTIFICIAL (decl) - && INTEGRAL_TYPE_P (TREE_TYPE (decl))) - return OMP_CLAUSE_DEFAULT_SHARED; - - if (c_omp_predefined_variable (decl)) - return OMP_CLAUSE_DEFAULT_SHARED; - - return OMP_CLAUSE_DEFAULT_UNSPECIFIED; -} - -/* OMP_CLAUSE_DEFAULTMAP_CATEGORY_UNSPECIFIED unless OpenMP mapping attribute - of DECL is predetermined. */ - -enum omp_clause_defaultmap_kind -c_omp_predetermined_mapping (tree decl) -{ - /* Predetermine artificial variables holding integral values, those - are usually result of gimplify_one_sizepos or SAVE_EXPR - gimplification. */ - if (VAR_P (decl) - && DECL_ARTIFICIAL (decl) - && INTEGRAL_TYPE_P (TREE_TYPE (decl))) - return OMP_CLAUSE_DEFAULTMAP_FIRSTPRIVATE; - - if (c_omp_predefined_variable (decl)) - return OMP_CLAUSE_DEFAULTMAP_TO; - - return OMP_CLAUSE_DEFAULTMAP_CATEGORY_UNSPECIFIED; -} - - -/* For OpenACC, the OMP_CLAUSE_MAP_KIND of an OMP_CLAUSE_MAP is used internally - to distinguish clauses as seen by the user. Return the "friendly" clause - name for error messages etc., where possible. See also - c/c-parser.c:c_parser_oacc_data_clause and - cp/parser.c:cp_parser_oacc_data_clause. */ - -const char * -c_omp_map_clause_name (tree clause, bool oacc) -{ - if (oacc && OMP_CLAUSE_CODE (clause) == OMP_CLAUSE_MAP) - switch (OMP_CLAUSE_MAP_KIND (clause)) - { - case GOMP_MAP_FORCE_ALLOC: - case GOMP_MAP_ALLOC: return "create"; - case GOMP_MAP_FORCE_TO: - case GOMP_MAP_TO: return "copyin"; - case GOMP_MAP_FORCE_FROM: - case GOMP_MAP_FROM: return "copyout"; - case GOMP_MAP_FORCE_TOFROM: - case GOMP_MAP_TOFROM: return "copy"; - case GOMP_MAP_RELEASE: return "delete"; - case GOMP_MAP_FORCE_PRESENT: return "present"; - case GOMP_MAP_ATTACH: return "attach"; - case GOMP_MAP_FORCE_DETACH: - case GOMP_MAP_DETACH: return "detach"; - case GOMP_MAP_DEVICE_RESIDENT: return "device_resident"; - case GOMP_MAP_LINK: return "link"; - case GOMP_MAP_FORCE_DEVICEPTR: return "deviceptr"; - default: break; - } - return omp_clause_code_name[OMP_CLAUSE_CODE (clause)]; -} - -/* Used to merge map clause information in c_omp_adjust_map_clauses. */ -struct map_clause -{ - tree clause; - bool firstprivate_ptr_p; - bool decl_mapped; - bool omp_declare_target; - map_clause (void) : clause (NULL_TREE), firstprivate_ptr_p (false), - decl_mapped (false), omp_declare_target (false) { } -}; - -/* Adjust map clauses after normal clause parsing, mainly to turn specific - base-pointer map cases into attach/detach and mark them addressable. */ -void -c_omp_adjust_map_clauses (tree clauses, bool is_target) -{ - if (!is_target) - { - /* If this is not a target construct, just turn firstprivate pointers - into attach/detach, the runtime will check and do the rest. */ - - for (tree c = clauses; c; c = OMP_CLAUSE_CHAIN (c)) - if (OMP_CLAUSE_CODE (c) == OMP_CLAUSE_MAP - && OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_FIRSTPRIVATE_POINTER - && DECL_P (OMP_CLAUSE_DECL (c)) - && POINTER_TYPE_P (TREE_TYPE (OMP_CLAUSE_DECL (c)))) - { - tree ptr = OMP_CLAUSE_DECL (c); - OMP_CLAUSE_SET_MAP_KIND (c, GOMP_MAP_ATTACH_DETACH); - c_common_mark_addressable_vec (ptr); - } - return; - } - - hash_map<tree, map_clause> maps; - - for (tree c = clauses; c; c = OMP_CLAUSE_CHAIN (c)) - if (OMP_CLAUSE_CODE (c) == OMP_CLAUSE_MAP - && DECL_P (OMP_CLAUSE_DECL (c))) - { - /* If this is for a target construct, the firstprivate pointer - is changed to attach/detach if either is true: - (1) the base-pointer is mapped in this same construct, or - (2) the base-pointer is a variable place on the device by - "declare target" directives. - - Here we iterate through all map clauses collecting these cases, - and merge them with a hash_map to process below. */ - - if (OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_FIRSTPRIVATE_POINTER - && POINTER_TYPE_P (TREE_TYPE (OMP_CLAUSE_DECL (c)))) - { - tree ptr = OMP_CLAUSE_DECL (c); - map_clause &mc = maps.get_or_insert (ptr); - if (mc.clause == NULL_TREE) - mc.clause = c; - mc.firstprivate_ptr_p = true; - - if (is_global_var (ptr) - && lookup_attribute ("omp declare target", - DECL_ATTRIBUTES (ptr))) - mc.omp_declare_target = true; - } - else if (OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_ALLOC - || OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_TO - || OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_FROM - || OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_TOFROM - || OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_ALWAYS_TO - || OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_ALWAYS_FROM - || OMP_CLAUSE_MAP_KIND (c) == GOMP_MAP_ALWAYS_TOFROM) - { - map_clause &mc = maps.get_or_insert (OMP_CLAUSE_DECL (c)); - mc.decl_mapped = true; - } - } - - for (hash_map<tree, map_clause>::iterator i = maps.begin (); - i != maps.end (); ++i) - { - map_clause &mc = (*i).second; - - if (mc.firstprivate_ptr_p - && (mc.decl_mapped || mc.omp_declare_target)) - { - OMP_CLAUSE_SET_MAP_KIND (mc.clause, GOMP_MAP_ATTACH_DETACH); - c_common_mark_addressable_vec (OMP_CLAUSE_DECL (mc.clause)); - } - } -} - -static const struct c_omp_directive omp_directives[] = { - /* Keep this alphabetically sorted by the first word. Non-null second/third - if any should precede null ones. */ - { "allocate", nullptr, nullptr, PRAGMA_OMP_ALLOCATE, - C_OMP_DIR_DECLARATIVE, false }, - /* { "assume", nullptr, nullptr, PRAGMA_OMP_ASSUME, - C_OMP_DIR_INFORMATIONAL, false }, */ - /* { "assumes", nullptr, nullptr, PRAGMA_OMP_ASSUMES, - C_OMP_DIR_INFORMATIONAL, false }, */ - { "atomic", nullptr, nullptr, PRAGMA_OMP_ATOMIC, - C_OMP_DIR_CONSTRUCT, false }, - { "barrier", nullptr, nullptr, PRAGMA_OMP_BARRIER, - C_OMP_DIR_STANDALONE, false }, - /* { "begin", "assumes", nullptr, PRAGMA_OMP_BEGIN, - C_OMP_DIR_INFORMATIONAL, false }, */ - /* { "begin", "declare", "target", PRAGMA_OMP_BEGIN, - C_OMP_DIR_DECLARATIVE, false }, */ - /* { "begin", "declare", "variant", PRAGMA_OMP_BEGIN, - C_OMP_DIR_DECLARATIVE, false }, */ - /* { "begin", "metadirective", nullptr, PRAGMA_OMP_BEGIN, - C_OMP_DIR_???, ??? }, */ - { "cancel", nullptr, nullptr, PRAGMA_OMP_CANCEL, - C_OMP_DIR_STANDALONE, false }, - { "cancellation", "point", nullptr, PRAGMA_OMP_CANCELLATION_POINT, - C_OMP_DIR_STANDALONE, false }, - { "critical", nullptr, nullptr, PRAGMA_OMP_CRITICAL, - C_OMP_DIR_CONSTRUCT, false }, - /* { "declare", "mapper", nullptr, PRAGMA_OMP_DECLARE, - C_OMP_DIR_DECLARATIVE, false }, */ - { "declare", "reduction", nullptr, PRAGMA_OMP_DECLARE, - C_OMP_DIR_DECLARATIVE, true }, - { "declare", "simd", nullptr, PRAGMA_OMP_DECLARE, - C_OMP_DIR_DECLARATIVE, true }, - { "declare", "target", nullptr, PRAGMA_OMP_DECLARE, - C_OMP_DIR_DECLARATIVE, false }, - { "declare", "variant", nullptr, PRAGMA_OMP_DECLARE, - C_OMP_DIR_DECLARATIVE, false }, - { "depobj", nullptr, nullptr, PRAGMA_OMP_DEPOBJ, - C_OMP_DIR_STANDALONE, false }, - /* { "dispatch", nullptr, nullptr, PRAGMA_OMP_DISPATCH, - C_OMP_DIR_CONSTRUCT, false }, */ - { "distribute", nullptr, nullptr, PRAGMA_OMP_DISTRIBUTE, - C_OMP_DIR_CONSTRUCT, true }, - /* { "end", "assumes", nullptr, PRAGMA_OMP_END, - C_OMP_DIR_INFORMATIONAL, false }, */ - { "end", "declare", "target", PRAGMA_OMP_END_DECLARE_TARGET, - C_OMP_DIR_DECLARATIVE, false }, - /* { "end", "declare", "variant", PRAGMA_OMP_END, - C_OMP_DIR_DECLARATIVE, false }, */ - /* { "end", "metadirective", nullptr, PRAGMA_OMP_END, - C_OMP_DIR_???, ??? }, */ - /* error with at(execution) is C_OMP_DIR_STANDALONE. */ - { "error", nullptr, nullptr, PRAGMA_OMP_ERROR, - C_OMP_DIR_UTILITY, false }, - { "flush", nullptr, nullptr, PRAGMA_OMP_FLUSH, - C_OMP_DIR_STANDALONE, false }, - { "for", nullptr, nullptr, PRAGMA_OMP_FOR, - C_OMP_DIR_CONSTRUCT, true }, - /* { "interop", nullptr, nullptr, PRAGMA_OMP_INTEROP, - C_OMP_DIR_STANDALONE, false }, */ - { "loop", nullptr, nullptr, PRAGMA_OMP_LOOP, - C_OMP_DIR_CONSTRUCT, true }, - { "masked", nullptr, nullptr, PRAGMA_OMP_MASKED, - C_OMP_DIR_CONSTRUCT, true }, - { "master", nullptr, nullptr, PRAGMA_OMP_MASTER, - C_OMP_DIR_CONSTRUCT, true }, - /* { "metadirective", nullptr, nullptr, PRAGMA_OMP_METADIRECTIVE, - C_OMP_DIR_???, ??? }, */ - { "nothing", nullptr, nullptr, PRAGMA_OMP_NOTHING, - C_OMP_DIR_UTILITY, false }, - /* ordered with depend clause is C_OMP_DIR_STANDALONE. */ - { "ordered", nullptr, nullptr, PRAGMA_OMP_ORDERED, - C_OMP_DIR_CONSTRUCT, true }, - { "parallel", nullptr, nullptr, PRAGMA_OMP_PARALLEL, - C_OMP_DIR_CONSTRUCT, true }, - { "requires", nullptr, nullptr, PRAGMA_OMP_REQUIRES, - C_OMP_DIR_INFORMATIONAL, false }, - { "scan", nullptr, nullptr, PRAGMA_OMP_SCAN, - C_OMP_DIR_CONSTRUCT, true }, - { "scope", nullptr, nullptr, PRAGMA_OMP_SCOPE, - C_OMP_DIR_CONSTRUCT, false }, - { "section", nullptr, nullptr, PRAGMA_OMP_SECTION, - C_OMP_DIR_CONSTRUCT, false }, - { "sections", nullptr, nullptr, PRAGMA_OMP_SECTIONS, - C_OMP_DIR_CONSTRUCT, false }, - { "simd", nullptr, nullptr, PRAGMA_OMP_SIMD, - C_OMP_DIR_CONSTRUCT, true }, - { "single", nullptr, nullptr, PRAGMA_OMP_SINGLE, - C_OMP_DIR_CONSTRUCT, false }, - { "target", "data", nullptr, PRAGMA_OMP_TARGET, - C_OMP_DIR_CONSTRUCT, false }, - { "target", "enter", "data", PRAGMA_OMP_TARGET, - C_OMP_DIR_STANDALONE, false }, - { "target", "exit", "data", PRAGMA_OMP_TARGET, - C_OMP_DIR_STANDALONE, false }, - { "target", "update", nullptr, PRAGMA_OMP_TARGET, - C_OMP_DIR_STANDALONE, false }, - { "target", nullptr, nullptr, PRAGMA_OMP_TARGET, - C_OMP_DIR_CONSTRUCT, true }, - { "task", nullptr, nullptr, PRAGMA_OMP_TASK, - C_OMP_DIR_CONSTRUCT, false }, - { "taskgroup", nullptr, nullptr, PRAGMA_OMP_TASKGROUP, - C_OMP_DIR_CONSTRUCT, false }, - { "taskloop", nullptr, nullptr, PRAGMA_OMP_TASKLOOP, - C_OMP_DIR_CONSTRUCT, true }, - { "taskwait", nullptr, nullptr, PRAGMA_OMP_TASKWAIT, - C_OMP_DIR_STANDALONE, false }, - { "taskyield", nullptr, nullptr, PRAGMA_OMP_TASKYIELD, - C_OMP_DIR_STANDALONE, false }, - /* { "tile", nullptr, nullptr, PRAGMA_OMP_TILE, - C_OMP_DIR_CONSTRUCT, false }, */ - { "teams", nullptr, nullptr, PRAGMA_OMP_TEAMS, - C_OMP_DIR_CONSTRUCT, true }, - { "threadprivate", nullptr, nullptr, PRAGMA_OMP_THREADPRIVATE, - C_OMP_DIR_DECLARATIVE, false } - /* { "unroll", nullptr, nullptr, PRAGMA_OMP_UNROLL, - C_OMP_DIR_CONSTRUCT, false }, */ -}; - -/* Find (non-combined/composite) OpenMP directive (if any) which starts - with FIRST keyword and for multi-word directives has SECOND and - THIRD keyword after it. */ - -const struct c_omp_directive * -c_omp_categorize_directive (const char *first, const char *second, - const char *third) -{ - const size_t n_omp_directives = ARRAY_SIZE (omp_directives); - for (size_t i = 0; i < n_omp_directives; i++) - { - if ((unsigned char) omp_directives[i].first[0] - < (unsigned char) first[0]) - continue; - if ((unsigned char) omp_directives[i].first[0] - > (unsigned char) first[0]) - break; - if (strcmp (omp_directives[i].first, first)) - continue; - if (!omp_directives[i].second) - return &omp_directives[i]; - if (!second || strcmp (omp_directives[i].second, second)) - continue; - if (!omp_directives[i].third) - return &omp_directives[i]; - if (!third || strcmp (omp_directives[i].third, third)) - continue; - return &omp_directives[i]; - } - return NULL; -} |