Date: Tue, 25 Feb 2014 06:29:57 +0000 (UTC) From: Peter Grehan <grehan@FreeBSD.org> To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: 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... Message-ID: <201402250629.s1P6TvJI046855@svn.freebsd.org>
next in thread | raw e-mail | index | archive | help
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@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@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@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@google.com> (r125653) + Daniel Berlin <dberlin@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@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@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@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@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@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@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@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@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@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 +@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}. +@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}. +@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 +@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}. +@c APPLE LOCAL begin -Wnewline-eof 2001-08-23 --sts ** +@item -Wnewline-eof +@opindex Wnewline-eof +Warn about files missing a newline at the end of the file. (Apple compatible) +@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 -@file{@var{file}.155r.mach}. +@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@redhat.com> Rewritten by Jason Merrill <jason@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@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@redhat.com> and Andrew MacLeod <amacleod@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 ***
Want to link to this message? Use this URL: <https://mail-archive.FreeBSD.org/cgi/mid.cgi?201402250629.s1P6TvJI046855>