svn commit: r262470 - in projects/bhyve_svm: . bin bin/date bin/date/tests bin/mv bin/mv/tests bin/pax bin/pax/tests bin/sh bin/sh/tests bin/test bin/test/tests bin/tests contrib/gcc contrib/gcc/co...
Peter Grehan
grehan at FreeBSD.org
Tue Feb 25 06:30:04 UTC 2014
Author: grehan
Date: Tue Feb 25 06:29:56 2014
New Revision: 262470
URL: http://svnweb.freebsd.org/changeset/base/262470
Log:
MFC @ r259635
This brings in the "-w" option from bhyve to ignore unknown MSRs.
It will make debugging Linux guests a bit easier.
Suggested by: Willem Jan Withagen (wjw at digiware nl)
Added:
projects/bhyve_svm/bin/date/tests/
- copied from r259635, head/bin/date/tests/
projects/bhyve_svm/bin/mv/tests/
- copied from r259635, head/bin/mv/tests/
projects/bhyve_svm/bin/pax/tests/
- copied from r259635, head/bin/pax/tests/
projects/bhyve_svm/bin/sh/tests/
- copied from r259635, head/bin/sh/tests/
projects/bhyve_svm/bin/test/tests/
- copied from r259635, head/bin/test/tests/
projects/bhyve_svm/bin/tests/
- copied from r259635, head/bin/tests/
projects/bhyve_svm/contrib/gcclibs/libcpp/ChangeLog.apple
- copied unchanged from r259635, head/contrib/gcclibs/libcpp/ChangeLog.apple
projects/bhyve_svm/etc/rc.d/casperd
- copied unchanged from r259635, head/etc/rc.d/casperd
projects/bhyve_svm/lib/clang/include/PPCGenAsmMatcher.inc
- copied unchanged from r259635, head/lib/clang/include/PPCGenAsmMatcher.inc
projects/bhyve_svm/lib/clang/libllvmpowerpcasmparser/
- copied from r259635, head/lib/clang/libllvmpowerpcasmparser/
projects/bhyve_svm/release/scripts/FreeBSD_install_cdrom.conf
- copied unchanged from r259635, head/release/scripts/FreeBSD_install_cdrom.conf
projects/bhyve_svm/share/mk/tap.test.mk
- copied unchanged from r259635, head/share/mk/tap.test.mk
projects/bhyve_svm/sys/arm/broadcom/bcm2835/bcm2835_fbd.c
- copied unchanged from r259635, head/sys/arm/broadcom/bcm2835/bcm2835_fbd.c
projects/bhyve_svm/sys/boot/fdt/dts/beri-netfpga.dts
- copied unchanged from r259635, head/sys/boot/fdt/dts/beri-netfpga.dts
projects/bhyve_svm/sys/dev/netmap/netmap_freebsd.c
- copied unchanged from r259635, head/sys/dev/netmap/netmap_freebsd.c
projects/bhyve_svm/sys/dev/netmap/netmap_generic.c
- copied unchanged from r259635, head/sys/dev/netmap/netmap_generic.c
projects/bhyve_svm/sys/dev/netmap/netmap_mbq.c
- copied unchanged from r259635, head/sys/dev/netmap/netmap_mbq.c
projects/bhyve_svm/sys/dev/netmap/netmap_mbq.h
- copied unchanged from r259635, head/sys/dev/netmap/netmap_mbq.h
projects/bhyve_svm/sys/dev/netmap/netmap_vale.c
- copied unchanged from r259635, head/sys/dev/netmap/netmap_vale.c
projects/bhyve_svm/sys/mips/conf/BERI_NETFPGA_MDROOT
- copied unchanged from r259635, head/sys/mips/conf/BERI_NETFPGA_MDROOT
projects/bhyve_svm/sys/powerpc/cpufreq/pmufreq.c
- copied unchanged from r259635, head/sys/powerpc/cpufreq/pmufreq.c
projects/bhyve_svm/usr.sbin/bhyve/bhyve.8
- copied unchanged from r259635, head/usr.sbin/bhyve/bhyve.8
Deleted:
projects/bhyve_svm/sys/i386/i386/symbols.raw
projects/bhyve_svm/tools/regression/bin/
Modified:
projects/bhyve_svm/ObsoleteFiles.inc
projects/bhyve_svm/UPDATING
projects/bhyve_svm/bin/Makefile
projects/bhyve_svm/bin/date/Makefile
projects/bhyve_svm/bin/mv/Makefile
projects/bhyve_svm/bin/pax/Makefile
projects/bhyve_svm/bin/sh/Makefile
projects/bhyve_svm/bin/test/Makefile
projects/bhyve_svm/contrib/gcc/ChangeLog.gcc43
projects/bhyve_svm/contrib/gcc/c-opts.c
projects/bhyve_svm/contrib/gcc/c.opt
projects/bhyve_svm/contrib/gcc/calls.c
projects/bhyve_svm/contrib/gcc/config/rs6000/rs6000.c
projects/bhyve_svm/contrib/gcc/cp/ChangeLog.gcc43
projects/bhyve_svm/contrib/gcc/cp/decl.c
projects/bhyve_svm/contrib/gcc/cp/init.c
projects/bhyve_svm/contrib/gcc/cp/method.c
projects/bhyve_svm/contrib/gcc/cp/parser.c
projects/bhyve_svm/contrib/gcc/doc/c-tree.texi
projects/bhyve_svm/contrib/gcc/doc/cppopts.texi
projects/bhyve_svm/contrib/gcc/doc/invoke.texi
projects/bhyve_svm/contrib/gcc/expr.c
projects/bhyve_svm/contrib/gcc/gimple-low.c
projects/bhyve_svm/contrib/gcc/gimplify.c
projects/bhyve_svm/contrib/gcc/omp-low.c
projects/bhyve_svm/contrib/gcc/print-tree.c
projects/bhyve_svm/contrib/gcc/tree-gimple.c
projects/bhyve_svm/contrib/gcc/tree-inline.c
projects/bhyve_svm/contrib/gcc/tree-pretty-print.c
projects/bhyve_svm/contrib/gcc/tree-ssa-alias.c
projects/bhyve_svm/contrib/gcc/tree-ssa-dce.c
projects/bhyve_svm/contrib/gcc/tree-ssa-operands.c
projects/bhyve_svm/contrib/gcc/tree-ssa-structalias.c
projects/bhyve_svm/contrib/gcc/tree.def
projects/bhyve_svm/contrib/gcc/tree.h
projects/bhyve_svm/contrib/gcc/version.c
projects/bhyve_svm/contrib/gcclibs/libcpp/charset.c
projects/bhyve_svm/contrib/gcclibs/libcpp/include/cpplib.h
projects/bhyve_svm/contrib/gcclibs/libcpp/init.c
projects/bhyve_svm/contrib/gcclibs/libcpp/lex.c
projects/bhyve_svm/contrib/llvm/tools/clang/lib/Headers/cpuid.h
projects/bhyve_svm/contrib/tcpdump/addrtoname.c
projects/bhyve_svm/contrib/tcpdump/tcpdump.c
projects/bhyve_svm/contrib/tzcode/stdtime/tzfile.5
projects/bhyve_svm/contrib/tzdata/asia
projects/bhyve_svm/contrib/tzdata/northamerica
projects/bhyve_svm/crypto/heimdal/lib/gssapi/krb5/prf.c
projects/bhyve_svm/etc/defaults/rc.conf
projects/bhyve_svm/etc/mtree/BSD.tests.dist
projects/bhyve_svm/etc/rc.d/Makefile
projects/bhyve_svm/etc/syslog.conf
projects/bhyve_svm/lib/clang/Makefile
projects/bhyve_svm/lib/clang/include/llvm/Config/AsmParsers.def
projects/bhyve_svm/lib/libc/stdlib/getopt_long.3
projects/bhyve_svm/lib/libc/sys/shm_open.2
projects/bhyve_svm/lib/libcam/Makefile
projects/bhyve_svm/lib/libnv/msgio.c
projects/bhyve_svm/lib/libnv/msgio.h
projects/bhyve_svm/lib/libnv/nvlist.c
projects/bhyve_svm/lib/libstand/close.c
projects/bhyve_svm/lib/libstand/dosfs.c
projects/bhyve_svm/lib/libstand/dosfs.h
projects/bhyve_svm/lib/libstand/environment.c
projects/bhyve_svm/lib/libvmmapi/vmmapi.c
projects/bhyve_svm/lib/libvmmapi/vmmapi.h
projects/bhyve_svm/release/Makefile
projects/bhyve_svm/release/doc/en_US.ISO8859-1/relnotes/article.xml
projects/bhyve_svm/release/picobsd/build/picobsd
projects/bhyve_svm/release/scripts/pkg-stage.sh
projects/bhyve_svm/sbin/casperd/zygote.c
projects/bhyve_svm/sbin/devd/devd.cc
projects/bhyve_svm/sbin/growfs/growfs.8
projects/bhyve_svm/sbin/ipfw/ipfw.8
projects/bhyve_svm/sbin/iscontrol/iscsi.conf.5
projects/bhyve_svm/share/man/man4/arcmsr.4
projects/bhyve_svm/share/man/man4/cxgbe.4
projects/bhyve_svm/share/misc/committers-ports.dot
projects/bhyve_svm/share/misc/committers-src.dot
projects/bhyve_svm/share/mk/Makefile
projects/bhyve_svm/share/mk/bsd.own.mk
projects/bhyve_svm/share/mk/bsd.progs.mk
projects/bhyve_svm/sys/amd64/include/vmm_dev.h (contents, props changed)
projects/bhyve_svm/sys/amd64/vmm/intel/vmcs.c
projects/bhyve_svm/sys/amd64/vmm/intel/vmcs.h
projects/bhyve_svm/sys/amd64/vmm/intel/vmx.c
projects/bhyve_svm/sys/amd64/vmm/intel/vmx_genassym.c
projects/bhyve_svm/sys/amd64/vmm/io/ppt.c
projects/bhyve_svm/sys/amd64/vmm/io/ppt.h
projects/bhyve_svm/sys/amd64/vmm/io/vhpet.c
projects/bhyve_svm/sys/amd64/vmm/io/vioapic.c
projects/bhyve_svm/sys/amd64/vmm/io/vlapic.c
projects/bhyve_svm/sys/amd64/vmm/io/vlapic.h
projects/bhyve_svm/sys/amd64/vmm/vmm_dev.c
projects/bhyve_svm/sys/amd64/vmm/vmm_lapic.c
projects/bhyve_svm/sys/amd64/vmm/vmm_lapic.h
projects/bhyve_svm/sys/arm/at91/if_ate.c
projects/bhyve_svm/sys/arm/broadcom/bcm2835/files.bcm2835
projects/bhyve_svm/sys/arm/conf/RPI-B
projects/bhyve_svm/sys/arm/freescale/imx/files.imx51
projects/bhyve_svm/sys/arm/freescale/imx/files.imx53
projects/bhyve_svm/sys/arm/freescale/imx/files.imx6
projects/bhyve_svm/sys/arm/mv/mv_pci.c
projects/bhyve_svm/sys/arm/ti/files.ti
projects/bhyve_svm/sys/boot/ia64/efi/version
projects/bhyve_svm/sys/cam/cam.h
projects/bhyve_svm/sys/cam/cam_ccb.h
projects/bhyve_svm/sys/cam/cam_compat.c
projects/bhyve_svm/sys/cam/cam_compat.h
projects/bhyve_svm/sys/cam/scsi/scsi_xpt.c
projects/bhyve_svm/sys/cddl/contrib/opensolaris/uts/common/fs/zfs/dmu_tx.c
projects/bhyve_svm/sys/cddl/contrib/opensolaris/uts/common/fs/zfs/vdev_geom.c
projects/bhyve_svm/sys/cddl/contrib/opensolaris/uts/intel/dtrace/fasttrap_isa.c
projects/bhyve_svm/sys/cddl/contrib/opensolaris/uts/powerpc/dtrace/fasttrap_isa.c
projects/bhyve_svm/sys/conf/files
projects/bhyve_svm/sys/conf/files.powerpc
projects/bhyve_svm/sys/conf/kern.mk
projects/bhyve_svm/sys/dev/ae/if_ae.c
projects/bhyve_svm/sys/dev/ahci/ahciem.c
projects/bhyve_svm/sys/dev/an/if_an.c
projects/bhyve_svm/sys/dev/an/if_an_pccard.c
projects/bhyve_svm/sys/dev/arcmsr/arcmsr.c
projects/bhyve_svm/sys/dev/arcmsr/arcmsr.h
projects/bhyve_svm/sys/dev/cxgbe/common/common.h
projects/bhyve_svm/sys/dev/cxgbe/offload.h
projects/bhyve_svm/sys/dev/cxgbe/t4_main.c
projects/bhyve_svm/sys/dev/cxgbe/t4_sge.c
projects/bhyve_svm/sys/dev/cxgbe/tom/t4_cpl_io.c
projects/bhyve_svm/sys/dev/cxgbe/tom/t4_listen.c
projects/bhyve_svm/sys/dev/cxgbe/tom/t4_tom.h
projects/bhyve_svm/sys/dev/drm2/drm_fb_helper.c
projects/bhyve_svm/sys/dev/drm2/ttm/ttm_bo_vm.c
projects/bhyve_svm/sys/dev/fdt/fdt_common.h
projects/bhyve_svm/sys/dev/fdt/fdt_pci.c
projects/bhyve_svm/sys/dev/hwpmc/hwpmc_powerpc.c
projects/bhyve_svm/sys/dev/netmap/if_em_netmap.h
projects/bhyve_svm/sys/dev/netmap/if_igb_netmap.h
projects/bhyve_svm/sys/dev/netmap/if_lem_netmap.h
projects/bhyve_svm/sys/dev/netmap/if_re_netmap.h
projects/bhyve_svm/sys/dev/netmap/ixgbe_netmap.h
projects/bhyve_svm/sys/dev/netmap/netmap.c
projects/bhyve_svm/sys/dev/netmap/netmap_kern.h
projects/bhyve_svm/sys/dev/netmap/netmap_mem2.c
projects/bhyve_svm/sys/dev/netmap/netmap_mem2.h
projects/bhyve_svm/sys/dev/nmdm/nmdm.c
projects/bhyve_svm/sys/dev/ofw/ofw_bus_subr.c
projects/bhyve_svm/sys/dev/ofw/ofw_bus_subr.h
projects/bhyve_svm/sys/dev/ofw/ofw_console.c
projects/bhyve_svm/sys/dev/usb/controller/at91dci.c
projects/bhyve_svm/sys/dev/usb/controller/atmegadci.c
projects/bhyve_svm/sys/dev/usb/controller/avr32dci.c
projects/bhyve_svm/sys/dev/usb/controller/dwc_otg.c
projects/bhyve_svm/sys/dev/usb/controller/ehci.c
projects/bhyve_svm/sys/dev/usb/controller/musb_otg.c
projects/bhyve_svm/sys/dev/usb/controller/ohci.c
projects/bhyve_svm/sys/dev/usb/controller/uhci.c
projects/bhyve_svm/sys/dev/usb/controller/uss820dci.c
projects/bhyve_svm/sys/dev/usb/controller/xhci.c
projects/bhyve_svm/sys/dev/usb/template/usb_template.c
projects/bhyve_svm/sys/dev/usb/usb_bus.h
projects/bhyve_svm/sys/dev/usb/usb_device.c
projects/bhyve_svm/sys/dev/usb/usb_device.h
projects/bhyve_svm/sys/dev/usb/usb_hub.c
projects/bhyve_svm/sys/dev/usb/usb_transfer.c
projects/bhyve_svm/sys/dev/usb/usbdi.h
projects/bhyve_svm/sys/dev/usb/wlan/if_run.c
projects/bhyve_svm/sys/dev/usb/wlan/if_runreg.h
projects/bhyve_svm/sys/dev/usb/wlan/if_runvar.h
projects/bhyve_svm/sys/dev/vt/vt.h
projects/bhyve_svm/sys/dev/vt/vt_core.c
projects/bhyve_svm/sys/dev/vt/vt_sysmouse.c
projects/bhyve_svm/sys/fs/devfs/devfs_devs.c
projects/bhyve_svm/sys/fs/fifofs/fifo_vnops.c
projects/bhyve_svm/sys/geom/eli/g_eli.c
projects/bhyve_svm/sys/geom/eli/g_eli_crypto.c
projects/bhyve_svm/sys/geom/geom_dev.c
projects/bhyve_svm/sys/geom/mirror/g_mirror_ctl.c
projects/bhyve_svm/sys/ia64/ia64/pmap.c
projects/bhyve_svm/sys/kern/capabilities.conf
projects/bhyve_svm/sys/kern/init_sysent.c
projects/bhyve_svm/sys/kern/kern_clocksource.c
projects/bhyve_svm/sys/kern/kern_event.c
projects/bhyve_svm/sys/kern/kern_exit.c
projects/bhyve_svm/sys/kern/kern_fork.c
projects/bhyve_svm/sys/kern/kern_jail.c
projects/bhyve_svm/sys/kern/kern_linker.c
projects/bhyve_svm/sys/kern/kern_resource.c
projects/bhyve_svm/sys/kern/kern_rwlock.c
projects/bhyve_svm/sys/kern/makesyscalls.sh
projects/bhyve_svm/sys/kern/subr_trap.c
projects/bhyve_svm/sys/kern/subr_vmem.c
projects/bhyve_svm/sys/kern/tty.c
projects/bhyve_svm/sys/kern/uipc_syscalls.c
projects/bhyve_svm/sys/kern/vfs_vnops.c
projects/bhyve_svm/sys/mips/beri/beri_machdep.c
projects/bhyve_svm/sys/modules/netmap/Makefile
projects/bhyve_svm/sys/net/netmap.h
projects/bhyve_svm/sys/net/netmap_user.h
projects/bhyve_svm/sys/net/radix.c
projects/bhyve_svm/sys/netinet6/send.c
projects/bhyve_svm/sys/netpfil/ipfw/ip_fw_dynamic.c
projects/bhyve_svm/sys/ofed/drivers/net/mlx4/en_netdev.c
projects/bhyve_svm/sys/ofed/drivers/net/mlx4/mlx4_en.h
projects/bhyve_svm/sys/powerpc/aim/mp_cpudep.c
projects/bhyve_svm/sys/powerpc/aim/trap.c
projects/bhyve_svm/sys/powerpc/aim/trap_subr32.S
projects/bhyve_svm/sys/powerpc/aim/trap_subr64.S
projects/bhyve_svm/sys/powerpc/include/cpu.h
projects/bhyve_svm/sys/powerpc/include/dbdma.h
projects/bhyve_svm/sys/powerpc/include/pcpu.h
projects/bhyve_svm/sys/powerpc/include/pmc_mdep.h
projects/bhyve_svm/sys/powerpc/include/spr.h
projects/bhyve_svm/sys/powerpc/ofw/ofw_pci.c
projects/bhyve_svm/sys/powerpc/ofw/ofw_pcib_pci.c
projects/bhyve_svm/sys/powerpc/powermac/platform_powermac.c
projects/bhyve_svm/sys/powerpc/powermac/pmu.c
projects/bhyve_svm/sys/powerpc/powermac/pmuvar.h
projects/bhyve_svm/sys/powerpc/powermac/uninorth.c
projects/bhyve_svm/sys/powerpc/powermac/uninorthvar.h
projects/bhyve_svm/sys/powerpc/powermac/viareg.h
projects/bhyve_svm/sys/powerpc/powerpc/mp_machdep.c
projects/bhyve_svm/sys/powerpc/pseries/phyp_vscsi.c
projects/bhyve_svm/sys/rpc/svc_vc.c
projects/bhyve_svm/sys/sparc64/ebus/ebus.c
projects/bhyve_svm/sys/sparc64/isa/ofw_isa.c
projects/bhyve_svm/sys/sparc64/pci/fire.c
projects/bhyve_svm/sys/sparc64/pci/ofw_pcib_subr.c
projects/bhyve_svm/sys/sparc64/pci/psycho.c
projects/bhyve_svm/sys/sparc64/pci/schizo.c
projects/bhyve_svm/sys/sys/param.h
projects/bhyve_svm/sys/sys/tty.h
projects/bhyve_svm/sys/x86/include/mptable.h
projects/bhyve_svm/sys/x86/x86/mptable.c
projects/bhyve_svm/usr.bin/calendar/calcpp.c
projects/bhyve_svm/usr.bin/clang/clang/Makefile
projects/bhyve_svm/usr.bin/clang/llc/Makefile
projects/bhyve_svm/usr.bin/clang/lldb/Makefile
projects/bhyve_svm/usr.bin/clang/llvm-mc/Makefile
projects/bhyve_svm/usr.bin/clang/llvm-objdump/Makefile
projects/bhyve_svm/usr.bin/clang/llvm-rtdyld/Makefile
projects/bhyve_svm/usr.bin/clang/opt/Makefile
projects/bhyve_svm/usr.bin/dtc/fdt.cc
projects/bhyve_svm/usr.bin/kdump/Makefile
projects/bhyve_svm/usr.bin/kdump/kdump.c
projects/bhyve_svm/usr.bin/netstat/main.c
projects/bhyve_svm/usr.bin/netstat/netstat.h
projects/bhyve_svm/usr.bin/netstat/route.c
projects/bhyve_svm/usr.sbin/bhyve/Makefile
projects/bhyve_svm/usr.sbin/bhyve/bhyverun.c
projects/bhyve_svm/usr.sbin/bhyve/pci_emul.c
projects/bhyve_svm/usr.sbin/bhyve/pci_emul.h
projects/bhyve_svm/usr.sbin/bhyve/pci_passthru.c
projects/bhyve_svm/usr.sbin/bhyve/xmsr.c
projects/bhyve_svm/usr.sbin/bhyve/xmsr.h
projects/bhyve_svm/usr.sbin/bhyvectl/bhyvectl.c
projects/bhyve_svm/usr.sbin/bsdconfig/share/packages/index.subr
projects/bhyve_svm/usr.sbin/bsdinstall/scripts/auto
projects/bhyve_svm/usr.sbin/bsdinstall/scripts/config
projects/bhyve_svm/usr.sbin/bsdinstall/scripts/services
projects/bhyve_svm/usr.sbin/bsdinstall/scripts/zfsboot
projects/bhyve_svm/usr.sbin/mptable/mptable.c
projects/bhyve_svm/usr.sbin/pkg/config.c
projects/bhyve_svm/usr.sbin/pkg/config.h
projects/bhyve_svm/usr.sbin/pkg/pkg.7
projects/bhyve_svm/usr.sbin/tcpdump/tcpdump/Makefile
projects/bhyve_svm/usr.sbin/ypbind/yp_ping.c
Directory Properties:
projects/bhyve_svm/ (props changed)
projects/bhyve_svm/contrib/gcc/ (props changed)
projects/bhyve_svm/contrib/llvm/ (props changed)
projects/bhyve_svm/contrib/llvm/tools/clang/ (props changed)
projects/bhyve_svm/contrib/tcpdump/ (props changed)
projects/bhyve_svm/contrib/tzcode/stdtime/ (props changed)
projects/bhyve_svm/contrib/tzdata/ (props changed)
projects/bhyve_svm/crypto/heimdal/ (props changed)
projects/bhyve_svm/etc/ (props changed)
projects/bhyve_svm/gnu/lib/ (props changed)
projects/bhyve_svm/lib/libc/ (props changed)
projects/bhyve_svm/lib/libvmmapi/ (props changed)
projects/bhyve_svm/sbin/ (props changed)
projects/bhyve_svm/sbin/ipfw/ (props changed)
projects/bhyve_svm/share/man/man4/ (props changed)
projects/bhyve_svm/sys/ (props changed)
projects/bhyve_svm/sys/amd64/vmm/ (props changed)
projects/bhyve_svm/sys/boot/ (props changed)
projects/bhyve_svm/sys/boot/ia64/efi/ (props changed)
projects/bhyve_svm/sys/cddl/contrib/opensolaris/ (props changed)
projects/bhyve_svm/sys/conf/ (props changed)
projects/bhyve_svm/usr.bin/calendar/ (props changed)
projects/bhyve_svm/usr.sbin/bhyve/ (props changed)
projects/bhyve_svm/usr.sbin/bhyvectl/ (props changed)
Modified: projects/bhyve_svm/ObsoleteFiles.inc
==============================================================================
--- projects/bhyve_svm/ObsoleteFiles.inc Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/ObsoleteFiles.inc Tue Feb 25 06:29:56 2014 (r262470)
@@ -38,6 +38,8 @@
# xargs -n1 | sort | uniq -d;
# done
+# 20131215: libcam version bumped
+OLD_LIBS+=lib/libcam.so.6 usr/lib32/libcam.so.6
# 20131202: libcapsicum and libcasper moved to /lib/
OLD_LIBS+=usr/lib/libcapsicum.so.0
OLD_LIBS+=usr/lib/libcasper.so.0
Modified: projects/bhyve_svm/UPDATING
==============================================================================
--- projects/bhyve_svm/UPDATING Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/UPDATING Tue Feb 25 06:29:56 2014 (r262470)
@@ -31,6 +31,17 @@ NOTE TO PEOPLE WHO THINK THAT FreeBSD 11
disable the most expensive debugging functionality run
"ln -s 'abort:false,junk:false' /etc/malloc.conf".)
+20131213:
+ The behavior of gss_pseudo_random() for the krb5 mechanism
+ has changed, for applications requesting a longer random string
+ than produced by the underlying enctype's pseudo-random() function.
+ In particular, the random string produced from a session key of
+ enctype aes256-cts-hmac-sha1-96 or aes256-cts-hmac-sha1-96 will
+ be different at the 17th octet and later, after this change.
+ The counter used in the PRF+ construction is now encoded as a
+ big-endian integer in accordance with RFC 4402.
+ __FreeBSD_version is bumped to 1100004.
+
20131108:
The WITHOUT_ATF build knob has been removed and its functionality
has been subsumed into the more generic WITHOUT_TESTS. If you were
Modified: projects/bhyve_svm/bin/Makefile
==============================================================================
--- projects/bhyve_svm/bin/Makefile Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/bin/Makefile Tue Feb 25 06:29:56 2014 (r262470)
@@ -52,6 +52,10 @@ SUBDIR+= rmail
SUBDIR+= csh
.endif
+.if ${MK_TESTS} != "no"
+SUBDIR+= tests
+.endif
+
.include <bsd.arch.inc.mk>
SUBDIR:= ${SUBDIR:O}
Modified: projects/bhyve_svm/bin/date/Makefile
==============================================================================
--- projects/bhyve_svm/bin/date/Makefile Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/bin/date/Makefile Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,7 +1,13 @@
# @(#)Makefile 8.1 (Berkeley) 5/31/93
# $FreeBSD$
+.include <bsd.own.mk>
+
PROG= date
SRCS= date.c netdate.c vary.c
+.if ${MK_TESTS} != "no"
+SUBDIR+= tests
+.endif
+
.include <bsd.prog.mk>
Modified: projects/bhyve_svm/bin/mv/Makefile
==============================================================================
--- projects/bhyve_svm/bin/mv/Makefile Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/bin/mv/Makefile Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,6 +1,12 @@
# @(#)Makefile 8.2 (Berkeley) 4/2/94
# $FreeBSD$
+.include <bsd.own.mk>
+
PROG= mv
+.if ${MK_TESTS} != "no"
+SUBDIR+= tests
+.endif
+
.include <bsd.prog.mk>
Modified: projects/bhyve_svm/bin/pax/Makefile
==============================================================================
--- projects/bhyve_svm/bin/pax/Makefile Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/bin/pax/Makefile Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,6 +1,8 @@
# @(#)Makefile 8.1 (Berkeley) 5/31/93
# $FreeBSD$
+.include <bsd.own.mk>
+
# To install on versions prior to BSD 4.4 the following may have to be
# defined with CFLAGS +=
#
@@ -30,4 +32,8 @@ SRCS= ar_io.c ar_subs.c buf_subs.c cache
gen_subs.c getoldopt.c options.c pat_rep.c pax.c sel_subs.c \
tables.c tar.c tty_subs.c
+.if ${MK_TESTS} != "no"
+SUBDIR+= tests
+.endif
+
.include <bsd.prog.mk>
Modified: projects/bhyve_svm/bin/sh/Makefile
==============================================================================
--- projects/bhyve_svm/bin/sh/Makefile Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/bin/sh/Makefile Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,6 +1,8 @@
# @(#)Makefile 8.4 (Berkeley) 5/5/95
# $FreeBSD$
+.include <bsd.own.mk>
+
PROG= sh
INSTALLFLAGS= -S
SHSRCS= alias.c arith_yacc.c arith_yylex.c cd.c echo.c error.c eval.c \
@@ -59,7 +61,8 @@ syntax.c syntax.h: mksyntax
token.h: mktokens
sh ${.CURDIR}/mktokens
-regress:
- cd ${.CURDIR}/../../tools/regression/bin/sh && ${MAKE} SH=${.OBJDIR}/sh
+.if ${MK_TESTS} != "no"
+SUBDIR+= tests
+.endif
.include <bsd.prog.mk>
Modified: projects/bhyve_svm/bin/test/Makefile
==============================================================================
--- projects/bhyve_svm/bin/test/Makefile Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/bin/test/Makefile Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,8 +1,14 @@
# @(#)Makefile 8.1 (Berkeley) 5/31/93
# $FreeBSD$
+.include <bsd.own.mk>
+
PROG= test
LINKS= ${BINDIR}/test ${BINDIR}/[
MLINKS= test.1 [.1
+.if ${MK_TESTS} != "no"
+SUBDIR+= tests
+.endif
+
.include <bsd.prog.mk>
Modified: projects/bhyve_svm/contrib/gcc/ChangeLog.gcc43
==============================================================================
--- projects/bhyve_svm/contrib/gcc/ChangeLog.gcc43 Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/ChangeLog.gcc43 Tue Feb 25 06:29:56 2014 (r262470)
@@ -45,12 +45,68 @@
* flags.h (force_align_functions_log): Delete.
* toplev.c (force_align_functions_log): Delete.
+2007-07-06 Josh Conner <jconner at apple.com> (r126422)
+
+ PR middle-end/32602
+ PR middle-end/32603
+ * calls.c (store_one_arg): Handle arguments which are partially
+ on the stack when detecting argument overlap.
+
+2007-07-03 Eric Christopher <echristo at apple.com> (r126278)
+
+ * doc/cppopts.texi: Add conflicting option note to -dM.
+ * doc/invoke.texi: Add note about possible conflicts with
+ -E for -dCHARS and note that -dM will not produce
+ any results if there is no machine dependent reorg.
+
2007-06-28 Geoffrey Keating <geoffk at apple.com> (r126088)
* doc/invoke.texi (C++ Dialect Options): Document
fvisibility-ms-compat.
* c.opt (fvisibility-ms-compat): New.
+2007-06-12 Ian Lance Taylor <iant at google.com> (r125653)
+ Daniel Berlin <dberlin at dberlin.org>
+
+ PR libstdc++/29286
+ * tree.def: Add CHANGE_DYNAMIC_TYPE_EXPR.
+ * tree.h (CHANGE_DYNAMIC_TYPE_NEW_TYPE): Define.
+ (CHANGE_DYNAMIC_TYPE_LOCATION): Define.
+ (DECL_NO_TBAA_P): Define.
+ (struct tree_decl_common): Add no_tbaa_flag field.
+ * tree-ssa-structalias.c (struct variable_info): Add
+ no_tbaa_pruning field.
+ (new_var_info): Initialize no_tbaa_pruning field.
+ (unify_nodes): Copy no_tbaa_pruning field.
+ (find_func_aliases): Handle CHANGE_DYNAMIC_TYPE_EXPR.
+ (dump_solution_for_var): Print no_tbaa_pruning flag.
+ (set_uids_in_ptset): Add no_tbaa_pruning parameter. Change all
+ callers.
+ (compute_tbaa_pruning): New static function.
+ (compute_points_to_sets): Remove CHANGE_DYNAMIC_TYPE_EXPR nodes.
+ Call compute_tbaa_pruning.
+ * tree-ssa-alias.c (may_alias_p): Test no_tbaa_flag for pointers.
+ * gimplify.c (gimplify_expr): Handle CHANGE_DYNAMIC_TYPE_EXPR.
+ * gimple-low.c (lower_stmt): Likewise.
+ * tree-gimple.c (is_gimple_stmt): Likewise.
+ * tree-ssa-operands.c (get_expr_operands): Likewise.
+ * tree-ssa-dce.c (mark_stmt_if_obviously_necessary): Likewise.
+ * tree-inline.c (estimate_num_insns_1): Likewise.
+ (copy_result_decl_to_var): Likewise.
+ * expr.c (expand_expr_real_1): Likewise.
+ * tree-pretty-print.c (dump_generic_node): Likewise.
+ * tree-inline.c (copy_decl_to_var): Copy DECL_NO_TBAA_P flag.
+ * omp-low.c (omp_copy_decl_2): Likewise.
+ * print-tree.c (print_node): Print DECL_NO_TBAA_P flag.
+ * doc/c-tree.texi (Expression trees): Document
+ CHANGE_DYNAMIC_TYPE_EXPR.
+
+2007-06-09 Daniel Berlin <dberlin at dberlin.org> (r125603)
+
+ * tree-ssa-structalias.c (set_uids_in_ptset): Add is_deref'd
+ parameter, use it.
+ (find_what_p_points_to): Pass new parameter to set_uids_in_ptset.
+
2007-06-05 Joerg Wunsch <j.gnu at uriah.heep.sax.de> (r125346)
PR preprocessor/23479
@@ -399,6 +455,12 @@
(override_options): Add PTA_CX16 flag. Set x86_cmpxchg16b
for CPUs that have PTA_CX16 set.
+2007-01-18 Josh Conner <jconner at apple.com> (r120902)
+
+ PR target/30485
+ * config/rs6000/rs6000.c (rs6000_emit_vector_compare): Add
+ support for UNLE, UNLT, UNGE, and UNGT.
+
2007-01-17 Eric Christopher <echristo at apple.com> (r120846)
* config.gcc: Support core2 processor.
Modified: projects/bhyve_svm/contrib/gcc/c-opts.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/c-opts.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/c-opts.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -487,6 +487,12 @@ c_common_handle_option (size_t scode, co
cpp_opts->warn_multichar = value;
break;
+ /* APPLE LOCAL begin -Wnewline-eof */
+ case OPT_Wnewline_eof:
+ cpp_opts->warn_newline_at_eof = value;
+ break;
+ /* APPLE LOCAL end -Wnewline-eof */
+
case OPT_Wnormalized_:
if (!value || (arg && strcasecmp (arg, "none") == 0))
cpp_opts->warn_normalize = normalized_none;
Modified: projects/bhyve_svm/contrib/gcc/c.opt
==============================================================================
--- projects/bhyve_svm/contrib/gcc/c.opt Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/c.opt Tue Feb 25 06:29:56 2014 (r262470)
@@ -292,6 +292,12 @@ Wnested-externs
C ObjC Var(warn_nested_externs)
Warn about \"extern\" declarations not at file scope
+; APPLE LOCAL begin -Wnewline-eof
+Wnewline-eof
+C ObjC C++ ObjC++
+Warn about files missing a newline at the end of the file
+; APPLE LOCAL end -Wnewline-eof
+
Wnon-template-friend
C++ ObjC++ Var(warn_nontemplate_friend) Init(1)
Warn when non-templatized friend functions are declared within a template
Modified: projects/bhyve_svm/contrib/gcc/calls.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/calls.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/calls.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -4297,6 +4297,7 @@ store_one_arg (struct arg_data *arg, rtx
/* expand_call should ensure this. */
gcc_assert (!arg->locate.offset.var
+ && arg->locate.size.var == 0
&& GET_CODE (size_rtx) == CONST_INT);
if (arg->locate.offset.constant > i)
@@ -4306,7 +4307,21 @@ store_one_arg (struct arg_data *arg, rtx
}
else if (arg->locate.offset.constant < i)
{
- if (i < arg->locate.offset.constant + INTVAL (size_rtx))
+ /* Use arg->locate.size.constant instead of size_rtx
+ because we only care about the part of the argument
+ on the stack. */
+ if (i < (arg->locate.offset.constant
+ + arg->locate.size.constant))
+ sibcall_failure = 1;
+ }
+ else
+ {
+ /* Even though they appear to be at the same location,
+ if part of the outgoing argument is in registers,
+ they aren't really at the same location. Check for
+ this by making sure that the incoming size is the
+ same as the outgoing size. */
+ if (arg->locate.size.constant != INTVAL (size_rtx))
sibcall_failure = 1;
}
}
Modified: projects/bhyve_svm/contrib/gcc/config/rs6000/rs6000.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/config/rs6000/rs6000.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/config/rs6000/rs6000.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -11738,11 +11738,20 @@ rs6000_emit_vector_compare (enum rtx_cod
try_again = true;
break;
case NE:
- /* Treat A != B as ~(A==B). */
+ case UNLE:
+ case UNLT:
+ case UNGE:
+ case UNGT:
+ /* Invert condition and try again.
+ e.g., A != B becomes ~(A==B). */
{
+ enum rtx_code rev_code;
enum insn_code nor_code;
- rtx eq_rtx = rs6000_emit_vector_compare (EQ, op0, op1,
- dest_mode);
+ rtx eq_rtx;
+
+ rev_code = reverse_condition_maybe_unordered (rcode);
+ eq_rtx = rs6000_emit_vector_compare (rev_code, op0, op1,
+ dest_mode);
nor_code = one_cmpl_optab->handlers[(int)dest_mode].insn_code;
gcc_assert (nor_code != CODE_FOR_nothing);
Modified: projects/bhyve_svm/contrib/gcc/cp/ChangeLog.gcc43
==============================================================================
--- projects/bhyve_svm/contrib/gcc/cp/ChangeLog.gcc43 Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/cp/ChangeLog.gcc43 Tue Feb 25 06:29:56 2014 (r262470)
@@ -25,6 +25,12 @@
* decl2.c (determine_visibility): Remove duplicate code for
handling type info.
+2007-06-12 Ian Lance Taylor <iant at google.com> (r125653)
+
+ PR libstdc++/29286
+ * init.c (avoid_placement_new_aliasing): New static function.
+ (build_new_1): Call it.
+
2007-05-31 Daniel Berlin <dberlin at dberlin.org> (r125239)
* typeck.c (build_binary_op): Include types in error.
@@ -62,6 +68,18 @@
* semantics.c (finish_unary_op_expr): Warn only if result
overflowed and operands did not.
+2006-12-01 Geoffrey Keating <geoffk at apple.com> (r119427)
+
+ * decl.c (poplevel): Check DECL_INITIAL invariant.
+ (duplicate_decls): Preserve DECL_INITIAL when eliminating
+ a new definition in favour of an old declaration.
+ (start_preparsed_function): Define and document value of
+ DECL_INITIAL before and after routine.
+ (finish_function): Check DECL_INITIAL invariant.
+ * parser.c
+ (cp_parser_function_definition_from_specifiers_and_declarator):
+ Skip duplicate function definitions.
+
2006-10-31 Geoffrey Keating <geoffk at apple.com> (r118360)
* name-lookup.c (get_anonymous_namespace_name): New.
Modified: projects/bhyve_svm/contrib/gcc/cp/decl.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/cp/decl.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/cp/decl.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -758,7 +758,12 @@ poplevel (int keep, int reverse, int fun
leave_scope ();
if (functionbody)
- DECL_INITIAL (current_function_decl) = block;
+ {
+ /* The current function is being defined, so its DECL_INITIAL
+ should be error_mark_node. */
+ gcc_assert (DECL_INITIAL (current_function_decl) == error_mark_node);
+ DECL_INITIAL (current_function_decl) = block;
+ }
else if (block)
current_binding_level->blocks
= chainon (current_binding_level->blocks, block);
@@ -1635,13 +1640,15 @@ duplicate_decls (tree newdecl, tree oldd
}
/* If the new declaration is a definition, update the file and
- line information on the declaration. */
+ line information on the declaration, and also make
+ the old declaration the same definition. */
if (DECL_INITIAL (old_result) == NULL_TREE
&& DECL_INITIAL (new_result) != NULL_TREE)
{
DECL_SOURCE_LOCATION (olddecl)
= DECL_SOURCE_LOCATION (old_result)
= DECL_SOURCE_LOCATION (newdecl);
+ DECL_INITIAL (old_result) = DECL_INITIAL (new_result);
if (DECL_FUNCTION_TEMPLATE_P (newdecl))
DECL_ARGUMENTS (old_result)
= DECL_ARGUMENTS (new_result);
@@ -10509,7 +10516,13 @@ check_function_type (tree decl, tree cur
For C++, we must first check whether that datum makes any sense.
For example, "class A local_a(1,2);" means that variable local_a
is an aggregate of type A, which should have a constructor
- applied to it with the argument list [1, 2]. */
+ applied to it with the argument list [1, 2].
+
+ On entry, DECL_INITIAL (decl1) should be NULL_TREE or error_mark_node,
+ or may be a BLOCK if the function has been defined previously
+ in this translation unit. On exit, DECL_INITIAL (decl1) will be
+ error_mark_node if the function has never been defined, or
+ a BLOCK if the function has been defined somewhere. */
void
start_preparsed_function (tree decl1, tree attrs, int flags)
@@ -10638,24 +10651,6 @@ start_preparsed_function (tree decl1, tr
cp_apply_type_quals_to_decl (cp_type_quals (restype), resdecl);
}
- /* Initialize RTL machinery. We cannot do this until
- CURRENT_FUNCTION_DECL and DECL_RESULT are set up. We do this
- even when processing a template; this is how we get
- CFUN set up, and our per-function variables initialized.
- FIXME factor out the non-RTL stuff. */
- bl = current_binding_level;
- allocate_struct_function (decl1);
- current_binding_level = bl;
-
- /* Even though we're inside a function body, we still don't want to
- call expand_expr to calculate the size of a variable-sized array.
- We haven't necessarily assigned RTL to all variables yet, so it's
- not safe to try to expand expressions involving them. */
- cfun->x_dont_save_pending_sizes_p = 1;
-
- /* Start the statement-tree, start the tree now. */
- DECL_SAVED_TREE (decl1) = push_stmt_list ();
-
/* Let the user know we're compiling this function. */
announce_function (decl1);
@@ -10701,9 +10696,33 @@ start_preparsed_function (tree decl1, tr
maybe_apply_pragma_weak (decl1);
}
- /* Reset these in case the call to pushdecl changed them. */
+ /* Reset this in case the call to pushdecl changed it. */
current_function_decl = decl1;
- cfun->decl = decl1;
+
+ gcc_assert (DECL_INITIAL (decl1));
+
+ /* This function may already have been parsed, in which case just
+ return; our caller will skip over the body without parsing. */
+ if (DECL_INITIAL (decl1) != error_mark_node)
+ return;
+
+ /* Initialize RTL machinery. We cannot do this until
+ CURRENT_FUNCTION_DECL and DECL_RESULT are set up. We do this
+ even when processing a template; this is how we get
+ CFUN set up, and our per-function variables initialized.
+ FIXME factor out the non-RTL stuff. */
+ bl = current_binding_level;
+ allocate_struct_function (decl1);
+ current_binding_level = bl;
+
+ /* Even though we're inside a function body, we still don't want to
+ call expand_expr to calculate the size of a variable-sized array.
+ We haven't necessarily assigned RTL to all variables yet, so it's
+ not safe to try to expand expressions involving them. */
+ cfun->x_dont_save_pending_sizes_p = 1;
+
+ /* Start the statement-tree, start the tree now. */
+ DECL_SAVED_TREE (decl1) = push_stmt_list ();
/* If we are (erroneously) defining a function that we have already
defined before, wipe out what we knew before. */
@@ -11212,6 +11231,10 @@ finish_function (int flags)
which then got a warning when stored in a ptr-to-function variable. */
gcc_assert (building_stmt_tree ());
+ /* The current function is being defined, so its DECL_INITIAL should
+ be set, and unless there's a multiple definition, it should be
+ error_mark_node. */
+ gcc_assert (DECL_INITIAL (fndecl) == error_mark_node);
/* For a cloned function, we've already got all the code we need;
there's no need to add any extra bits. */
Modified: projects/bhyve_svm/contrib/gcc/cp/init.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/cp/init.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/cp/init.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,6 +1,7 @@
/* Handle initialization things in C++.
Copyright (C) 1987, 1989, 1992, 1993, 1994, 1995, 1996, 1997, 1998,
- 1999, 2000, 2001, 2002, 2003, 2004, 2005 Free Software Foundation, Inc.
+ 1999, 2000, 2001, 2002, 2003, 2004, 2005, 2006, 2007
+ Free Software Foundation, Inc.
Contributed by Michael Tiemann (tiemann at cygnus.com)
This file is part of GCC.
@@ -1564,6 +1565,55 @@ build_raw_new_expr (tree placement, tree
return new_expr;
}
+/* Make sure that there are no aliasing issues with T, a placement new
+ expression applied to PLACEMENT, by recording the change in dynamic
+ type. If placement new is inlined, as it is with libstdc++, and if
+ the type of the placement new differs from the type of the
+ placement location itself, then alias analysis may think it is OK
+ to interchange writes to the location from before the placement new
+ and from after the placement new. We have to prevent type-based
+ alias analysis from applying. PLACEMENT may be NULL, which means
+ that we couldn't capture it in a temporary variable, in which case
+ we use a memory clobber. */
+
+static tree
+avoid_placement_new_aliasing (tree t, tree placement)
+{
+ tree type_change;
+
+ if (processing_template_decl)
+ return t;
+
+ /* If we are not using type based aliasing, we don't have to do
+ anything. */
+ if (!flag_strict_aliasing)
+ return t;
+
+ /* If we have a pointer and a location, record the change in dynamic
+ type. Otherwise we need a general memory clobber. */
+ if (TREE_CODE (TREE_TYPE (t)) == POINTER_TYPE
+ && placement != NULL_TREE
+ && TREE_CODE (TREE_TYPE (placement)) == POINTER_TYPE)
+ type_change = build_stmt (CHANGE_DYNAMIC_TYPE_EXPR,
+ TREE_TYPE (t),
+ placement);
+ else
+ {
+ /* Build a memory clobber. */
+ type_change = build_stmt (ASM_EXPR,
+ build_string (0, ""),
+ NULL_TREE,
+ NULL_TREE,
+ tree_cons (NULL_TREE,
+ build_string (6, "memory"),
+ NULL_TREE));
+
+ ASM_VOLATILE_P (type_change) = 1;
+ }
+
+ return build2 (COMPOUND_EXPR, TREE_TYPE (t), type_change, t);
+}
+
/* Generate code for a new-expression, including calling the "operator
new" function, initializing the object, and, if an exception occurs
during construction, cleaning up. The arguments are as for
@@ -1607,6 +1657,7 @@ build_new_1 (tree placement, tree type,
beginning of the storage allocated for an array-new expression in
order to store the number of elements. */
tree cookie_size = NULL_TREE;
+ tree placement_var;
/* True if the function we are calling is a placement allocation
function. */
bool placement_allocation_fn_p;
@@ -1700,6 +1751,20 @@ build_new_1 (tree placement, tree type,
alloc_fn = NULL_TREE;
+ /* If PLACEMENT is a simple pointer type, then copy it into
+ PLACEMENT_VAR. */
+ if (processing_template_decl
+ || placement == NULL_TREE
+ || TREE_CHAIN (placement) != NULL_TREE
+ || TREE_CODE (TREE_TYPE (TREE_VALUE (placement))) != POINTER_TYPE)
+ placement_var = NULL_TREE;
+ else
+ {
+ placement_var = get_temp_regvar (TREE_TYPE (TREE_VALUE (placement)),
+ TREE_VALUE (placement));
+ placement = tree_cons (NULL_TREE, placement_var, NULL_TREE);
+ }
+
/* Allocate the object. */
if (! placement && TYPE_FOR_JAVA (elt_type))
{
@@ -1792,7 +1857,12 @@ build_new_1 (tree placement, tree type,
/* In the simple case, we can stop now. */
pointer_type = build_pointer_type (type);
if (!cookie_size && !is_initialized)
- return build_nop (pointer_type, alloc_call);
+ {
+ rval = build_nop (pointer_type, alloc_call);
+ if (placement != NULL)
+ rval = avoid_placement_new_aliasing (rval, placement_var);
+ return rval;
+ }
/* While we're working, use a pointer to the type we've actually
allocated. Store the result of the call in a variable so that we
@@ -2051,6 +2121,9 @@ build_new_1 (tree placement, tree type,
/* A new-expression is never an lvalue. */
gcc_assert (!lvalue_p (rval));
+ if (placement != NULL)
+ rval = avoid_placement_new_aliasing (rval, placement_var);
+
return rval;
}
Modified: projects/bhyve_svm/contrib/gcc/cp/method.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/cp/method.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/cp/method.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -407,10 +407,6 @@ use_thunk (tree thunk_fndecl, bool emit_
}
}
- /* The back-end expects DECL_INITIAL to contain a BLOCK, so we
- create one. */
- DECL_INITIAL (thunk_fndecl) = make_node (BLOCK);
-
/* Set up cloned argument trees for the thunk. */
t = NULL_TREE;
for (a = DECL_ARGUMENTS (function); a; a = TREE_CHAIN (a))
@@ -424,17 +420,23 @@ use_thunk (tree thunk_fndecl, bool emit_
}
a = nreverse (t);
DECL_ARGUMENTS (thunk_fndecl) = a;
- BLOCK_VARS (DECL_INITIAL (thunk_fndecl)) = a;
if (this_adjusting
&& targetm.asm_out.can_output_mi_thunk (thunk_fndecl, fixed_offset,
virtual_value, alias))
{
const char *fnname;
+ tree fn_block;
+
current_function_decl = thunk_fndecl;
DECL_RESULT (thunk_fndecl)
= build_decl (RESULT_DECL, 0, integer_type_node);
fnname = XSTR (XEXP (DECL_RTL (thunk_fndecl), 0), 0);
+ /* The back-end expects DECL_INITIAL to contain a BLOCK, so we
+ create one. */
+ fn_block = make_node (BLOCK);
+ BLOCK_VARS (fn_block) = a;
+ DECL_INITIAL (thunk_fndecl) = fn_block;
init_function_start (thunk_fndecl);
current_function_is_thunk = 1;
assemble_start_function (thunk_fndecl, fnname);
Modified: projects/bhyve_svm/contrib/gcc/cp/parser.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/cp/parser.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/cp/parser.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -15637,6 +15637,16 @@ cp_parser_function_definition_from_speci
cp_parser_skip_to_end_of_block_or_statement (parser);
fn = error_mark_node;
}
+ else if (DECL_INITIAL (current_function_decl) != error_mark_node)
+ {
+ /* Seen already, skip it. An error message has already been output. */
+ cp_parser_skip_to_end_of_block_or_statement (parser);
+ fn = current_function_decl;
+ current_function_decl = NULL_TREE;
+ /* If this is a function from a class, pop the nested class. */
+ if (current_class_name)
+ pop_nested_class ();
+ }
else
fn = cp_parser_function_definition_after_declarator (parser,
/*inline_p=*/false);
Modified: projects/bhyve_svm/contrib/gcc/doc/c-tree.texi
==============================================================================
--- projects/bhyve_svm/contrib/gcc/doc/c-tree.texi Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/doc/c-tree.texi Tue Feb 25 06:29:56 2014 (r262470)
@@ -1916,6 +1916,7 @@ This macro returns the attributes on the
@tindex TARGET_EXPR
@tindex AGGR_INIT_EXPR
@tindex VA_ARG_EXPR
+ at tindex CHANGE_DYNAMIC_TYPE_EXPR
@tindex OMP_PARALLEL
@tindex OMP_FOR
@tindex OMP_SECTIONS
@@ -2572,6 +2573,13 @@ mechanism. It represents expressions li
Its @code{TREE_TYPE} yields the tree representation for @code{type} and
its sole argument yields the representation for @code{ap}.
+ at item CHANGE_DYNAMIC_TYPE_EXPR
+Indicates the special aliasing required by C++ placement new. It has
+two operands: a type and a location. It means that the dynamic type
+of the location is changing to be the specified type. The alias
+analysis code takes this into account when doing type based alias
+analysis.
+
@item OMP_PARALLEL
Represents @code{#pragma omp parallel [clause1 ... clauseN]}. It
Modified: projects/bhyve_svm/contrib/gcc/doc/cppopts.texi
==============================================================================
--- projects/bhyve_svm/contrib/gcc/doc/cppopts.texi Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/doc/cppopts.texi Tue Feb 25 06:29:56 2014 (r262470)
@@ -645,6 +645,10 @@ touch foo.h; cpp -dM foo.h
@noindent
will show all the predefined macros.
+If you use @option{-dM} without the @option{-E} option, @option{-dM} is
+interpreted as a synonym for @option{-fdump-rtl-mach}.
+ at xref{Debugging Options, , ,gcc}.
+
@item D
@opindex dD
Like @samp{M} except in two respects: it does @emph{not} include the
Modified: projects/bhyve_svm/contrib/gcc/doc/invoke.texi
==============================================================================
--- projects/bhyve_svm/contrib/gcc/doc/invoke.texi Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/doc/invoke.texi Tue Feb 25 06:29:56 2014 (r262470)
@@ -169,6 +169,8 @@ in the following sections.
-trigraphs -no-integrated-cpp -traditional -traditional-cpp @gol
-fallow-single-precision -fcond-mismatch -flax-vector-conversions @gol
-fsigned-bitfields -fsigned-char @gol
+ at c APPLE LOCAL -Wnewline-eof 2001-08-23 --sts **
+-Wnewline-eof (Apple compatible) @gol
-funsigned-bitfields -funsigned-char}
@item C++ Language Options
@@ -2082,6 +2084,12 @@ Inhibit all warning messages.
@opindex Wno-import
Inhibit warning messages about the use of @samp{#import}.
+ at c APPLE LOCAL begin -Wnewline-eof 2001-08-23 --sts **
+ at item -Wnewline-eof
+ at opindex Wnewline-eof
+Warn about files missing a newline at the end of the file. (Apple compatible)
+ at c APPLE LOCAL end -Wnewline-eof 2001-08-23 --sts **
+
@item -Wchar-subscripts
@opindex Wchar-subscripts
Warn if an array subscript has type @code{char}. This is a common cause
@@ -3675,7 +3683,9 @@ Says to make debugging dumps during comp
compiler. The file names for most of the dumps are made by appending a
pass number and a word to the @var{dumpname}. @var{dumpname} is generated
from the name of the output file, if explicitly specified and it is not
-an executable, otherwise it is the basename of the source file.
+an executable, otherwise it is the basename of the source file. These
+switches may have different effects when @option{-E} is used for
+preprocessing.
Most debug dumps can be enabled either passing a letter to the @option{-d}
option, or with a long @option{-fdump-rtl} switch; here are the possible
@@ -3810,7 +3820,7 @@ Dump after modulo scheduling, to @file{@
@opindex dM
@opindex fdump-rtl-mach
Dump after performing the machine dependent reorganization pass, to
- at file{@var{file}.155r.mach}.
+ at file{@var{file}.155r.mach} if that pass exists.
@item -dn
@itemx -fdump-rtl-rnreg
Modified: projects/bhyve_svm/contrib/gcc/expr.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/expr.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/expr.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -8718,6 +8718,13 @@ expand_expr_real_1 (tree exp, rtx target
/* Lowered by gimplify.c. */
gcc_unreachable ();
+ case CHANGE_DYNAMIC_TYPE_EXPR:
+ /* This is ignored at the RTL level. The tree level set
+ DECL_POINTER_ALIAS_SET of any variable to be 0, which is
+ overkill for the RTL layer but is all that we can
+ represent. */
+ return const0_rtx;
+
case EXC_PTR_EXPR:
return get_exception_pointer (cfun);
Modified: projects/bhyve_svm/contrib/gcc/gimple-low.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/gimple-low.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/gimple-low.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -243,6 +243,7 @@ lower_stmt (tree_stmt_iterator *tsi, str
case GOTO_EXPR:
case LABEL_EXPR:
case SWITCH_EXPR:
+ case CHANGE_DYNAMIC_TYPE_EXPR:
case OMP_FOR:
case OMP_SECTIONS:
case OMP_SECTION:
Modified: projects/bhyve_svm/contrib/gcc/gimplify.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/gimplify.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/gimplify.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -5748,6 +5748,11 @@ gimplify_expr (tree *expr_p, tree *pre_p
ret = GS_ALL_DONE;
break;
+ case CHANGE_DYNAMIC_TYPE_EXPR:
+ ret = gimplify_expr (&CHANGE_DYNAMIC_TYPE_LOCATION (*expr_p),
+ pre_p, post_p, is_gimple_reg, fb_lvalue);
+ break;
+
case OBJ_TYPE_REF:
{
enum gimplify_status r0, r1;
Modified: projects/bhyve_svm/contrib/gcc/omp-low.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/omp-low.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/omp-low.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -518,6 +518,7 @@ omp_copy_decl_2 (tree var, tree name, tr
TREE_ADDRESSABLE (copy) = TREE_ADDRESSABLE (var);
DECL_COMPLEX_GIMPLE_REG_P (copy) = DECL_COMPLEX_GIMPLE_REG_P (var);
+ DECL_NO_TBAA_P (copy) = DECL_NO_TBAA_P (var);
DECL_ARTIFICIAL (copy) = DECL_ARTIFICIAL (var);
DECL_IGNORED_P (copy) = DECL_IGNORED_P (var);
TREE_USED (copy) = 1;
Modified: projects/bhyve_svm/contrib/gcc/print-tree.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/print-tree.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/print-tree.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -401,7 +401,9 @@ print_node (FILE *file, const char *pref
if (DECL_VIRTUAL_P (node))
fputs (" virtual", file);
if (DECL_PRESERVE_P (node))
- fputs (" preserve", file);
+ fputs (" preserve", file);
+ if (DECL_NO_TBAA_P (node))
+ fputs (" no-tbaa", file);
if (DECL_LANG_FLAG_0 (node))
fputs (" decl_0", file);
if (DECL_LANG_FLAG_1 (node))
Modified: projects/bhyve_svm/contrib/gcc/tree-gimple.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/tree-gimple.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/tree-gimple.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,5 +1,6 @@
/* Functions to analyze and validate GIMPLE trees.
- Copyright (C) 2002, 2003, 2004, 2005 Free Software Foundation, Inc.
+ Copyright (C) 2002, 2003, 2004, 2005, 2006, 2007
+ Free Software Foundation, Inc.
Contributed by Diego Novillo <dnovillo at redhat.com>
Rewritten by Jason Merrill <jason at redhat.com>
@@ -215,6 +216,7 @@ is_gimple_stmt (tree t)
case TRY_FINALLY_EXPR:
case EH_FILTER_EXPR:
case CATCH_EXPR:
+ case CHANGE_DYNAMIC_TYPE_EXPR:
case ASM_EXPR:
case RESX_EXPR:
case PHI_NODE:
Modified: projects/bhyve_svm/contrib/gcc/tree-inline.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/tree-inline.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/tree-inline.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -1649,6 +1649,11 @@ estimate_num_insns_1 (tree *tp, int *wal
*walk_subtrees = 0;
return NULL;
+ /* CHANGE_DYNAMIC_TYPE_EXPR explicitly expands to nothing. */
+ case CHANGE_DYNAMIC_TYPE_EXPR:
+ *walk_subtrees = 0;
+ return NULL;
+
/* Try to estimate the cost of assignments. We have three cases to
deal with:
1) Simple assignments to registers;
@@ -2635,6 +2640,7 @@ copy_decl_to_var (tree decl, copy_body_d
TREE_READONLY (copy) = TREE_READONLY (decl);
TREE_THIS_VOLATILE (copy) = TREE_THIS_VOLATILE (decl);
DECL_COMPLEX_GIMPLE_REG_P (copy) = DECL_COMPLEX_GIMPLE_REG_P (decl);
+ DECL_NO_TBAA_P (copy) = DECL_NO_TBAA_P (decl);
return copy_decl_for_dup_finish (id, decl, copy);
}
@@ -2661,6 +2667,7 @@ copy_result_decl_to_var (tree decl, copy
{
TREE_ADDRESSABLE (copy) = TREE_ADDRESSABLE (decl);
DECL_COMPLEX_GIMPLE_REG_P (copy) = DECL_COMPLEX_GIMPLE_REG_P (decl);
+ DECL_NO_TBAA_P (copy) = DECL_NO_TBAA_P (decl);
}
return copy_decl_for_dup_finish (id, decl, copy);
Modified: projects/bhyve_svm/contrib/gcc/tree-pretty-print.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/tree-pretty-print.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/tree-pretty-print.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -1443,6 +1443,17 @@ dump_generic_node (pretty_printer *buffe
is_expr = false;
break;
+ case CHANGE_DYNAMIC_TYPE_EXPR:
+ pp_string (buffer, "<<<change_dynamic_type (");
+ dump_generic_node (buffer, CHANGE_DYNAMIC_TYPE_NEW_TYPE (node), spc + 2,
+ flags, false);
+ pp_string (buffer, ") ");
+ dump_generic_node (buffer, CHANGE_DYNAMIC_TYPE_LOCATION (node), spc + 2,
+ flags, false);
+ pp_string (buffer, ")>>>");
+ is_expr = false;
+ break;
+
case LABEL_EXPR:
op0 = TREE_OPERAND (node, 0);
/* If this is for break or continue, don't bother printing it. */
Modified: projects/bhyve_svm/contrib/gcc/tree-ssa-alias.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/tree-ssa-alias.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/tree-ssa-alias.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,5 +1,5 @@
/* Alias analysis for trees.
- Copyright (C) 2004, 2005 Free Software Foundation, Inc.
+ Copyright (C) 2004, 2005, 2006, 2007 Free Software Foundation, Inc.
Contributed by Diego Novillo <dnovillo at redhat.com>
This file is part of GCC.
@@ -1961,28 +1961,29 @@ may_alias_p (tree ptr, HOST_WIDE_INT mem
gcc_assert (TREE_CODE (mem) == SYMBOL_MEMORY_TAG);
- alias_stats.tbaa_queries++;
-
- /* If the alias sets don't conflict then MEM cannot alias VAR. */
- if (!alias_sets_conflict_p (mem_alias_set, var_alias_set))
+ if (!DECL_NO_TBAA_P (ptr))
{
- alias_stats.alias_noalias++;
- alias_stats.tbaa_resolved++;
- return false;
- }
+ alias_stats.tbaa_queries++;
- /* If var is a record or union type, ptr cannot point into var
- unless there is some operation explicit address operation in the
- program that can reference a field of the ptr's dereferenced
- type. This also assumes that the types of both var and ptr are
- contained within the compilation unit, and that there is no fancy
- addressing arithmetic associated with any of the types
- involved. */
+ /* If the alias sets don't conflict then MEM cannot alias VAR. */
+ if (!alias_sets_conflict_p (mem_alias_set, var_alias_set))
+ {
+ alias_stats.alias_noalias++;
+ alias_stats.tbaa_resolved++;
+ return false;
+ }
- if ((mem_alias_set != 0) && (var_alias_set != 0))
- {
- tree ptr_type = TREE_TYPE (ptr);
- tree var_type = TREE_TYPE (var);
+ /* If VAR is a record or union type, PTR cannot point into VAR
+ unless there is some explicit address operation in the
+ program that can reference a field of the type pointed-to by
+ PTR. This also assumes that the types of both VAR and PTR
+ are contained within the compilation unit, and that there is
+ no fancy addressing arithmetic associated with any of the
+ types involved. */
+ if (mem_alias_set != 0 && var_alias_set != 0)
+ {
+ tree ptr_type = TREE_TYPE (ptr);
+ tree var_type = TREE_TYPE (var);
/* The star count is -1 if the type at the end of the pointer_to
chain is not a record or union type. */
@@ -1991,41 +1992,41 @@ may_alias_p (tree ptr, HOST_WIDE_INT mem
{
int ptr_star_count = 0;
- /* Ipa_type_escape_star_count_of_interesting_type is a little to
- restrictive for the pointer type, need to allow pointers to
- primitive types as long as those types cannot be pointers
- to everything. */
- while (POINTER_TYPE_P (ptr_type))
- /* Strip the *'s off. */
- {
- ptr_type = TREE_TYPE (ptr_type);
- ptr_star_count++;
- }
-
- /* There does not appear to be a better test to see if the
- pointer type was one of the pointer to everything
- types. */
+ /* ipa_type_escape_star_count_of_interesting_type is a
+ little too restrictive for the pointer type, need to
+ allow pointers to primitive types as long as those
+ types cannot be pointers to everything. */
+ while (POINTER_TYPE_P (ptr_type))
+ {
+ /* Strip the *s off. */
+ ptr_type = TREE_TYPE (ptr_type);
+ ptr_star_count++;
+ }
- if (ptr_star_count > 0)
- {
- alias_stats.structnoaddress_queries++;
- if (ipa_type_escape_field_does_not_clobber_p (var_type,
- TREE_TYPE (ptr)))
+ /* There does not appear to be a better test to see if
+ the pointer type was one of the pointer to everything
+ types. */
+ if (ptr_star_count > 0)
+ {
+ alias_stats.structnoaddress_queries++;
+ if (ipa_type_escape_field_does_not_clobber_p (var_type,
+ TREE_TYPE (ptr)))
+ {
+ alias_stats.structnoaddress_resolved++;
+ alias_stats.alias_noalias++;
+ return false;
+ }
+ }
+ else if (ptr_star_count == 0)
{
+ /* If PTR_TYPE was not really a pointer to type, it cannot
+ alias. */
+ alias_stats.structnoaddress_queries++;
alias_stats.structnoaddress_resolved++;
alias_stats.alias_noalias++;
return false;
}
}
- else if (ptr_star_count == 0)
- {
- /* If ptr_type was not really a pointer to type, it cannot
- alias. */
- alias_stats.structnoaddress_queries++;
- alias_stats.structnoaddress_resolved++;
- alias_stats.alias_noalias++;
- return false;
- }
}
}
Modified: projects/bhyve_svm/contrib/gcc/tree-ssa-dce.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/tree-ssa-dce.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/tree-ssa-dce.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -1,5 +1,6 @@
/* Dead code elimination pass for the GNU compiler.
- Copyright (C) 2002, 2003, 2004, 2005, 2006 Free Software Foundation, Inc.
+ Copyright (C) 2002, 2003, 2004, 2005, 2006, 2007
+ Free Software Foundation, Inc.
Contributed by Ben Elliston <bje at redhat.com>
and Andrew MacLeod <amacleod at redhat.com>
Adapted to use control dependence by Steven Bosscher, SUSE Labs.
@@ -307,6 +308,7 @@ mark_stmt_if_obviously_necessary (tree s
case ASM_EXPR:
case RESX_EXPR:
case RETURN_EXPR:
+ case CHANGE_DYNAMIC_TYPE_EXPR:
mark_stmt_necessary (stmt, true);
return;
Modified: projects/bhyve_svm/contrib/gcc/tree-ssa-operands.c
==============================================================================
--- projects/bhyve_svm/contrib/gcc/tree-ssa-operands.c Tue Feb 25 04:19:15 2014 (r262469)
+++ projects/bhyve_svm/contrib/gcc/tree-ssa-operands.c Tue Feb 25 06:29:56 2014 (r262470)
@@ -2057,6 +2057,10 @@ get_expr_operands (tree stmt, tree *expr
return;
*** DIFF OUTPUT TRUNCATED AT 1000 LINES ***
More information about the svn-src-projects
mailing list