From owner-svn-src-projects@freebsd.org Sun Aug 25 20:36:02 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id CF344C21E4 for ; Sun, 25 Aug 2019 20:36:02 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46Gn364pytz4R3t; Sun, 25 Aug 2019 20:36:02 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id 8325A2309D; Sun, 25 Aug 2019 20:36:02 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7PKa22M070479; Sun, 25 Aug 2019 20:36:02 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7PKa2Vx070478; Sun, 25 Aug 2019 20:36:02 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908252036.x7PKa2Vx070478@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Sun, 25 Aug 2019 20:36:02 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351492 - projects/clang900-import/contrib/llvm/tools/lldb/utils X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: projects/clang900-import/contrib/llvm/tools/lldb/utils X-SVN-Commit-Revision: 351492 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 25 Aug 2019 20:36:02 -0000 Author: dim Date: Sun Aug 25 20:36:02 2019 New Revision: 351492 URL: https://svnweb.freebsd.org/changeset/base/351492 Log: Merge missed sources for lldb-specific TableGen tool. Added: projects/clang900-import/contrib/llvm/tools/lldb/utils/ - copied from r351491, vendor/lldb/dist/utils/ Modified: Directory Properties: projects/clang900-import/contrib/llvm/tools/lldb/ (props changed) From owner-svn-src-projects@freebsd.org Sun Aug 25 20:36:53 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id 39D8DC24DD for ; Sun, 25 Aug 2019 20:36:53 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46Gn446cq9z4RFh; Sun, 25 Aug 2019 20:36:52 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id C27FD230A2; Sun, 25 Aug 2019 20:36:52 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7PKaqfb070562; Sun, 25 Aug 2019 20:36:52 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7PKaquZ070561; Sun, 25 Aug 2019 20:36:52 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908252036.x7PKaquZ070561@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Sun, 25 Aug 2019 20:36:52 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351493 - projects/clang900-import/contrib/llvm/tools/lldb X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: projects/clang900-import/contrib/llvm/tools/lldb X-SVN-Commit-Revision: 351493 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 25 Aug 2019 20:36:53 -0000 Author: dim Date: Sun Aug 25 20:36:52 2019 New Revision: 351493 URL: https://svnweb.freebsd.org/changeset/base/351493 Log: Update FREEBSD-Xlist for lldb. Modified: projects/clang900-import/contrib/llvm/tools/lldb/FREEBSD-Xlist Modified: projects/clang900-import/contrib/llvm/tools/lldb/FREEBSD-Xlist ============================================================================== --- projects/clang900-import/contrib/llvm/tools/lldb/FREEBSD-Xlist Sun Aug 25 20:36:02 2019 (r351492) +++ projects/clang900-import/contrib/llvm/tools/lldb/FREEBSD-Xlist Sun Aug 25 20:36:52 2019 (r351493) @@ -9,14 +9,9 @@ cmake/ docs/.htaccess docs/CMakeLists.txt docs/_static/ -docs/building-with-debug-llvm.txt -docs/code-signing.txt docs/conf.py docs/doxygen-mainpage.dox docs/doxygen.cfg.in -docs/doxygen.footer -docs/doxygen.header -docs/doxygen.intro docs/index.rst docs/lldb-for-gdb-users.txt docs/lldb-gdb-remote.txt @@ -125,7 +120,6 @@ source/Plugins/OperatingSystem/Python/CMakeLists.txt source/Plugins/Platform/Android/ source/Plugins/Platform/CMakeLists.txt source/Plugins/Platform/FreeBSD/CMakeLists.txt -source/Plugins/Platform/Kalimba/ source/Plugins/Platform/Linux/ source/Plugins/Platform/MacOSX/ source/Plugins/Platform/NetBSD/CMakeLists.txt @@ -175,7 +169,6 @@ tools/darwin-threads/ tools/debugserver/ tools/driver/CMakeLists.txt tools/driver/lldb-Info.plist -tools/install-headers/ tools/intel-features/ tools/lldb-instr/CMakeLists.txt tools/lldb-mi/CMakeLists.txt @@ -186,5 +179,12 @@ tools/lldb-test/ tools/lldb-vscode/ unittests/ use_lldb_suite_root.py -utils/ -www/ +utils/TableGen/CMakeLists.txt +utils/git-svn/ +utils/lit-cpuid/ +utils/lldb-dotest/ +utils/lui/ +utils/misc/ +utils/sync-source/ +utils/test/ +utils/vim-lldb/ From owner-svn-src-projects@freebsd.org Mon Aug 26 20:56:16 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id DD179E5146 for ; Mon, 26 Aug 2019 20:56:16 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46HPS05VVFz3QFs; Mon, 26 Aug 2019 20:56:16 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id 9F971C09F; Mon, 26 Aug 2019 20:56:16 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7QKuGbN044908; Mon, 26 Aug 2019 20:56:16 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7QKuGTI044907; Mon, 26 Aug 2019 20:56:16 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908262056.x7QKuGTI044907@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Mon, 26 Aug 2019 20:56:16 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351519 - projects/clang900-import/contrib/llvm/tools/lldb/source/API X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: projects/clang900-import/contrib/llvm/tools/lldb/source/API X-SVN-Commit-Revision: 351519 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 26 Aug 2019 20:56:16 -0000 Author: dim Date: Mon Aug 26 20:56:16 2019 New Revision: 351519 URL: https://svnweb.freebsd.org/changeset/base/351519 Log: Disable UniversalMachO support in lldb's SystemInitializerFull.cpp, since we do not need it. Modified: projects/clang900-import/contrib/llvm/tools/lldb/source/API/SystemInitializerFull.cpp Modified: projects/clang900-import/contrib/llvm/tools/lldb/source/API/SystemInitializerFull.cpp ============================================================================== --- projects/clang900-import/contrib/llvm/tools/lldb/source/API/SystemInitializerFull.cpp Mon Aug 26 20:20:10 2019 (r351518) +++ projects/clang900-import/contrib/llvm/tools/lldb/source/API/SystemInitializerFull.cpp Mon Aug 26 20:56:16 2019 (r351519) @@ -81,7 +81,9 @@ #endif // LLDB_ENABLE_ALL #include "Plugins/MemoryHistory/asan/MemoryHistoryASan.h" #include "Plugins/ObjectContainer/BSD-Archive/ObjectContainerBSDArchive.h" +#ifdef LLDB_ENABLE_ALL #include "Plugins/ObjectContainer/Universal-Mach-O/ObjectContainerUniversalMachO.h" +#endif // LLDB_ENABLE_ALL #include "Plugins/ObjectFile/Breakpad/ObjectFileBreakpad.h" #include "Plugins/ObjectFile/ELF/ObjectFileELF.h" #ifdef LLDB_ENABLE_ALL @@ -173,7 +175,9 @@ llvm::Error SystemInitializerFull::Initialize() { #endif // LLDB_ENABLE_ALL ObjectContainerBSDArchive::Initialize(); +#ifdef LLDB_ENABLE_ALL ObjectContainerUniversalMachO::Initialize(); +#endif // LLDB_ENABLE_ALL ScriptInterpreterNone::Initialize(); @@ -467,7 +471,9 @@ void SystemInitializerFull::Terminate() { #endif // LLDB_ENABLE_ALL ObjectContainerBSDArchive::Terminate(); +#ifdef LLDB_ENABLE_ALL ObjectContainerUniversalMachO::Terminate(); +#endif // LLDB_ENABLE_ALL // Now shutdown the common parts, in reverse order. SystemInitializerCommon::Terminate(); From owner-svn-src-projects@freebsd.org Mon Aug 26 20:57:46 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id 62768E5176 for ; Mon, 26 Aug 2019 20:57:46 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46HPTk1wFNz3QLV; Mon, 26 Aug 2019 20:57:46 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id 23AC7C0A0; Mon, 26 Aug 2019 20:57:46 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7QKvkSN045013; Mon, 26 Aug 2019 20:57:46 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7QKvjPC045011; Mon, 26 Aug 2019 20:57:45 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908262057.x7QKvjPC045011@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Mon, 26 Aug 2019 20:57:45 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351520 - in projects/clang900-import/usr.bin/clang: . lldb-tblgen X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: in projects/clang900-import/usr.bin/clang: . lldb-tblgen X-SVN-Commit-Revision: 351520 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 26 Aug 2019 20:57:46 -0000 Author: dim Date: Mon Aug 26 20:57:45 2019 New Revision: 351520 URL: https://svnweb.freebsd.org/changeset/base/351520 Log: Add lldb-tblgen tool. Added: projects/clang900-import/usr.bin/clang/lldb-tblgen/ projects/clang900-import/usr.bin/clang/lldb-tblgen/Makefile (contents, props changed) Modified: projects/clang900-import/usr.bin/clang/Makefile projects/clang900-import/usr.bin/clang/llvm.prog.mk Modified: projects/clang900-import/usr.bin/clang/Makefile ============================================================================== --- projects/clang900-import/usr.bin/clang/Makefile Mon Aug 26 20:56:16 2019 (r351519) +++ projects/clang900-import/usr.bin/clang/Makefile Mon Aug 26 20:57:45 2019 (r351520) @@ -6,6 +6,10 @@ SUBDIR+= clang SUBDIR+= clang-tblgen SUBDIR+= llvm-tblgen +.if ${MK_LLDB} != "no" +SUBDIR+= lldb-tblgen +.endif + .if !defined(TOOLS_PREFIX) SUBDIR+= llvm-ar SUBDIR+= llvm-nm Added: projects/clang900-import/usr.bin/clang/lldb-tblgen/Makefile ============================================================================== --- /dev/null 00:00:00 1970 (empty, because file is newly added) +++ projects/clang900-import/usr.bin/clang/lldb-tblgen/Makefile Mon Aug 26 20:57:45 2019 (r351520) @@ -0,0 +1,10 @@ +# $FreeBSD$ + +PROG_CXX= lldb-tblgen +MAN= + +SRCDIR= tools/lldb/utils/TableGen +SRCS+= LLDBOptionDefEmitter.cpp +SRCS+= LLDBTableGen.cpp + +.include "../llvm.prog.mk" Modified: projects/clang900-import/usr.bin/clang/llvm.prog.mk ============================================================================== --- projects/clang900-import/usr.bin/clang/llvm.prog.mk Mon Aug 26 20:56:16 2019 (r351519) +++ projects/clang900-import/usr.bin/clang/llvm.prog.mk Mon Aug 26 20:57:45 2019 (r351520) @@ -8,7 +8,8 @@ CFLAGS+= -I${OBJTOP}/lib/clang/libllvm # Special case for the bootstrap-tools phase. .if (defined(TOOLS_PREFIX) || ${MACHINE} == "host") && \ - (${PROG_CXX} == "clang-tblgen" || ${PROG_CXX} == "llvm-tblgen") + (${PROG_CXX} == "clang-tblgen" || ${PROG_CXX} == "lldb-tblgen" || \ + ${PROG_CXX} == "llvm-tblgen") LIBDEPS+= llvmminimal .else LIBDEPS+= llvm From owner-svn-src-projects@freebsd.org Mon Aug 26 21:00:15 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id 64B34E52AB for ; Mon, 26 Aug 2019 21:00:15 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46HPXb1nsNz3QZh; Mon, 26 Aug 2019 21:00:15 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id 1FC5CC0BD; Mon, 26 Aug 2019 21:00:15 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7QL0FVO045228; Mon, 26 Aug 2019 21:00:15 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7QL0El5045225; Mon, 26 Aug 2019 21:00:14 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908262100.x7QL0El5045225@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Mon, 26 Aug 2019 21:00:14 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351521 - in projects/clang900-import: . lib/clang/liblldb usr.bin/clang/lldb X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: in projects/clang900-import: . lib/clang/liblldb usr.bin/clang/lldb X-SVN-Commit-Revision: 351521 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 26 Aug 2019 21:00:15 -0000 Author: dim Date: Mon Aug 26 21:00:14 2019 New Revision: 351521 URL: https://svnweb.freebsd.org/changeset/base/351521 Log: Update build glue for a build of clang plus lldb (enabled via MK_LLDB). Modified: projects/clang900-import/Makefile.inc1 projects/clang900-import/lib/clang/liblldb/Makefile projects/clang900-import/usr.bin/clang/lldb/Makefile Modified: projects/clang900-import/Makefile.inc1 ============================================================================== --- projects/clang900-import/Makefile.inc1 Mon Aug 26 20:57:45 2019 (r351520) +++ projects/clang900-import/Makefile.inc1 Mon Aug 26 21:00:14 2019 (r351521) @@ -2182,6 +2182,10 @@ _clang_tblgen= \ lib/clang/libllvmminimal \ usr.bin/clang/llvm-tblgen \ usr.bin/clang/clang-tblgen +.if ${MK_LLDB} != "no" +_clang_tblgen+= \ + usr.bin/clang/lldb-tblgen +.endif ${_bt}-usr.bin/clang/clang-tblgen: ${_bt}-lib/clang/libllvmminimal ${_bt}-usr.bin/clang/llvm-tblgen: ${_bt}-lib/clang/libllvmminimal Modified: projects/clang900-import/lib/clang/liblldb/Makefile ============================================================================== --- projects/clang900-import/lib/clang/liblldb/Makefile Mon Aug 26 20:57:45 2019 (r351520) +++ projects/clang900-import/lib/clang/liblldb/Makefile Mon Aug 26 21:00:14 2019 (r351521) @@ -12,6 +12,7 @@ CFLAGS+= -I${LLDB_SRCS}/source/Plugins/Process/POSIX CFLAGS+= -I${LLDB_SRCS}/source/Plugins/Process/Utility CFLAGS+= -I${OBJTOP}/lib/clang/libllvm CFLAGS+= -I${OBJTOP}/lib/clang/libclang +CFLAGS+= -I${OBJTOP}/lib/clang/liblldb CFLAGS+= -DLLDB_DISABLE_PYTHON SRCS+= API/SBAddress.cpp @@ -19,10 +20,12 @@ SRCS+= API/SBAttachInfo.cpp SRCS+= API/SBBlock.cpp SRCS+= API/SBBreakpoint.cpp SRCS+= API/SBBreakpointLocation.cpp +SRCS+= API/SBBreakpointName.cpp SRCS+= API/SBBreakpointOptionCommon.cpp SRCS+= API/SBBroadcaster.cpp SRCS+= API/SBCommandInterpreter.cpp SRCS+= API/SBCommandReturnObject.cpp +SRCS+= API/SBCommunication.cpp SRCS+= API/SBCompileUnit.cpp SRCS+= API/SBData.cpp SRCS+= API/SBDebugger.cpp @@ -36,7 +39,6 @@ SRCS+= API/SBFileSpecList.cpp SRCS+= API/SBFrame.cpp SRCS+= API/SBFunction.cpp SRCS+= API/SBHostOS.cpp -SRCS+= API/SBInitializerOptions.cpp SRCS+= API/SBInstruction.cpp SRCS+= API/SBInstructionList.cpp SRCS+= API/SBLanguageRuntime.cpp @@ -52,6 +54,7 @@ SRCS+= API/SBProcess.cpp SRCS+= API/SBProcessInfo.cpp SRCS+= API/SBQueue.cpp SRCS+= API/SBQueueItem.cpp +SRCS+= API/SBReproducer.cpp SRCS+= API/SBSection.cpp SRCS+= API/SBSourceManager.cpp SRCS+= API/SBStream.cpp @@ -65,6 +68,7 @@ SRCS+= API/SBThread.cpp SRCS+= API/SBThreadCollection.cpp SRCS+= API/SBThreadPlan.cpp SRCS+= API/SBTrace.cpp +SRCS+= API/SBTraceOptions.cpp SRCS+= API/SBType.cpp SRCS+= API/SBTypeCategory.cpp SRCS+= API/SBTypeEnumMember.cpp @@ -72,6 +76,7 @@ SRCS+= API/SBTypeFilter.cpp SRCS+= API/SBTypeFormat.cpp SRCS+= API/SBTypeNameSpecifier.cpp SRCS+= API/SBTypeSummary.cpp +SRCS+= API/SBTypeSynthetic.cpp SRCS+= API/SBUnixSignals.cpp SRCS+= API/SBValue.cpp SRCS+= API/SBValueList.cpp @@ -194,10 +199,8 @@ SRCS+= DataFormatters/VectorType.cpp SRCS+= Expression/DWARFExpression.cpp SRCS+= Expression/DiagnosticManager.cpp SRCS+= Expression/Expression.cpp -SRCS+= Expression/ExpressionSourceCode.cpp SRCS+= Expression/ExpressionVariable.cpp SRCS+= Expression/FunctionCaller.cpp -SRCS+= Expression/IRDynamicChecks.cpp SRCS+= Expression/IRExecutionUnit.cpp SRCS+= Expression/IRInterpreter.cpp SRCS+= Expression/IRMemoryMap.cpp @@ -208,6 +211,7 @@ SRCS+= Expression/UserExpression.cpp SRCS+= Expression/UtilityFunction.cpp SRCS+= Host/common/Editline.cpp SRCS+= Host/common/File.cpp +SRCS+= Host/common/FileAction.cpp SRCS+= Host/common/FileCache.cpp SRCS+= Host/common/FileSystem.cpp SRCS+= Host/common/Host.cpp @@ -221,12 +225,12 @@ SRCS+= Host/common/MonitoringProcessLauncher.cpp SRCS+= Host/common/NativeWatchpointList.cpp SRCS+= Host/common/OptionParser.cpp SRCS+= Host/common/PipeBase.cpp +SRCS+= Host/common/ProcessLaunchInfo.cpp SRCS+= Host/common/ProcessRunLock.cpp SRCS+= Host/common/PseudoTerminal.cpp SRCS+= Host/common/Socket.cpp SRCS+= Host/common/SocketAddress.cpp SRCS+= Host/common/StringConvert.cpp -SRCS+= Host/common/Symbols.cpp SRCS+= Host/common/TCPSocket.cpp SRCS+= Host/common/TaskPool.cpp SRCS+= Host/common/Terminal.cpp @@ -302,16 +306,17 @@ SRCS+= Plugins/Architecture/Arm/ArchitectureArm.cpp SRCS+= Plugins/Architecture/Mips/ArchitectureMips.cpp SRCS+= Plugins/Architecture/PPC64/ArchitecturePPC64.cpp SRCS+= Plugins/Disassembler/llvm/DisassemblerLLVMC.cpp -SRCS+= Plugins/DynamicLoader/POSIX-DYLD/AuxVector.cpp SRCS+= Plugins/DynamicLoader/POSIX-DYLD/DYLDRendezvous.cpp SRCS+= Plugins/DynamicLoader/POSIX-DYLD/DynamicLoaderPOSIXDYLD.cpp SRCS+= Plugins/DynamicLoader/Static/DynamicLoaderStatic.cpp SRCS+= Plugins/ExpressionParser/Clang/ASTDumper.cpp SRCS+= Plugins/ExpressionParser/Clang/ASTResultSynthesizer.cpp SRCS+= Plugins/ExpressionParser/Clang/ASTStructExtractor.cpp +SRCS+= Plugins/ExpressionParser/Clang/ASTUtils.cpp SRCS+= Plugins/ExpressionParser/Clang/ClangASTSource.cpp SRCS+= Plugins/ExpressionParser/Clang/ClangExpressionDeclMap.cpp SRCS+= Plugins/ExpressionParser/Clang/ClangExpressionParser.cpp +SRCS+= Plugins/ExpressionParser/Clang/ClangExpressionSourceCode.cpp SRCS+= Plugins/ExpressionParser/Clang/ClangExpressionVariable.cpp SRCS+= Plugins/ExpressionParser/Clang/ClangFunctionCaller.cpp SRCS+= Plugins/ExpressionParser/Clang/ClangHost.cpp @@ -319,6 +324,7 @@ SRCS+= Plugins/ExpressionParser/Clang/ClangModulesDec SRCS+= Plugins/ExpressionParser/Clang/ClangPersistentVariables.cpp SRCS+= Plugins/ExpressionParser/Clang/ClangUserExpression.cpp SRCS+= Plugins/ExpressionParser/Clang/ClangUtilityFunction.cpp +SRCS+= Plugins/ExpressionParser/Clang/IRDynamicChecks.cpp SRCS+= Plugins/ExpressionParser/Clang/IRForTarget.cpp SRCS+= Plugins/Instruction/ARM/EmulateInstructionARM.cpp SRCS+= Plugins/Instruction/ARM/EmulationStateARM.cpp @@ -333,14 +339,22 @@ SRCS+= Plugins/JITLoader/GDB/JITLoaderGDB.cpp SRCS+= Plugins/Language/CPlusPlus/BlockPointer.cpp SRCS+= Plugins/Language/CPlusPlus/CPlusPlusLanguage.cpp SRCS+= Plugins/Language/CPlusPlus/CPlusPlusNameParser.cpp +SRCS+= Plugins/Language/CPlusPlus/CxxStringTypes.cpp SRCS+= Plugins/Language/CPlusPlus/LibCxx.cpp SRCS+= Plugins/Language/CPlusPlus/LibCxxAtomic.cpp +SRCS+= Plugins/Language/CPlusPlus/LibCxxBitset.cpp SRCS+= Plugins/Language/CPlusPlus/LibCxxInitializerList.cpp SRCS+= Plugins/Language/CPlusPlus/LibCxxList.cpp SRCS+= Plugins/Language/CPlusPlus/LibCxxMap.cpp +SRCS+= Plugins/Language/CPlusPlus/LibCxxOptional.cpp +SRCS+= Plugins/Language/CPlusPlus/LibCxxQueue.cpp +SRCS+= Plugins/Language/CPlusPlus/LibCxxTuple.cpp SRCS+= Plugins/Language/CPlusPlus/LibCxxUnorderedMap.cpp +SRCS+= Plugins/Language/CPlusPlus/LibCxxVariant.cpp SRCS+= Plugins/Language/CPlusPlus/LibCxxVector.cpp SRCS+= Plugins/Language/CPlusPlus/LibStdcpp.cpp +SRCS+= Plugins/Language/CPlusPlus/LibStdcppTuple.cpp +SRCS+= Plugins/Language/CPlusPlus/LibStdcppUniquePointer.cpp SRCS+= Plugins/Language/CPlusPlus/MSVCUndecoratedNameParser.cpp SRCS+= Plugins/Language/ClangCommon/ClangHighlighter.cpp SRCS+= Plugins/Language/ObjC/CF.cpp @@ -354,11 +368,14 @@ SRCS+= Plugins/Language/ObjC/NSSet.cpp SRCS+= Plugins/Language/ObjC/NSString.cpp SRCS+= Plugins/Language/ObjC/ObjCLanguage.cpp SRCS+= Plugins/LanguageRuntime/CPlusPlus/ItaniumABI/ItaniumABILanguageRuntime.cpp +SRCS+= Plugins/LanguageRuntime/CPlusPlus/CPPLanguageRuntime.cpp SRCS+= Plugins/LanguageRuntime/ObjC/AppleObjCRuntime/AppleObjCRuntime.cpp SRCS+= Plugins/LanguageRuntime/ObjC/AppleObjCRuntime/AppleObjCTrampolineHandler.cpp SRCS+= Plugins/LanguageRuntime/ObjC/AppleObjCRuntime/AppleThreadPlanStepThroughObjCTrampoline.cpp +SRCS+= Plugins/LanguageRuntime/ObjC/ObjCLanguageRuntime.cpp SRCS+= Plugins/MemoryHistory/asan/MemoryHistoryASan.cpp SRCS+= Plugins/ObjectContainer/BSD-Archive/ObjectContainerBSDArchive.cpp +SRCS+= Plugins/ObjectFile/Breakpad/BreakpadRecords.cpp SRCS+= Plugins/ObjectFile/Breakpad/ObjectFileBreakpad.cpp SRCS+= Plugins/ObjectFile/ELF/ELFHeader.cpp SRCS+= Plugins/ObjectFile/ELF/ObjectFileELF.cpp @@ -378,6 +395,7 @@ SRCS+= Plugins/Process/FreeBSD/RegisterContextPOSIXPr SRCS+= Plugins/Process/POSIX/CrashReason.cpp SRCS+= Plugins/Process/POSIX/ProcessMessage.cpp SRCS+= Plugins/Process/POSIX/ProcessPOSIXLog.cpp +SRCS+= Plugins/Process/Utility/AuxVector.cpp SRCS+= Plugins/Process/Utility/DynamicRegisterInfo.cpp SRCS+= Plugins/Process/Utility/FreeBSDSignals.cpp SRCS+= Plugins/Process/Utility/GDBRemoteSignals.cpp @@ -451,8 +469,8 @@ SRCS+= Plugins/SymbolFile/DWARF/DWARFAbbreviationDecl SRCS+= Plugins/SymbolFile/DWARF/DWARFAttribute.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFBaseDIE.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFCompileUnit.cpp +SRCS+= Plugins/SymbolFile/DWARF/DWARFContext.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFDIE.cpp -SRCS+= Plugins/SymbolFile/DWARF/DWARFDIECollection.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFDataExtractor.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFDebugAbbrev.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFDebugArangeSet.cpp @@ -466,6 +484,7 @@ SRCS+= Plugins/SymbolFile/DWARF/DWARFDeclContext.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFDefines.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFFormValue.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFIndex.cpp +SRCS+= Plugins/SymbolFile/DWARF/DWARFTypeUnit.cpp SRCS+= Plugins/SymbolFile/DWARF/DWARFUnit.cpp SRCS+= Plugins/SymbolFile/DWARF/HashedNameToDIE.cpp SRCS+= Plugins/SymbolFile/DWARF/LogChannelDWARF.cpp @@ -494,14 +513,18 @@ SRCS+= Symbol/CompileUnit.cpp SRCS+= Symbol/CompilerDecl.cpp SRCS+= Symbol/CompilerDeclContext.cpp SRCS+= Symbol/CompilerType.cpp +SRCS+= Symbol/CxxModuleHandler.cpp SRCS+= Symbol/DWARFCallFrameInfo.cpp SRCS+= Symbol/DebugMacros.cpp +SRCS+= Symbol/DeclVendor.cpp SRCS+= Symbol/Declaration.cpp SRCS+= Symbol/FuncUnwinders.cpp SRCS+= Symbol/Function.cpp SRCS+= Symbol/LineEntry.cpp SRCS+= Symbol/LineTable.cpp +SRCS+= Symbol/LocateSymbolFile.cpp SRCS+= Symbol/ObjectFile.cpp +SRCS+= Symbol/PostfixExpression.cpp SRCS+= Symbol/Symbol.cpp SRCS+= Symbol/SymbolContext.cpp SRCS+= Symbol/SymbolFile.cpp @@ -516,9 +539,7 @@ SRCS+= Symbol/UnwindTable.cpp SRCS+= Symbol/Variable.cpp SRCS+= Symbol/VariableList.cpp SRCS+= Target/ABI.cpp -SRCS+= Target/CPPLanguageRuntime.cpp SRCS+= Target/ExecutionContext.cpp -SRCS+= Target/FileAction.cpp SRCS+= Target/InstrumentationRuntime.cpp SRCS+= Target/InstrumentationRuntimeStopInfo.cpp SRCS+= Target/JITLoader.cpp @@ -528,18 +549,16 @@ SRCS+= Target/LanguageRuntime.cpp SRCS+= Target/Memory.cpp SRCS+= Target/MemoryHistory.cpp SRCS+= Target/ModuleCache.cpp -SRCS+= Target/ObjCLanguageRuntime.cpp SRCS+= Target/OperatingSystem.cpp SRCS+= Target/PathMappingList.cpp SRCS+= Target/Platform.cpp SRCS+= Target/Process.cpp -SRCS+= Target/ProcessInfo.cpp -SRCS+= Target/ProcessLaunchInfo.cpp SRCS+= Target/Queue.cpp SRCS+= Target/QueueItem.cpp SRCS+= Target/QueueList.cpp SRCS+= Target/RegisterContext.cpp SRCS+= Target/RegisterNumber.cpp +SRCS+= Target/RemoteAwarePlatform.cpp SRCS+= Target/SectionLoadHistory.cpp SRCS+= Target/SectionLoadList.cpp SRCS+= Target/StackFrame.cpp @@ -586,6 +605,7 @@ SRCS+= Utility/DataEncoder.cpp SRCS+= Utility/DataExtractor.cpp SRCS+= Utility/Environment.cpp SRCS+= Utility/Event.cpp +SRCS+= Utility/FileCollector.cpp SRCS+= Utility/FileSpec.cpp SRCS+= Utility/IOObject.cpp SRCS+= Utility/JSON.cpp @@ -594,9 +614,11 @@ SRCS+= Utility/Listener.cpp SRCS+= Utility/Log.cpp SRCS+= Utility/Logging.cpp SRCS+= Utility/NameMatches.cpp +SRCS+= Utility/ProcessInfo.cpp SRCS+= Utility/RegisterValue.cpp SRCS+= Utility/RegularExpression.cpp SRCS+= Utility/Reproducer.cpp +SRCS+= Utility/ReproducerInstrumentation.cpp SRCS+= Utility/Scalar.cpp SRCS+= Utility/SelectHelper.cpp SRCS+= Utility/SharingPtr.cpp @@ -616,9 +638,22 @@ SRCS+= Utility/Timer.cpp SRCS+= Utility/UUID.cpp SRCS+= Utility/UriParser.cpp SRCS+= Utility/UserID.cpp +SRCS+= Utility/UserIDResolver.cpp SRCS+= Utility/VASprintf.cpp SRCS+= Utility/VMRange.cpp SRCS+= lldb.cpp + +LLDB_TBLGEN?= lldb-tblgen +INCFILE= CommandOptions.inc +TDFILE= ${LLDB_SRCS}/source/Commands/Options.td +GENOPT= -gen-lldb-option-defs +${INCFILE}: ${TDFILE} + ${LLDB_TBLGEN} ${GENOPT} -I ${LLDB_SRCS}/source/Commands \ + -d ${.TARGET:C/$/.d/} -o ${.TARGET} ${TDFILE} +TGHDRS+= ${INCFILE} + +DPSRCS+= ${TGHDRS} +CLEANFILES+= ${TGHDRS} ${TGHDRS:C/$/.d/} .include "../clang.build.mk" Modified: projects/clang900-import/usr.bin/clang/lldb/Makefile ============================================================================== --- projects/clang900-import/usr.bin/clang/lldb/Makefile Mon Aug 26 20:57:45 2019 (r351520) +++ projects/clang900-import/usr.bin/clang/lldb/Makefile Mon Aug 26 21:00:14 2019 (r351521) @@ -37,6 +37,7 @@ DPSRCS+= ${TGHDRS} CLEANFILES+= ${TGHDRS} ${TGHDRS:C/$/.d/} LIBADD+= edit +LIBADD+= execinfo LIBADD+= panel LIBADD+= ncursesw LIBADD+= pthread From owner-svn-src-projects@freebsd.org Tue Aug 27 01:40:40 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id 109A3C40E4 for ; Tue, 27 Aug 2019 01:40:40 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46HWm76dBsz4BHW; Tue, 27 Aug 2019 01:40:39 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id 8B89DF56E; Tue, 27 Aug 2019 01:40:39 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7R1edtj011074; Tue, 27 Aug 2019 01:40:39 GMT (envelope-from rmacklem@FreeBSD.org) Received: (from rmacklem@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7R1edvC010782; Tue, 27 Aug 2019 01:40:39 GMT (envelope-from rmacklem@FreeBSD.org) Message-Id: <201908270140.x7R1edvC010782@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: rmacklem set sender to rmacklem@FreeBSD.org using -f From: Rick Macklem Date: Tue, 27 Aug 2019 01:40:39 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351525 - projects/nfsv42/sys/fs/nfsclient X-SVN-Group: projects X-SVN-Commit-Author: rmacklem X-SVN-Commit-Paths: projects/nfsv42/sys/fs/nfsclient X-SVN-Commit-Revision: 351525 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 27 Aug 2019 01:40:40 -0000 Author: rmacklem Date: Tue Aug 27 01:40:38 2019 New Revision: 351525 URL: https://svnweb.freebsd.org/changeset/base/351525 Log: Add support for _PC_MIN_HOLE_SIZE to the NFSv4.2 client. Unfortunately there is no NFSv4.2 attribute for this, so all I could come up with was to try Seek to see if it supported and, if it is, return mnt_stat.f_iosize as a "best guess". At least this allows applications to use hole size non-zero to indicate support for holes. Modified: projects/nfsv42/sys/fs/nfsclient/nfs_clvnops.c projects/nfsv42/sys/fs/nfsclient/nfsmount.h Modified: projects/nfsv42/sys/fs/nfsclient/nfs_clvnops.c ============================================================================== --- projects/nfsv42/sys/fs/nfsclient/nfs_clvnops.c Tue Aug 27 01:16:02 2019 (r351524) +++ projects/nfsv42/sys/fs/nfsclient/nfs_clvnops.c Tue Aug 27 01:40:38 2019 (r351525) @@ -3754,7 +3754,10 @@ nfs_pathconf(struct vop_pathconf_args *ap) struct nfsv3_pathconf pc; struct nfsvattr nfsva; struct vnode *vp = ap->a_vp; + struct nfsmount *nmp; struct thread *td = curthread; + off_t off; + bool eof; int attrflag, error; if ((NFS_ISV34(vp) && (ap->a_name == _PC_LINK_MAX || @@ -3852,6 +3855,40 @@ nfs_pathconf(struct vop_pathconf_args *ap) break; case _PC_SYMLINK_MAX: *ap->a_retval = NFS_MAXPATHLEN; + break; + case _PC_MIN_HOLE_SIZE: + /* Only some NFSv4.2 servers support Seek for Holes. */ + *ap->a_retval = 0; + nmp = VFSTONFS(vp->v_mount); + if (NFS_ISV4(vp) && nmp->nm_minorvers == NFSV42_MINORVERSION) { + /* + * NFSv4.2 doesn't have an attribute for hole size, + * so all we can do is see if the Seek operation is + * supported and then use f_iosize as a "best guess". + */ + mtx_lock(&nmp->nm_mtx); + if ((nmp->nm_privflag & NFSMNTP_SEEKTESTED) == 0) { + mtx_unlock(&nmp->nm_mtx); + off = 0; + attrflag = 0; + error = nfsrpc_seek(vp, &off, &eof, + NFSV4CONTENT_HOLE, td->td_ucred, &nfsva, + &attrflag); + if (attrflag != 0) + nfscl_loadattrcache(&vp, &nfsva, + NULL, NULL, 0, 1); + mtx_lock(&nmp->nm_mtx); + if (error == NFSERR_NOTSUPP) + nmp->nm_privflag |= NFSMNTP_SEEKTESTED; + else + nmp->nm_privflag |= NFSMNTP_SEEKTESTED | + NFSMNTP_SEEK; + error = 0; + } + if ((nmp->nm_privflag & NFSMNTP_SEEK) != 0) + *ap->a_retval = vp->v_mount->mnt_stat.f_iosize; + mtx_unlock(&nmp->nm_mtx); + } break; default: Modified: projects/nfsv42/sys/fs/nfsclient/nfsmount.h ============================================================================== --- projects/nfsv42/sys/fs/nfsclient/nfsmount.h Tue Aug 27 01:16:02 2019 (r351524) +++ projects/nfsv42/sys/fs/nfsclient/nfsmount.h Tue Aug 27 01:40:38 2019 (r351525) @@ -108,6 +108,8 @@ struct nfsmount { #define NFSMNTP_IOADVISETHRUMDS 0x00000004 #define NFSMNTP_NOCOPY 0x00000008 #define NFSMNTP_NOCONSECUTIVE 0x00000010 +#define NFSMNTP_SEEK 0x00000020 +#define NFSMNTP_SEEKTESTED 0x00000040 #define NFSMNT_DIRPATH(m) (&((m)->nm_name[(m)->nm_krbnamelen + 1])) #define NFSMNT_SRVKRBNAME(m) \ From owner-svn-src-projects@freebsd.org Wed Aug 28 20:05:56 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id DF0DBE5260 for ; Wed, 28 Aug 2019 20:05:56 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46JcF05WSzz4dJK; Wed, 28 Aug 2019 20:05:56 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id 9F0F2CB63; Wed, 28 Aug 2019 20:05:56 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7SK5uLR058131; Wed, 28 Aug 2019 20:05:56 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7SK5u2V058128; Wed, 28 Aug 2019 20:05:56 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908282005.x7SK5u2V058128@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Wed, 28 Aug 2019 20:05:56 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351578 - in projects/clang900-import: . lib lib/libc++ lib/libc++fs X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: in projects/clang900-import: . lib lib/libc++ lib/libc++fs X-SVN-Commit-Revision: 351578 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 28 Aug 2019 20:05:56 -0000 Author: dim Date: Wed Aug 28 20:05:55 2019 New Revision: 351578 URL: https://svnweb.freebsd.org/changeset/base/351578 Log: Update build glue for building libc++. Deleted: projects/clang900-import/lib/libc++fs/ Modified: projects/clang900-import/ObsoleteFiles.inc projects/clang900-import/lib/Makefile projects/clang900-import/lib/libc++/Makefile Modified: projects/clang900-import/ObsoleteFiles.inc ============================================================================== --- projects/clang900-import/ObsoleteFiles.inc Wed Aug 28 19:40:57 2019 (r351577) +++ projects/clang900-import/ObsoleteFiles.inc Wed Aug 28 20:05:55 2019 (r351578) @@ -38,6 +38,17 @@ # xargs -n1 | sort | uniq -d; # done +# 2019mmdd: libc++ 9.0.0 removed some experimental files +OLD_FILES+=usr/include/c++/v1/experimental/any +OLD_FILES+=usr/include/c++/v1/experimental/chrono +OLD_FILES+=usr/include/c++/v1/experimental/numeric +OLD_FILES+=usr/include/c++/v1/experimental/optional +OLD_FILES+=usr/include/c++/v1/experimental/ratio +OLD_FILES+=usr/include/c++/v1/experimental/string_view +OLD_FILES+=usr/include/c++/v1/experimental/system_error +OLD_FILES+=usr/include/c++/v1/experimental/tuple +OLD_FILES+=usr/lib/libc++fs.a + # 20190817: pft_ping.py and sniffer.py moved to /usr/tests/sys/netpfil/common OLD_FILES+=usr/tests/sys/netpfil/pf/sniffer.py OLD_FILES+=usr/tests/sys/netpfil/pf/pft_ping.py Modified: projects/clang900-import/lib/Makefile ============================================================================== --- projects/clang900-import/lib/Makefile Wed Aug 28 19:40:57 2019 (r351577) +++ projects/clang900-import/lib/Makefile Wed Aug 28 20:05:55 2019 (r351578) @@ -166,7 +166,6 @@ _libclang_rt= libclang_rt _libcxxrt= libcxxrt _libcplusplus= libc++ _libcplusplus+= libc++experimental -_libcplusplus+= libc++fs .endif SUBDIR.${MK_EFI}+= libefivar Modified: projects/clang900-import/lib/libc++/Makefile ============================================================================== --- projects/clang900-import/lib/libc++/Makefile Wed Aug 28 19:40:57 2019 (r351577) +++ projects/clang900-import/lib/libc++/Makefile Wed Aug 28 20:05:55 2019 (r351578) @@ -23,8 +23,12 @@ SRCS+= bind.cpp SRCS+= charconv.cpp SRCS+= chrono.cpp SRCS+= condition_variable.cpp +SRCS+= condition_variable_destructor.cpp SRCS+= debug.cpp SRCS+= exception.cpp +SRCS+= filesystem/directory_iterator.cpp +SRCS+= filesystem/int128_builtins.cpp +SRCS+= filesystem/operations.cpp SRCS+= functional.cpp SRCS+= future.cpp SRCS+= hash.cpp @@ -33,6 +37,7 @@ SRCS+= iostream.cpp SRCS+= locale.cpp SRCS+= memory.cpp SRCS+= mutex.cpp +SRCS+= mutex_destructor.cpp SRCS+= new.cpp SRCS+= optional.cpp SRCS+= random.cpp @@ -48,9 +53,6 @@ SRCS+= utility.cpp SRCS+= valarray.cpp SRCS+= variant.cpp SRCS+= vector.cpp -SRCS+= filesystem/directory_iterator.cpp -SRCS+= filesystem/int128_builtins.cpp -SRCS+= filesystem/operations.cpp CXXRT_SRCS+= auxhelper.cc CXXRT_SRCS+= dynamic_cast.cc @@ -145,6 +147,7 @@ STD_HEADERS+= cwctype STD_HEADERS+= deque STD_HEADERS+= errno.h STD_HEADERS+= exception +STD_HEADERS+= fenv.h STD_HEADERS+= filesystem STD_HEADERS+= float.h STD_HEADERS+= forward_list @@ -228,8 +231,6 @@ STDDIR= ${CXXINCLUDEDIR} EXP_HEADERS+= __config EXP_HEADERS+= __memory EXP_HEADERS+= algorithm -EXP_HEADERS+= any -EXP_HEADERS+= chrono EXP_HEADERS+= coroutine EXP_HEADERS+= deque EXP_HEADERS+= filesystem @@ -239,17 +240,11 @@ EXP_HEADERS+= iterator EXP_HEADERS+= list EXP_HEADERS+= map EXP_HEADERS+= memory_resource -EXP_HEADERS+= numeric -EXP_HEADERS+= optional EXP_HEADERS+= propagate_const -EXP_HEADERS+= ratio EXP_HEADERS+= regex EXP_HEADERS+= set EXP_HEADERS+= simd EXP_HEADERS+= string -EXP_HEADERS+= string_view -EXP_HEADERS+= system_error -EXP_HEADERS+= tuple EXP_HEADERS+= type_traits EXP_HEADERS+= unordered_map EXP_HEADERS+= unordered_set From owner-svn-src-projects@freebsd.org Thu Aug 29 18:53:01 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id 1A621DD75B for ; Thu, 29 Aug 2019 18:53:01 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46KBZN6sB6z43pF; Thu, 29 Aug 2019 18:53:00 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id CCFC124466; Thu, 29 Aug 2019 18:53:00 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7TIr0gq072261; Thu, 29 Aug 2019 18:53:00 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7TIr0Ix072260; Thu, 29 Aug 2019 18:53:00 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908291853.x7TIr0Ix072260@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Thu, 29 Aug 2019 18:53:00 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351610 - projects/clang900-import/contrib/libunwind/src X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: projects/clang900-import/contrib/libunwind/src X-SVN-Commit-Revision: 351610 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 29 Aug 2019 18:53:01 -0000 Author: dim Date: Thu Aug 29 18:53:00 2019 New Revision: 351610 URL: https://svnweb.freebsd.org/changeset/base/351610 Log: Update libunwind custom frame register and deregister functions for FreeBSD: use the new doubly underscored names for unw_add_dynamic_fde and unw_remove_dynamic_fde. NOTE: this should be upstreamed... Modified: projects/clang900-import/contrib/libunwind/src/UnwindLevel1-gcc-ext.c Modified: projects/clang900-import/contrib/libunwind/src/UnwindLevel1-gcc-ext.c ============================================================================== --- projects/clang900-import/contrib/libunwind/src/UnwindLevel1-gcc-ext.c Thu Aug 29 18:23:38 2019 (r351609) +++ projects/clang900-import/contrib/libunwind/src/UnwindLevel1-gcc-ext.c Thu Aug 29 18:53:00 2019 (r351610) @@ -227,7 +227,7 @@ _LIBUNWIND_EXPORT uintptr_t _Unwind_GetIPInfo(struct _ #if defined(_LIBUNWIND_SUPPORT_DWARF_UNWIND) -#ifdef __FreeBSD__ +#if defined(__FreeBSD__) // Based on LLVM's lib/ExecutionEngine/RuntimeDyld/RTDyldMemoryManager.cpp // and XXX should be fixed to be alignment-safe. @@ -242,9 +242,9 @@ static void processFDE(const char *addr, bool isDeregi uint32_t offset = *((const uint32_t *)p); if (offset != 0) { if (isDeregister) - _unw_remove_dynamic_fde((unw_word_t)(uintptr_t)addr); + __unw_remove_dynamic_fde((unw_word_t)(uintptr_t)addr); else - _unw_add_dynamic_fde((unw_word_t)(uintptr_t)addr); + __unw_add_dynamic_fde((unw_word_t)(uintptr_t)addr); } addr = p + length; } @@ -265,9 +265,8 @@ _LIBUNWIND_EXPORT void __deregister_frame(const void * processFDE(addr, true); } +#else // defined(__FreeBSD__) -#else - /// Called by programs with dynamic code generators that want /// to register a dynamically generated FDE. /// This function has existed on Mac OS X since 10.4, but @@ -277,7 +276,6 @@ _LIBUNWIND_EXPORT void __register_frame(const void *fd __unw_add_dynamic_fde((unw_word_t)(uintptr_t)fde); } - /// Called by programs with dynamic code generators that want /// to unregister a dynamically generated FDE. /// This function has existed on Mac OS X since 10.4, but @@ -287,7 +285,7 @@ _LIBUNWIND_EXPORT void __deregister_frame(const void * __unw_remove_dynamic_fde((unw_word_t)(uintptr_t)fde); } -#endif +#endif // defined(__FreeBSD__) // The following register/deregister functions are gcc extensions. // They have existed on Mac OS X, but have never worked because Mac OS X From owner-svn-src-projects@freebsd.org Thu Aug 29 20:39:25 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id 412FDDF8BF for ; Thu, 29 Aug 2019 20:39:25 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46KDx90n5rz49pC; Thu, 29 Aug 2019 20:39:25 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id F092C256A9; Thu, 29 Aug 2019 20:39:24 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7TKdOGX032474; Thu, 29 Aug 2019 20:39:24 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7TKdOV6032473; Thu, 29 Aug 2019 20:39:24 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908292039.x7TKdOV6032473@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Thu, 29 Aug 2019 20:39:24 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351612 - projects/clang900-import/lib/libcompiler_rt X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: projects/clang900-import/lib/libcompiler_rt X-SVN-Commit-Revision: 351612 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 29 Aug 2019 20:39:25 -0000 Author: dim Date: Thu Aug 29 20:39:24 2019 New Revision: 351612 URL: https://svnweb.freebsd.org/changeset/base/351612 Log: Update build glue for building compiler-rt. Modified: projects/clang900-import/lib/libcompiler_rt/Makefile.inc Modified: projects/clang900-import/lib/libcompiler_rt/Makefile.inc ============================================================================== --- projects/clang900-import/lib/libcompiler_rt/Makefile.inc Thu Aug 29 19:13:27 2019 (r351611) +++ projects/clang900-import/lib/libcompiler_rt/Makefile.inc Thu Aug 29 20:39:24 2019 (r351612) @@ -58,7 +58,6 @@ SRCF+= fixunsxfti SRCF+= fixxfdi SRCF+= fixxfti SRCF+= floatditf -SRCF+= floatsitf SRCF+= floattidf SRCF+= floattisf SRCF+= floattixf @@ -68,7 +67,7 @@ SRCF+= floatunsisf SRCF+= floatuntidf SRCF+= floatuntisf SRCF+= floatuntixf -SRCF+= gcc_personality_v0 +SRCF+= gcc_personality_v0 # not in upstream SRCF+= int_util SRCF+= lshrdi3 SRCF+= lshrti3 @@ -160,7 +159,10 @@ SRCF+= fixtfti SRCF+= fixunstfdi SRCF+= fixunstfsi SRCF+= fixunstfti +SRCF+= floatsitf +SRCF+= floattitf SRCF+= floatunsitf +SRCF+= floatuntitf SRCF+= multf3 SRCF+= subtf3 SRCF+= trunctfdf2 From owner-svn-src-projects@freebsd.org Sat Aug 31 15:17:23 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id D5BAFD4813 for ; Sat, 31 Aug 2019 15:17:23 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46LKhg5MK3z4bHS; Sat, 31 Aug 2019 15:17:23 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id 9B1D11AC02; Sat, 31 Aug 2019 15:17:23 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7VFHNW9066045; Sat, 31 Aug 2019 15:17:23 GMT (envelope-from rmacklem@FreeBSD.org) Received: (from rmacklem@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7VFHMSD066042; Sat, 31 Aug 2019 15:17:22 GMT (envelope-from rmacklem@FreeBSD.org) Message-Id: <201908311517.x7VFHMSD066042@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: rmacklem set sender to rmacklem@FreeBSD.org using -f From: Rick Macklem Date: Sat, 31 Aug 2019 15:17:22 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351645 - projects/nfsv42/sys/fs/nfs X-SVN-Group: projects X-SVN-Commit-Author: rmacklem X-SVN-Commit-Paths: projects/nfsv42/sys/fs/nfs X-SVN-Commit-Revision: 351645 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 31 Aug 2019 15:17:23 -0000 Author: rmacklem Date: Sat Aug 31 15:17:22 2019 New Revision: 351645 URL: https://svnweb.freebsd.org/changeset/base/351645 Log: Update the NFS common files for the optional Extended attribute support defined in RFC-8276. Updates to the rest of the files for get extended attributes coming soon. Modified: projects/nfsv42/sys/fs/nfs/nfs_commonsubs.c projects/nfsv42/sys/fs/nfs/nfs_var.h projects/nfsv42/sys/fs/nfs/nfsport.h projects/nfsv42/sys/fs/nfs/nfsproto.h Modified: projects/nfsv42/sys/fs/nfs/nfs_commonsubs.c ============================================================================== --- projects/nfsv42/sys/fs/nfs/nfs_commonsubs.c Sat Aug 31 15:10:27 2019 (r351644) +++ projects/nfsv42/sys/fs/nfs/nfs_commonsubs.c Sat Aug 31 15:17:22 2019 (r351645) @@ -107,7 +107,7 @@ SYSCTL_INT(_vfs_nfs, OID_AUTO, pnfsmirror, CTLFLAG_RD, * non-idempotent Ops. * Define it here, since it is used by both the client and server. */ -struct nfsv4_opflag nfsv4_opflag[NFSV42_NOPS] = { +struct nfsv4_opflag nfsv4_opflag[NFSV4N_NOPS] = { { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* undef */ { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* undef */ { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* undef */ @@ -180,6 +180,10 @@ struct nfsv4_opflag nfsv4_opflag[NFSV42_NOPS] = { { 0, 1, 0, 0, LK_SHARED, 1, 0 }, /* Seek */ { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* Write Same */ { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* Clone */ + { 0, 1, 0, 0, LK_SHARED, 1, 1 }, /* Getxattr */ + { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* Setxattr */ + { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* Listxattrs */ + { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* Removexattr */ }; #endif /* !APPLEKEXT */ @@ -206,7 +210,8 @@ static struct nfsrv_lughash *nfsgroupnamehash; */ static int nfs_bigreply[NFSV42_NPROCS] = { 0, 0, 0, 1, 0, 1, 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 1, 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, - 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 1, 0, 0, 0, 0, 0, 0, 0, 0 }; + 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 1, 0, 0, 0, 0, 0, 0, 0, 0, + 0 }; /* local functions */ static int nfsrv_skipace(struct nfsrv_descript *nd, int *acesizep); @@ -285,6 +290,7 @@ static struct { { NFSV4OP_SAVEFH, 5, "Copy", 4, }, { NFSV4OP_SEEK, 2, "Seek", 4, }, { NFSV4OP_SEEK, 1, "SeekDS", 6, }, + { NFSV4OP_GETXATTR, 2, "Getxattr", 8, }, }; /* @@ -293,7 +299,7 @@ static struct { static int nfs_bigrequest[NFSV42_NPROCS] = { 0, 0, 0, 0, 0, 0, 0, 1, 0, 0, 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, - 0, 0, 0, 0, 0, 0, 1, 0, 0, 0, 0, 0, 0, 0, 0, 0 + 0, 0, 0, 0, 0, 0, 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0 }; /* Modified: projects/nfsv42/sys/fs/nfs/nfs_var.h ============================================================================== --- projects/nfsv42/sys/fs/nfs/nfs_var.h Sat Aug 31 15:10:27 2019 (r351644) +++ projects/nfsv42/sys/fs/nfs/nfs_var.h Sat Aug 31 15:17:22 2019 (r351645) @@ -283,6 +283,8 @@ int nfsrvd_copy_file_range(struct nfsrv_descript *, in vnode_t, vnode_t, struct nfsexstuff *, struct nfsexstuff *); int nfsrvd_seek(struct nfsrv_descript *, int, vnode_t, struct nfsexstuff *); +int nfsrvd_getxattr(struct nfsrv_descript *, int, + vnode_t, struct nfsexstuff *); int nfsrvd_notsupp(struct nfsrv_descript *, int, vnode_t, struct nfsexstuff *); @@ -544,6 +546,8 @@ int nfsrpc_copy_file_range(vnode_t, off_t *, vnode_t, struct ucred *, bool, bool *); int nfsrpc_seek(vnode_t, off_t *, bool *, int, struct ucred *, struct nfsvattr *, int *); +int nfsrpc_getextattr(vnode_t, const char *, struct uio *, ssize_t *, + struct nfsvattr *, int *, struct ucred *, NFSPROC_T *); /* nfs_clstate.c */ int nfscl_open(vnode_t, u_int8_t *, int, u_int32_t, int, @@ -727,6 +731,8 @@ void nfsrv_killrpcs(struct nfsmount *); int nfsrv_setacl(struct vnode *, NFSACL_T *, struct ucred *, NFSPROC_T *); int nfsvno_seek(struct nfsrv_descript *, struct vnode *, u_long, off_t *, int, bool *, struct ucred *, NFSPROC_T *); +int nfsvno_getxattr(struct vnode *, char *, struct ucred *, struct thread *, + struct mbuf **, struct mbuf **, int *); /* nfs_commonkrpc.c */ int newnfs_nmcancelreqs(struct nfsmount *); Modified: projects/nfsv42/sys/fs/nfs/nfsport.h ============================================================================== --- projects/nfsv42/sys/fs/nfs/nfsport.h Sat Aug 31 15:10:27 2019 (r351644) +++ projects/nfsv42/sys/fs/nfs/nfsport.h Sat Aug 31 15:17:22 2019 (r351645) @@ -278,10 +278,21 @@ #define NFSV4OP_CLONE 71 /* - * Must be one more than the last op#. + * Must be one more than the last NFSv4.2 op#. */ #define NFSV42_NOPS 72 +/* and the optional Extended attribute operations (RFC-8276). */ +#define NFSV4OP_GETXATTR 72 +#define NFSV4OP_SETXATTR 73 +#define NFSV4OP_LISTXATTRS 74 +#define NFSV4OP_REMOVEXATTR 75 + +/* + * Must be one more that the last op#. + */ +#define NFSV4N_NOPS 76 + /* Quirky case if the illegal op code */ #define NFSV4OP_OPILLEGAL 10044 @@ -400,10 +411,13 @@ #define NFSPROC_SEEK 59 #define NFSPROC_SEEKDS 60 +/* and the ones for the optional Extended attribute support (RFC-8276). */ +#define NFSPROC_GETEXTATTR 61 + /* * Must be defined as one higher than the last NFSv4.2 Proc# above. */ -#define NFSV42_NPROCS 61 +#define NFSV42_NPROCS 62 #endif /* NFS_V3NPROCS */ @@ -432,7 +446,7 @@ struct nfsstatsv1 { uint64_t readlink_bios; uint64_t biocache_readdirs; uint64_t readdir_bios; - uint64_t rpccnt[NFSV42_NPROCS + 8]; + uint64_t rpccnt[NFSV42_NPROCS + 7]; uint64_t rpcretries; uint64_t srvrpccnt[NFSV42_NOPS + NFSV4OP_FAKENOPS]; uint64_t srvrpc_errs; Modified: projects/nfsv42/sys/fs/nfs/nfsproto.h ============================================================================== --- projects/nfsv42/sys/fs/nfs/nfsproto.h Sat Aug 31 15:10:27 2019 (r351644) +++ projects/nfsv42/sys/fs/nfs/nfsproto.h Sat Aug 31 15:17:22 2019 (r351645) @@ -224,8 +224,12 @@ #define NFSERR_BADLABEL 10093 #define NFSERR_OFFLOADNOREQS 10094 +/* NFSv4.2 Extended Attribute errors. */ +#define NFSERR_NOXATTR 10095 +#define NFSERR_XATTR2BIG 10096 + /* Maximum value of all the NFS error values. */ -#define NFSERR_MAXERRVAL NFSERR_OFFLOADNOREQS +#define NFSERR_MAXERRVAL NFSERR_XATTR2BIG #define NFSERR_STALEWRITEVERF 30001 /* Fake return for nfs_commit() */ #define NFSERR_DONTREPLY 30003 /* Don't process request */ @@ -384,10 +388,13 @@ #define NFSPROC_SEEK 59 #define NFSPROC_SEEKDS 60 +/* and the ones for the optional Extended attribute support (RFC-8276). */ +#define NFSPROC_GETEXTATTR 61 + /* * Must be defined as one higher than the last NFSv4.2 Proc# above. */ -#define NFSV42_NPROCS 61 +#define NFSV42_NPROCS 62 #endif /* NFS_V3NPROCS */ @@ -400,10 +407,10 @@ /* * NFSPROC_NOOP is a fake op# that can't be the same as any V2/3/4 Procedure - * or Operation#. Since the NFS V4 Op #s go higher, use NFSV42_NOPS, which + * or Operation#. Since the NFS V4 Op #s go higher, use NFSV4N_NOPS, which * is one greater than the highest Op#. */ -#define NFSPROC_NOOP NFSV42_NOPS +#define NFSPROC_NOOP NFSV4N_NOPS /* Actual Version 2 procedure numbers */ #define NFSV2PROC_NULL 0 From owner-svn-src-projects@freebsd.org Sat Aug 31 16:10:50 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id C03B8D58D0 for ; Sat, 31 Aug 2019 16:10:50 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46LLtL5TSLz4dNQ; Sat, 31 Aug 2019 16:10:50 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id 9C2241B545; Sat, 31 Aug 2019 16:10:50 +0000 (UTC) (envelope-from rmacklem@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7VGAo2b097206; Sat, 31 Aug 2019 16:10:50 GMT (envelope-from rmacklem@FreeBSD.org) Received: (from rmacklem@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7VGAmb9097196; Sat, 31 Aug 2019 16:10:48 GMT (envelope-from rmacklem@FreeBSD.org) Message-Id: <201908311610.x7VGAmb9097196@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: rmacklem set sender to rmacklem@FreeBSD.org using -f From: Rick Macklem Date: Sat, 31 Aug 2019 16:10:48 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351646 - in projects/nfsv42/sys/fs: nfs nfsclient nfsserver X-SVN-Group: projects X-SVN-Commit-Author: rmacklem X-SVN-Commit-Paths: in projects/nfsv42/sys/fs: nfs nfsclient nfsserver X-SVN-Commit-Revision: 351646 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 31 Aug 2019 16:10:50 -0000 Author: rmacklem Date: Sat Aug 31 16:10:48 2019 New Revision: 351646 URL: https://svnweb.freebsd.org/changeset/base/351646 Log: Add support for the Get extended attribute operation. RFC-8276 defines an optional extension to NFSv4.2 to handle extended attributes. This patch adds the first of the four of these operations. Modified: projects/nfsv42/sys/fs/nfs/nfs_commonsubs.c projects/nfsv42/sys/fs/nfs/nfsport.h projects/nfsv42/sys/fs/nfs/nfsproto.h projects/nfsv42/sys/fs/nfsclient/nfs_clrpcops.c projects/nfsv42/sys/fs/nfsclient/nfs_clvnops.c projects/nfsv42/sys/fs/nfsclient/nfsmount.h projects/nfsv42/sys/fs/nfsserver/nfs_nfsdport.c projects/nfsv42/sys/fs/nfsserver/nfs_nfsdserv.c projects/nfsv42/sys/fs/nfsserver/nfs_nfsdsocket.c Modified: projects/nfsv42/sys/fs/nfs/nfs_commonsubs.c ============================================================================== --- projects/nfsv42/sys/fs/nfs/nfs_commonsubs.c Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfs/nfs_commonsubs.c Sat Aug 31 16:10:48 2019 (r351646) @@ -107,7 +107,7 @@ SYSCTL_INT(_vfs_nfs, OID_AUTO, pnfsmirror, CTLFLAG_RD, * non-idempotent Ops. * Define it here, since it is used by both the client and server. */ -struct nfsv4_opflag nfsv4_opflag[NFSV4N_NOPS] = { +struct nfsv4_opflag nfsv4_opflag[NFSV42_NOPS] = { { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* undef */ { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* undef */ { 0, 0, 0, 0, LK_EXCLUSIVE, 1, 1 }, /* undef */ Modified: projects/nfsv42/sys/fs/nfs/nfsport.h ============================================================================== --- projects/nfsv42/sys/fs/nfs/nfsport.h Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfs/nfsport.h Sat Aug 31 16:10:48 2019 (r351646) @@ -277,11 +277,6 @@ #define NFSV4OP_WRITESAME 70 #define NFSV4OP_CLONE 71 -/* - * Must be one more than the last NFSv4.2 op#. - */ -#define NFSV42_NOPS 72 - /* and the optional Extended attribute operations (RFC-8276). */ #define NFSV4OP_GETXATTR 72 #define NFSV4OP_SETXATTR 73 @@ -289,9 +284,9 @@ #define NFSV4OP_REMOVEXATTR 75 /* - * Must be one more that the last op#. + * Must be one more than the last NFSv4.2 op#. */ -#define NFSV4N_NOPS 76 +#define NFSV42_NOPS 76 /* Quirky case if the illegal op code */ #define NFSV4OP_OPILLEGAL 10044 Modified: projects/nfsv42/sys/fs/nfs/nfsproto.h ============================================================================== --- projects/nfsv42/sys/fs/nfs/nfsproto.h Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfs/nfsproto.h Sat Aug 31 16:10:48 2019 (r351646) @@ -407,10 +407,10 @@ /* * NFSPROC_NOOP is a fake op# that can't be the same as any V2/3/4 Procedure - * or Operation#. Since the NFS V4 Op #s go higher, use NFSV4N_NOPS, which + * or Operation#. Since the NFS V4 Op #s go higher, use NFSV42_NOPS, which * is one greater than the highest Op#. */ -#define NFSPROC_NOOP NFSV4N_NOPS +#define NFSPROC_NOOP NFSV42_NOPS /* Actual Version 2 procedure numbers */ #define NFSV2PROC_NULL 0 Modified: projects/nfsv42/sys/fs/nfsclient/nfs_clrpcops.c ============================================================================== --- projects/nfsv42/sys/fs/nfsclient/nfs_clrpcops.c Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfsclient/nfs_clrpcops.c Sat Aug 31 16:10:48 2019 (r351646) @@ -8240,3 +8240,73 @@ nfsmout: return (error); } +/* + * The getextattr RPC. + */ +APPLESTATIC int +nfsrpc_getextattr(vnode_t vp, const char *name, struct uio *uiop, ssize_t *lenp, + struct nfsvattr *nap, int *attrflagp, struct ucred *cred, NFSPROC_T *p) +{ + uint32_t *tl; + int error; + struct nfsrv_descript nfsd; + struct nfsrv_descript *nd = &nfsd; + nfsattrbit_t attrbits; + uint32_t len, len2; + + *attrflagp = 0; + NFSCL_REQSTART(nd, NFSPROC_GETEXTATTR, vp); + nfsm_strtom(nd, name, strlen(name)); + NFSM_BUILD(tl, uint32_t *, NFSX_UNSIGNED); + *tl = txdr_unsigned(NFSV4OP_GETATTR); + NFSGETATTR_ATTRBIT(&attrbits); + nfsrv_putattrbit(nd, &attrbits); + error = nfscl_request(nd, vp, p, cred, NULL); + if (error != 0) + return (error); + if (nd->nd_repstat == 0) { + NFSM_DISSECT(tl, uint32_t *, NFSX_UNSIGNED); + len = fxdr_unsigned(uint32_t, *tl); + /* Sanity check lengths. */ + if (uiop != NULL && len > 0 && len <= IOSIZE_MAX && + uiop->uio_resid <= UINT32_MAX) { + len2 = uiop->uio_resid; + if (len2 >= len) + error = nfsm_mbufuio(nd, uiop, len); + else { + error = nfsm_mbufuio(nd, uiop, len2); + if (error == 0) { + /* + * nfsm_mbufuio() advances to a multiple + * of 4, so advance len2 as well. Then + * we need to advance over the rest of + * the data. + */ + len2 = NFSM_RNDUP(len2); + len2 = NFSM_RNDUP(len - len2); + if (len2 > 0) + error = nfsm_advance(nd, len2, + -1); + } + } + } else if (uiop == NULL && len > 0) { + /* Just wants the length and not the data. */ + error = nfsm_advance(nd, len, -1); + } else + error = ENOATTR; + if (error != 0) + goto nfsmout; + *lenp = len; + /* Just skip over Getattr op status. */ + NFSM_DISSECT(tl, uint32_t *, 2 * NFSX_UNSIGNED); + error = nfsm_loadattr(nd, nap); + if (error == 0) + *attrflagp = 1; + } + if (error == 0) + error = nd->nd_repstat; +nfsmout: + mbuf_freem(nd->nd_mrep); + return (error); +} + Modified: projects/nfsv42/sys/fs/nfsclient/nfs_clvnops.c ============================================================================== --- projects/nfsv42/sys/fs/nfsclient/nfs_clvnops.c Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfsclient/nfs_clvnops.c Sat Aug 31 16:10:48 2019 (r351646) @@ -51,6 +51,7 @@ __FBSDID("$FreeBSD$"); #include #include #include +#include #include #include #include @@ -147,6 +148,7 @@ static vop_advise_t nfs_advise; static vop_allocate_t nfs_allocate; static vop_copy_file_range_t nfs_copy_file_range; static vop_ioctl_t nfs_ioctl; +static vop_getextattr_t nfs_getextattr; /* * Global vfs data structures for nfs @@ -188,6 +190,7 @@ static struct vop_vector newnfs_vnodeops_nosig = { .vop_allocate = nfs_allocate, .vop_copy_file_range = nfs_copy_file_range, .vop_ioctl = nfs_ioctl, + .vop_getextattr = nfs_getextattr, }; static int @@ -3742,6 +3745,65 @@ nfs_ioctl(struct vop_ioctl_args *ap) if (error != 0) error = ENXIO; + return (error); +} + +/* + * nfs getextattr call + */ +static int +nfs_getextattr(struct vop_getextattr_args *ap) +{ + struct vnode *vp = ap->a_vp; + struct nfsmount *nmp; + struct ucred *cred; + struct thread *td = ap->a_td; + struct nfsvattr nfsva; + ssize_t len; + int attrflag, error, ret; + + nmp = VFSTONFS(vp->v_mount); + mtx_lock(&nmp->nm_mtx); + if (!NFSHASNFSV4(nmp) || nmp->nm_minorvers < NFSV42_MINORVERSION || + (nmp->nm_privflag & NFSMNTP_NOXATTR) != 0 || + ap->a_attrnamespace != EXTATTR_NAMESPACE_USER) { + mtx_unlock(&nmp->nm_mtx); + return (EOPNOTSUPP); + } + mtx_unlock(&nmp->nm_mtx); + + cred = ap->a_cred; + if (cred == NULL) + cred = td->td_ucred; + /* Do the actual NFSv4.2 Optional Extended Attribute (RFC-8276) RPC. */ + attrflag = 0; + error = nfsrpc_getextattr(vp, ap->a_name, ap->a_uio, &len, &nfsva, + &attrflag, cred, td); + if (attrflag != 0) { + ret = nfscl_loadattrcache(&vp, &nfsva, NULL, NULL, 0, 1); + if (error == 0 && ret != 0) + error = ret; + } + if (error == 0 && ap->a_size != NULL) + *ap->a_size = len; + + switch (error) { + case NFSERR_NOTSUPP: + case NFSERR_OPILLEGAL: + case NFSERR_MINORVERMISMATCH: + mtx_lock(&nmp->nm_mtx); + nmp->nm_privflag |= NFSMNTP_NOXATTR; + mtx_unlock(&nmp->nm_mtx); + error = EOPNOTSUPP; + break; + case NFSERR_NOXATTR: + case NFSERR_XATTR2BIG: + error = ENOATTR; + break; + default: + error = nfscl_maperr(td, error, 0, 0); + break; + } return (error); } Modified: projects/nfsv42/sys/fs/nfsclient/nfsmount.h ============================================================================== --- projects/nfsv42/sys/fs/nfsclient/nfsmount.h Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfsclient/nfsmount.h Sat Aug 31 16:10:48 2019 (r351646) @@ -110,6 +110,7 @@ struct nfsmount { #define NFSMNTP_NOCONSECUTIVE 0x00000010 #define NFSMNTP_SEEK 0x00000020 #define NFSMNTP_SEEKTESTED 0x00000040 +#define NFSMNTP_NOXATTR 0x00000080 #define NFSMNT_DIRPATH(m) (&((m)->nm_name[(m)->nm_krbnamelen + 1])) #define NFSMNT_SRVKRBNAME(m) \ Modified: projects/nfsv42/sys/fs/nfsserver/nfs_nfsdport.c ============================================================================== --- projects/nfsv42/sys/fs/nfsserver/nfs_nfsdport.c Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfsserver/nfs_nfsdport.c Sat Aug 31 16:10:48 2019 (r351646) @@ -46,6 +46,7 @@ __FBSDID("$FreeBSD$"); */ #include +#include #include #include #include @@ -5862,6 +5863,86 @@ nfsvno_seek(struct nfsrv_descript *nd, struct vnode *v if (ret != 0 && error == 0) error = ret; } + NFSEXITCODE(error); + return (error); +} + +/* + * Get Extended Atribute vnode op into an mbuf list. + */ +int +nfsvno_getxattr(struct vnode *vp, char *name, struct ucred *cred, + struct thread *p, struct mbuf **mpp, struct mbuf **mpendp, int *lenp) +{ + struct iovec *ivp, *ivp2; + struct uio io, *uiop = &io; + struct mbuf *mp, *mp2 = NULL, *mp3 = NULL; + int alen, error, i, len, maxiov, tlen; + size_t siz; + + maxiov = (NFS_SRVMAXIO + MCLBYTES - 1) / MCLBYTES; + if (maxiov < 1) + maxiov = 1; + ivp2 = ivp = mallocarray(maxiov, sizeof(*ivp), M_TEMP, M_WAITOK); + len = 0; + i = 0; + while (i < maxiov) { + NFSMGET(mp); + MCLGET(mp, M_WAITOK); + mp->m_len = M_SIZE(mp); + if (len == 0) { + mp3 = mp2 = mp; + } else { + mp2->m_next = mp; + mp2 = mp; + } + len += mp->m_len; + ivp->iov_base = mtod(mp, caddr_t); + ivp->iov_len = mp->m_len; + i++; + ivp++; + } + uiop->uio_iov = ivp2; + uiop->uio_iovcnt = i; + uiop->uio_offset = 0; + uiop->uio_resid = len; + uiop->uio_rw = UIO_READ; + uiop->uio_segflg = UIO_SYSSPACE; + uiop->uio_td = p; +#ifdef MAC + error = mac_vnode_check_getextattr(cred, vp, EXTATTR_NAMESPACE_USER, + name); + if (error != 0) + goto out; +#endif + + error = VOP_GETEXTATTR(vp, EXTATTR_NAMESPACE_USER, name, uiop, NULL, + cred, p); + if (error != 0) + goto out; + if (uiop->uio_resid > 0) { + alen = len; + len -= uiop->uio_resid; + tlen = NFSM_RNDUP(len); + nfsrv_adj(mp3, alen - tlen, tlen - len); + } else { + error = VOP_GETEXTATTR(vp, EXTATTR_NAMESPACE_USER, name, NULL, + &siz, cred, p); + if (error == 0 && len < siz) + error = NFSERR_XATTR2BIG; + } + if (error == 0) { + *lenp = len; + *mpp = mp3; + *mpendp = mp; + } + +out: + if (error != 0) { + m_freem(mp3); + *lenp = 0; + } + free(ivp2, M_TEMP); NFSEXITCODE(error); return (error); } Modified: projects/nfsv42/sys/fs/nfsserver/nfs_nfsdserv.c ============================================================================== --- projects/nfsv42/sys/fs/nfsserver/nfs_nfsdserv.c Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfsserver/nfs_nfsdserv.c Sat Aug 31 16:10:48 2019 (r351646) @@ -50,6 +50,7 @@ __FBSDID("$FreeBSD$"); #ifndef APPLEKEXT #include +#include #include /* Global vars */ @@ -5472,6 +5473,60 @@ nfsmout: vput(vp); NFSEXITCODE2(error, nd); return (error); +} + +/* + * nfs get extended attribute service + */ +APPLESTATIC int +nfsrvd_getxattr(struct nfsrv_descript *nd, __unused int isdgram, + vnode_t vp, __unused struct nfsexstuff *exp) +{ + uint32_t *tl; + mbuf_t mp = NULL, mpend = NULL; + int error, len; + char *name; + struct thread *p = curthread; + + error = 0; + if (nfs_rootfhset == 0 || nfsd_checkrootexp(nd) != 0) { + nd->nd_repstat = NFSERR_WRONGSEC; + goto nfsmout; + } + NFSM_DISSECT(tl, uint32_t *, NFSX_UNSIGNED); + len = fxdr_unsigned(int, *tl); + if (len <= 0) { + nd->nd_repstat = NFSERR_BADXDR; + goto nfsmout; + } + if (len > EXTATTR_MAXNAMELEN) { + nd->nd_repstat = NFSERR_NOXATTR; + goto nfsmout; + } + name = malloc(len + 1, M_TEMP, M_WAITOK); + nd->nd_repstat = nfsrv_mtostr(nd, name, len); + if (nd->nd_repstat == 0) + nd->nd_repstat = nfsvno_getxattr(vp, name, nd->nd_cred, p, + &mp, &mpend, &len); + if (nd->nd_repstat == ENOATTR) + nd->nd_repstat = NFSERR_NOXATTR; + else if (nd->nd_repstat == EOPNOTSUPP) + nd->nd_repstat = NFSERR_NOTSUPP; + if (nd->nd_repstat == 0) { + NFSM_BUILD(tl, uint32_t *, NFSX_UNSIGNED); + *tl = txdr_unsigned(len); + mbuf_setnext(nd->nd_mb, mp); + nd->nd_mb = mpend; + nd->nd_bpos = NFSMTOD(mpend, caddr_t) + mbuf_len(mpend); + } + free(name, M_TEMP); + +nfsmout: + if (nd->nd_repstat == 0) + nd->nd_repstat = error; + vput(vp); + NFSEXITCODE2(0, nd); + return (0); } /* Modified: projects/nfsv42/sys/fs/nfsserver/nfs_nfsdsocket.c ============================================================================== --- projects/nfsv42/sys/fs/nfsserver/nfs_nfsdsocket.c Sat Aug 31 15:17:22 2019 (r351645) +++ projects/nfsv42/sys/fs/nfsserver/nfs_nfsdsocket.c Sat Aug 31 16:10:48 2019 (r351646) @@ -209,6 +209,10 @@ int (*nfsrv4_ops0[NFSV42_NOPS])(struct nfsrv_descript nfsrvd_seek, nfsrvd_notsupp, nfsrvd_notsupp, + nfsrvd_getxattr, + nfsrvd_notsupp, + nfsrvd_notsupp, + nfsrvd_notsupp, }; int (*nfsrv4_ops1[NFSV42_NOPS])(struct nfsrv_descript *, @@ -285,6 +289,10 @@ int (*nfsrv4_ops1[NFSV42_NOPS])(struct nfsrv_descript (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t *, fhandle_t *, struct nfsexstuff *))0, (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t *, fhandle_t *, struct nfsexstuff *))0, (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t *, fhandle_t *, struct nfsexstuff *))0, + (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t *, fhandle_t *, struct nfsexstuff *))0, + (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t *, fhandle_t *, struct nfsexstuff *))0, + (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t *, fhandle_t *, struct nfsexstuff *))0, + (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t *, fhandle_t *, struct nfsexstuff *))0, }; int (*nfsrv4_ops2[NFSV42_NOPS])(struct nfsrv_descript *, @@ -350,6 +358,10 @@ int (*nfsrv4_ops2[NFSV42_NOPS])(struct nfsrv_descript (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, nfsrvd_copy_file_range, + (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, + (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, + (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, + (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, (int (*)(struct nfsrv_descript *, int, vnode_t , vnode_t , struct nfsexstuff *, struct nfsexstuff *))0, From owner-svn-src-projects@freebsd.org Sat Aug 31 18:04:35 2019 Return-Path: Delivered-To: svn-src-projects@mailman.nyi.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.nyi.freebsd.org (Postfix) with ESMTP id 0D4F1D816A for ; Sat, 31 Aug 2019 18:04:35 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from mxrelay.nyi.freebsd.org (mxrelay.nyi.freebsd.org [IPv6:2610:1c1:1:606c::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.nyi.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 46LPPZ6bd2z3FwY; Sat, 31 Aug 2019 18:04:34 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.nyi.freebsd.org (Postfix) with ESMTPS id C5F741CADE; Sat, 31 Aug 2019 18:04:34 +0000 (UTC) (envelope-from dim@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id x7VI4YuO067050; Sat, 31 Aug 2019 18:04:34 GMT (envelope-from dim@FreeBSD.org) Received: (from dim@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id x7VI4Ymn067048; Sat, 31 Aug 2019 18:04:34 GMT (envelope-from dim@FreeBSD.org) Message-Id: <201908311804.x7VI4Ymn067048@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: dim set sender to dim@FreeBSD.org using -f From: Dimitry Andric Date: Sat, 31 Aug 2019 18:04:34 +0000 (UTC) To: src-committers@freebsd.org, svn-src-projects@freebsd.org Subject: svn commit: r351647 - in projects/clang900-import: etc/mtree lib/clang/headers tools/build/mk X-SVN-Group: projects X-SVN-Commit-Author: dim X-SVN-Commit-Paths: in projects/clang900-import: etc/mtree lib/clang/headers tools/build/mk X-SVN-Commit-Revision: 351647 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-projects@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "SVN commit messages for the src " projects" tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 31 Aug 2019 18:04:35 -0000 Author: dim Date: Sat Aug 31 18:04:33 2019 New Revision: 351647 URL: https://svnweb.freebsd.org/changeset/base/351647 Log: Update Makefile and mtree for clang internal headers, and update OptionalObsoleteFiles.inc for added and removed files. Modified: projects/clang900-import/etc/mtree/BSD.usr.dist projects/clang900-import/lib/clang/headers/Makefile projects/clang900-import/tools/build/mk/OptionalObsoleteFiles.inc Modified: projects/clang900-import/etc/mtree/BSD.usr.dist ============================================================================== --- projects/clang900-import/etc/mtree/BSD.usr.dist Sat Aug 31 16:10:48 2019 (r351646) +++ projects/clang900-import/etc/mtree/BSD.usr.dist Sat Aug 31 18:04:33 2019 (r351647) @@ -39,6 +39,9 @@ clang 9.0.0 include + cuda_wrappers + openmp_wrappers + ppc_wrappers sanitizer .. .. Modified: projects/clang900-import/lib/clang/headers/Makefile ============================================================================== --- projects/clang900-import/lib/clang/headers/Makefile Sat Aug 31 16:10:48 2019 (r351646) +++ projects/clang900-import/lib/clang/headers/Makefile Sat Aug 31 18:04:33 2019 (r351647) @@ -4,7 +4,11 @@ .PATH: ${CLANG_SRCS}/lib/Headers +INCSGROUPS= INCS CUDA OMP PPC INCSDIR= ${LIBDIR}/clang/9.0.0/include +CUDADIR= ${INCSDIR}/cuda_wrappers +OMPDIR= ${INCSDIR}/openmp_wrappers +PPCDIR= ${INCSDIR}/ppc_wrappers GENINCS+= arm_fp16.h GENINCS+= arm_neon.h @@ -27,6 +31,7 @@ INCS+= arm64intr.h INCS+= arm_acle.h INCS+= armintr.h INCS+= avx2intrin.h +INCS+= avx512bf16intrin.h INCS+= avx512bitalgintrin.h INCS+= avx512bwintrin.h INCS+= avx512cdintrin.h @@ -39,6 +44,7 @@ INCS+= avx512pfintrin.h INCS+= avx512vbmi2intrin.h INCS+= avx512vbmiintrin.h INCS+= avx512vbmivlintrin.h +INCS+= avx512vlbf16intrin.h INCS+= avx512vlbitalgintrin.h INCS+= avx512vlbwintrin.h INCS+= avx512vlcdintrin.h @@ -46,7 +52,9 @@ INCS+= avx512vldqintrin.h INCS+= avx512vlintrin.h INCS+= avx512vlvbmi2intrin.h INCS+= avx512vlvnniintrin.h +INCS+= avx512vlvp2intersectintrin.h INCS+= avx512vnniintrin.h +INCS+= avx512vp2intersectintrin.h INCS+= avx512vpopcntdqintrin.h INCS+= avx512vpopcntdqvlintrin.h INCS+= avxintrin.h @@ -59,6 +67,7 @@ INCS+= clwbintrin.h INCS+= clzerointrin.h INCS+= cpuid.h INCS+= emmintrin.h +INCS+= enqcmdintrin.h INCS+= f16cintrin.h INCS+= fma4intrin.h INCS+= fmaintrin.h @@ -79,6 +88,7 @@ INCS+= movdirintrin.h INCS+= msa.h INCS+= mwaitxintrin.h INCS+= nmmintrin.h +INCS+= opencl-c-base.h INCS+= opencl-c.h INCS+= pconfigintrin.h INCS+= pkuintrin.h @@ -129,6 +139,20 @@ INCS+= tgmath.h INCS+= unwind.h INCS+= varargs.h .endif + +CUDA+= cuda_wrappers/algorithm +CUDA+= cuda_wrappers/complex +CUDA+= cuda_wrappers/new + +OMP+= openmp_wrappers/__clang_openmp_math.h +OMP+= openmp_wrappers/__clang_openmp_math_declares.h +OMP+= openmp_wrappers/cmath +OMP+= openmp_wrappers/math.h + +PPC+= ppc_wrappers/emmintrin.h +PPC+= ppc_wrappers/mm_malloc.h +PPC+= ppc_wrappers/mmintrin.h +PPC+= ppc_wrappers/xmmintrin.h arm_fp16.h: ${CLANG_SRCS}/include/clang/Basic/arm_fp16.td ${CLANG_TBLGEN} -gen-arm-fp16 \ Modified: projects/clang900-import/tools/build/mk/OptionalObsoleteFiles.inc ============================================================================== --- projects/clang900-import/tools/build/mk/OptionalObsoleteFiles.inc Sat Aug 31 16:10:48 2019 (r351646) +++ projects/clang900-import/tools/build/mk/OptionalObsoleteFiles.inc Sat Aug 31 18:04:33 2019 (r351647) @@ -1381,12 +1381,25 @@ OLD_FILES+=usr/bin/llvm-objdump OLD_FILES+=usr/bin/llvm-ranlib OLD_FILES+=usr/bin/llvm-symbolizer OLD_FILES+=usr/bin/llvm-tblgen +OLD_FILES+=usr/lib/clang/9.0.0/include/cuda_wrappers/algorithm +OLD_FILES+=usr/lib/clang/9.0.0/include/cuda_wrappers/complex +OLD_FILES+=usr/lib/clang/9.0.0/include/cuda_wrappers/new +OLD_DIRS+=usr/lib/clang/9.0.0/include/cuda_wrappers +OLD_FILES+=usr/lib/clang/9.0.0/include/openmp_wrappers/__clang_openmp_math.h +OLD_FILES+=usr/lib/clang/9.0.0/include/openmp_wrappers/__clang_openmp_math_declares.h +OLD_FILES+=usr/lib/clang/9.0.0/include/openmp_wrappers/cmath +OLD_FILES+=usr/lib/clang/9.0.0/include/openmp_wrappers/math.h +OLD_DIRS+=usr/lib/clang/9.0.0/include/openmp_wrappers +OLD_FILES+=usr/lib/clang/9.0.0/include/ppc_wrappers/emmintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/ppc_wrappers/mm_malloc.h +OLD_FILES+=usr/lib/clang/9.0.0/include/ppc_wrappers/mmintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/ppc_wrappers/xmmintrin.h +OLD_DIRS+=usr/lib/clang/9.0.0/include/ppc_wrappers OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/allocator_interface.h OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/asan_interface.h OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/common_interface_defs.h OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/coverage_interface.h OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/dfsan_interface.h -OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/esan_interface.h OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/hwasan_interface.h OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/linux_syscall_hooks.h OLD_FILES+=usr/lib/clang/9.0.0/include/sanitizer/lsan_interface.h @@ -1416,6 +1429,7 @@ OLD_FILES+=usr/lib/clang/9.0.0/include/arm_fp16.h OLD_FILES+=usr/lib/clang/9.0.0/include/arm_neon.h OLD_FILES+=usr/lib/clang/9.0.0/include/armintr.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx2intrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/avx512bf16intrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512bitalgintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512bwintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512cdintrin.h @@ -1428,6 +1442,7 @@ OLD_FILES+=usr/lib/clang/9.0.0/include/avx512pfintrin. OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vbmi2intrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vbmiintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vbmivlintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vlbf16intrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vlbitalgintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vlbwintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vlcdintrin.h @@ -1435,7 +1450,9 @@ OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vldqintri OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vlintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vlvbmi2intrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vlvnniintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vlvp2intersectintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vnniintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vp2intersectintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vpopcntdqintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avx512vpopcntdqvlintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/avxintrin.h @@ -1448,7 +1465,9 @@ OLD_FILES+=usr/lib/clang/9.0.0/include/clwbintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/clzerointrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/cpuid.h OLD_FILES+=usr/lib/clang/9.0.0/include/emmintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/enqcmdintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/f16cintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/float.h OLD_FILES+=usr/lib/clang/9.0.0/include/fma4intrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/fmaintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/fxsrintrin.h @@ -1457,7 +1476,11 @@ OLD_FILES+=usr/lib/clang/9.0.0/include/htmintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/htmxlintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/ia32intrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/immintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/intrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/inttypes.h OLD_FILES+=usr/lib/clang/9.0.0/include/invpcidintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/iso646.h +OLD_FILES+=usr/lib/clang/9.0.0/include/limits.h OLD_FILES+=usr/lib/clang/9.0.0/include/lwpintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/lzcntintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/mm3dnow.h @@ -1468,6 +1491,7 @@ OLD_FILES+=usr/lib/clang/9.0.0/include/movdirintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/msa.h OLD_FILES+=usr/lib/clang/9.0.0/include/mwaitxintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/nmmintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/opencl-c-base.h OLD_FILES+=usr/lib/clang/9.0.0/include/opencl-c.h OLD_FILES+=usr/lib/clang/9.0.0/include/pconfigintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/pkuintrin.h @@ -1481,10 +1505,20 @@ OLD_FILES+=usr/lib/clang/9.0.0/include/s390intrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/sgxintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/shaintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/smmintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/stdalign.h +OLD_FILES+=usr/lib/clang/9.0.0/include/stdarg.h +OLD_FILES+=usr/lib/clang/9.0.0/include/stdatomic.h +OLD_FILES+=usr/lib/clang/9.0.0/include/stdbool.h +OLD_FILES+=usr/lib/clang/9.0.0/include/stddef.h +OLD_FILES+=usr/lib/clang/9.0.0/include/stdint.h +OLD_FILES+=usr/lib/clang/9.0.0/include/stdnoreturn.h OLD_FILES+=usr/lib/clang/9.0.0/include/tbmintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/tgmath.h OLD_FILES+=usr/lib/clang/9.0.0/include/tmmintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/unwind.h OLD_FILES+=usr/lib/clang/9.0.0/include/vadefs.h OLD_FILES+=usr/lib/clang/9.0.0/include/vaesintrin.h +OLD_FILES+=usr/lib/clang/9.0.0/include/varargs.h OLD_FILES+=usr/lib/clang/9.0.0/include/vecintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/vpclmulqdqintrin.h OLD_FILES+=usr/lib/clang/9.0.0/include/waitpkgintrin.h