distrib/sets/lists/comp/md.i386
author kamil <kamil@NetBSD.org>
Thu, 23 Feb 2017 03:34:22 +0000
branchtrunk
changeset 248941 cc110d240bd0
parent 247660 0c9a6fd5d7eb
child 249209 738d4093e9bd
permissions -rw-r--r--
Introduce PT_GETDBREGS and PT_SETDBREGS in ptrace(2) on i386 and amd64 This interface is modeled after FreeBSD API with the usage. This replaced previous watchpoint API. The previous one was introduced recently in NetBSD-current and remove its spurs without any backward-compatibility. Design choices for Debug Register accessors: - exec() (TRAP_EXEC event) must remove debug registers from LWP - debug registers are only per-LWP, not per-process globally - debug registers must not be inherited after (v)forking a process - debug registers must not be inherited after forking a thread - a debugger is responsible to set global watchpoints/breakpoints with the debug registers, to achieve this PTRACE_LWP_CREATE/PTRACE_LWP_EXIT event monitoring function is designed to be used - debug register traps must generate SIGTRAP with si_code TRAP_DBREG - debugger is responsible to retrieve debug register state to distinguish the exact debug register trap (DR6 is Status Register on x86) - kernel must not remove debug register traps after triggering a trap event a debugger is responsible to detach this trap with appropriate PT_SETDBREGS call (DR7 is Control Register on x86) - debug registers must not be exposed in mcontext - userland must not be allowed to set a trap on the kernel Implementation notes on i386 and amd64: - the initial state of debug register is retrieved on boot and this value is stored in a local copy (initdbregs), this value is used to initialize dbreg context after PT_GETDBREGS - struct dbregs is stored in pcb as a pointer and by default not initialized - reserved registers (DR4-DR5, DR9-DR15) are ignored Further ideas: - restrict this interface with securelevel Tested on real hardware i386 (Intel Pentium IV) and amd64 (Intel i7). This commit enables 390 debug register ATF tests in kernel/arch/x86. All tests are passing. This commit does not cover netbsd32 compat code. Currently other interface PT_GET_SIGINFO/PT_SET_SIGINFO is required in netbsd32 compat code in order to validate reliably PT_GETDBREGS/PT_SETDBREGS. This implementation does not cover FreeBSD specific defines in their <x86/reg.h>: DBREG_DR7_LOCAL_ENABLE, DBREG_DR7_GLOBAL_ENABLE, DBREG_DR7_LEN_1 etc. These values tend to be reinvented by each tracer on its own. GNU Debugger (GDB) works with NetBSD debug registers after adding this patch: --- gdb/amd64bsd-nat.c.orig 2016-02-10 03:19:39.000000000 +0000 +++ gdb/amd64bsd-nat.c @@ -167,6 +167,10 @@ amd64bsd_target (void) #ifdef HAVE_PT_GETDBREGS +#ifndef DBREG_DRX +#define DBREG_DRX(d,x) ((d)->dr[(x)]) +#endif + static unsigned long amd64bsd_dr_get (ptid_t ptid, int regnum) { Another reason to stop introducing unpopular defines covering machine specific register macros is that these value varies across generations of the same CPU family. GDB demo: (gdb) c Continuing. Watchpoint 2: traceme Old value = 0 New value = 16 main (argc=1, argv=0x7f7fff79fe30) at test.c:8 8 printf("traceme=%d\n", traceme); (Currently the GDB interface is not reliable due to NetBSD support bugs) Sponsored by <The NetBSD Foundation>

# $NetBSD: md.i386,v 1.163 2017/02/23 03:34:22 kamil Exp $
./usr/include/clang-3.4/__wmmintrin_aes.h	comp-obsolete		obsolete
./usr/include/clang-3.4/__wmmintrin_pclmul.h	comp-obsolete		obsolete
./usr/include/clang-3.4/ammintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/avx2intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/avxintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/bmi2intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/bmiintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/emmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/f16cintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/fma4intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/fmaintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/immintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/lzcntintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/mm3dnow.h		comp-obsolete		obsolete
./usr/include/clang-3.4/mm_malloc.h		comp-obsolete		obsolete
./usr/include/clang-3.4/mmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/nmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/pmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/popcntintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/prfchwintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/rdseedintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/rtmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/shaintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/smmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/tbmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/tmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/wmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/x86intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/xmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.4/xopintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/__wmmintrin_aes.h	comp-obsolete		obsolete
./usr/include/clang-3.5/__wmmintrin_pclmul.h	comp-obsolete		obsolete
./usr/include/clang-3.5/ammintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/avx2intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/avxintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/bmi2intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/bmiintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/emmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/f16cintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/fma4intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/fmaintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/ia32intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/immintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/lzcntintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/mm3dnow.h		comp-obsolete		obsolete
./usr/include/clang-3.5/mm_malloc.h		comp-obsolete		obsolete
./usr/include/clang-3.5/mmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/nmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/pmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/popcntintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/prfchwintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/rdseedintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/rtmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/shaintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/smmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/tbmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/tmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/wmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/x86intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/xmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.5/xopintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/__wmmintrin_aes.h	comp-obsolete		obsolete
./usr/include/clang-3.6/__wmmintrin_pclmul.h	comp-obsolete		obsolete
./usr/include/clang-3.6/adxintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/ammintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/avx2intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/avx512bwintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.6/avx512erintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.6/avx512fintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/avx512vlbwintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.6/avx512vlintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.6/avxintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/bmi2intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/bmiintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/cpuid.h			comp-obsolete		obsolete
./usr/include/clang-3.6/emmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/f16cintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/fma4intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/fmaintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/ia32intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/immintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/lzcntintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/mm3dnow.h		comp-obsolete		obsolete
./usr/include/clang-3.6/mm_malloc.h		comp-obsolete		obsolete
./usr/include/clang-3.6/mmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/nmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/pmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/popcntintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/prfchwintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/rdseedintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/rtmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/shaintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/smmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/tbmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/tmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/wmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/x86intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/xmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.6/xopintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/__wmmintrin_aes.h	comp-obsolete		obsolete
./usr/include/clang-3.8/__wmmintrin_pclmul.h	comp-obsolete		obsolete
./usr/include/clang-3.8/ammintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/adxintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/avx2intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/avx512bwintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.8/avx512cdintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.8/avx512dqintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.8/avx512erintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.8/avx512fintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/avx512vlbwintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.8/avx512vldqintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.8/avx512vlintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.8/avxintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/bmi2intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/bmiintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/cpuid.h			comp-obsolete		obsolete
./usr/include/clang-3.8/emmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/f16cintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/fma4intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/fmaintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/fxsrintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/ia32intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/immintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/lzcntintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/mm3dnow.h		comp-obsolete		obsolete
./usr/include/clang-3.8/mm_malloc.h		comp-obsolete		obsolete
./usr/include/clang-3.8/mmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/nmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/pkuintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/pmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/popcntintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/prfchwintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/rdseedintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/rtmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/shaintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/smmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/tbmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/tmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/wmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/x86intrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/xmmintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/xopintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/xsavecintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/xsaveintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/xsaveoptintrin.h	comp-obsolete		obsolete
./usr/include/clang-3.8/xsavesintrin.h		comp-obsolete		obsolete
./usr/include/clang-3.8/xtestintrin.h		comp-obsolete		obsolete
./usr/include/clang-4.0/__wmmintrin_aes.h	comp-c-include		llvm
./usr/include/clang-4.0/__wmmintrin_pclmul.h	comp-c-include		llvm
./usr/include/clang-4.0/ammintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/adxintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/avx2intrin.h		comp-c-include		llvm
./usr/include/clang-4.0/avx512bwintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512cdintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512dqintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512erintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512fintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/avx512ifmaintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512ifmavlintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512pfintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512vbmiintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512vbmivlintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512vlbwintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512vlcdintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512vldqintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avx512vlintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/avxintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/bmi2intrin.h		comp-c-include		llvm
./usr/include/clang-4.0/bmiintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/clflushoptintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/cpuid.h			comp-c-include		llvm
./usr/include/clang-4.0/emmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/f16cintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/fma4intrin.h		comp-c-include		llvm
./usr/include/clang-4.0/fmaintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/fxsrintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/ia32intrin.h		comp-c-include		llvm
./usr/include/clang-4.0/immintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/lzcntintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/mm3dnow.h		comp-c-include		llvm
./usr/include/clang-4.0/mm_malloc.h		comp-c-include		llvm
./usr/include/clang-4.0/mmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/mwaitxintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/nmmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/pkuintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/pmmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/popcntintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/prfchwintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/rdseedintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/rtmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/shaintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/smmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/tbmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/tmmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/wmmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/x86intrin.h		comp-c-include		llvm
./usr/include/clang-4.0/xmmintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/xopintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/xsavecintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/xsaveintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/xsaveoptintrin.h	comp-c-include		llvm
./usr/include/clang-4.0/xsavesintrin.h		comp-c-include		llvm
./usr/include/clang-4.0/xtestintrin.h		comp-c-include		llvm
./usr/include/emmintrin.h			comp-obsolete		obsolete
./usr/include/gcc-4.1/emmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.1/mm_malloc.h		comp-obsolete		obsolete
./usr/include/gcc-4.1/mmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.1/pmmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.1/xmmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/abmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/ammintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/avxintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/bmmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/cpuid.h			comp-obsolete		obsolete
./usr/include/gcc-4.5/cross-stdarg.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/emmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/fma4intrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/ia32intrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/immintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/lwpintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/mm3dnow.h			comp-obsolete		obsolete
./usr/include/gcc-4.5/mm_malloc.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/mmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/nmmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/pmmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/popcntintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/smmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/tgmath.h			comp-obsolete		obsolete
./usr/include/gcc-4.5/tmmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/wmmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/x86intrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/xmmintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.5/xopintrin.h		comp-obsolete		obsolete
./usr/include/gcc-4.8/adxintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/ammintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/avx2intrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/avxintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/bmi2intrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/bmiintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/bmmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/cpuid.h			comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/cross-stdarg.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/emmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/f16cintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/fma4intrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/fmaintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/fxsrintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/ia32intrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/immintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/lwpintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/lzcntintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/mm3dnow.h			comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/mm_malloc.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/mmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/nmmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/pmmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/popcntintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/prfchwintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/rdseedintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/rtmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/smmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/tbmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/tgmath.h			comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/tmmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/wmmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/x86intrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/xmmintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/xopintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/xsaveintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/xsaveoptintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-4.8/xtestintrin.h		comp-c-include		gcccmds,gcc=48
./usr/include/gcc-5/adxintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/ammintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx2intrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512bwintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512cdintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512dqintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512erintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512fintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512ifmaintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512ifmavlintrin.h	comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512pfintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512vbmiintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512vbmivlintrin.h	comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512vlbwintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512vldqintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avx512vlintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/avxintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/bmi2intrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/bmiintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/bmmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/clflushoptintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/clwbintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/cpuid.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/cross-stdarg.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/emmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/f16cintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/fma4intrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/fmaintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/fxsrintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/ia32intrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/immintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/lwpintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/lzcntintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/mm3dnow.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/mm_malloc.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/mmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/mwaitxintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/nmmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/pcommitintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/pmmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/popcntintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/prfchwintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/rdseedintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/rtmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/shaintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/smmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/tbmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/tgmath.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/tmmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/wmmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/x86intrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/xmmintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/xopintrin.h			comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/xsavecintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/xsaveintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/xsaveoptintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/xsavesintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/gcc-5/xtestintrin.h		comp-c-include		gcccmds,gcc=53
./usr/include/i386				comp-c-include
./usr/include/i386/_G_config.h			comp-obsolete		obsolete
./usr/include/i386/ansi.h			comp-c-include
./usr/include/i386/aout_machdep.h		comp-c-include
./usr/include/i386/apmvar.h			comp-c-include
./usr/include/i386/asm.h			comp-c-include
./usr/include/i386/atomic.h			comp-obsolete		obsolete
./usr/include/i386/autoconf.h			comp-obsolete		obsolete
./usr/include/i386/bioscall.h			comp-c-include
./usr/include/i386/bootinfo.h			comp-c-include
./usr/include/i386/bswap.h			comp-c-include
./usr/include/i386/bus.h			comp-obsolete		obsolete
./usr/include/i386/byte_swap.h			comp-c-include
./usr/include/i386/cdefs.h			comp-c-include
./usr/include/i386/conf.h			comp-obsolete		obsolete
./usr/include/i386/cpu.h			comp-c-include
./usr/include/i386/cpu_rng.h			comp-c-include
./usr/include/i386/cpufunc.h			comp-obsolete		obsolete
./usr/include/i386/cputypes.h			comp-c-include
./usr/include/i386/db_machdep.h			comp-obsolete		obsolete
./usr/include/i386/disklabel.h			comp-c-include
./usr/include/i386/elf_machdep.h		comp-c-include
./usr/include/i386/endian.h			comp-c-include
./usr/include/i386/endian_machdep.h		comp-c-include
./usr/include/i386/fenv.h			comp-c-include
./usr/include/i386/float.h			comp-c-include
./usr/include/i386/frame.h			comp-c-include
./usr/include/i386/freebsd_machdep.h		comp-c-include
./usr/include/i386/gdt.h			comp-c-include
./usr/include/i386/ibcs2_machdep.h		comp-c-include
./usr/include/i386/ieee.h			comp-c-include
./usr/include/i386/ieeefp.h			comp-c-include
./usr/include/i386/int_const.h			comp-c-include
./usr/include/i386/int_fmtio.h			comp-c-include
./usr/include/i386/int_limits.h			comp-c-include
./usr/include/i386/int_mwgwtypes.h		comp-c-include
./usr/include/i386/int_types.h			comp-c-include
./usr/include/i386/intr.h			comp-c-include
./usr/include/i386/intrdefs.h			comp-c-include
./usr/include/i386/joystick.h			comp-c-include
./usr/include/i386/kcore.h			comp-c-include
./usr/include/i386/limits.h			comp-c-include
./usr/include/i386/loadfile_machdep.h		comp-obsolete		obsolete
./usr/include/i386/lock.h			comp-c-include
./usr/include/i386/math.h			comp-c-include
./usr/include/i386/mcontext.h			comp-c-include
./usr/include/i386/mouse.h			comp-obsolete		obsolete
./usr/include/i386/mtrr.h			comp-c-include
./usr/include/i386/multiboot.h			comp-c-include
./usr/include/i386/mutex.h			comp-c-include
./usr/include/i386/npx.h			comp-obsolete		obsolete
./usr/include/i386/param.h			comp-c-include
./usr/include/i386/pcb.h			comp-c-include
./usr/include/i386/pccons.h			comp-obsolete		obsolete
./usr/include/i386/pio.h			comp-c-include
./usr/include/i386/pmap.h			comp-c-include
./usr/include/i386/pmc.h			comp-c-include
./usr/include/i386/proc.h			comp-c-include
./usr/include/i386/profile.h			comp-c-include
./usr/include/i386/psl.h			comp-c-include
./usr/include/i386/pte.h			comp-c-include
./usr/include/i386/ptrace.h			comp-c-include
./usr/include/i386/reg.h			comp-c-include
./usr/include/i386/rwlock.h			comp-c-include
./usr/include/i386/segments.h			comp-c-include
./usr/include/i386/setjmp.h			comp-c-include
./usr/include/i386/signal.h			comp-c-include
./usr/include/i386/sljit_machdep.h		comp-c-include
./usr/include/i386/sljitarch.h			comp-obsolete		obsolete
./usr/include/i386/specialreg.h			comp-c-include
./usr/include/i386/spkr.h			comp-c-include
./usr/include/i386/stdarg.h			comp-obsolete		obsolete
./usr/include/i386/svr4_machdep.h		comp-c-include
./usr/include/i386/sysarch.h			comp-c-include
./usr/include/i386/trap.h			comp-c-include
./usr/include/i386/tss.h			comp-c-include
./usr/include/i386/types.h			comp-c-include
./usr/include/i386/varargs.h			comp-obsolete		obsolete
./usr/include/i386/vm86.h			comp-c-include
./usr/include/i386/vmparam.h			comp-c-include
./usr/include/i386/wchar_limits.h		comp-c-include
./usr/include/ieeefp.h				comp-c-include
./usr/include/mm_malloc.h			comp-obsolete		obsolete
./usr/include/mmintrin.h			comp-obsolete		obsolete
./usr/include/pmc.h				comp-c-include
./usr/include/pmmintrin.h			comp-obsolete		obsolete
./usr/include/x86				comp-c-include
./usr/include/x86/aout_machdep.h		comp-c-include
./usr/include/x86/autoconf.h			comp-obsolete		obsolete
./usr/include/x86/bootinfo.h			comp-c-include
./usr/include/x86/bus.h				comp-obsolete		obsolete
./usr/include/x86/cacheinfo.h			comp-c-include
./usr/include/x86/cpu.h				comp-c-include
./usr/include/x86/cpu_extended_state.h		comp-c-include
./usr/include/x86/cpu_rng.h			comp-c-include
./usr/include/x86/cpu_ucode.h			comp-c-include
./usr/include/x86/cputypes.h			comp-c-include
./usr/include/x86/cpuvar.h			comp-c-include
./usr/include/x86/dbregs.h			comp-obsolete		obsolete
./usr/include/x86/float.h			comp-c-include
./usr/include/x86/fpu.h				comp-c-include
./usr/include/x86/ieee.h			comp-c-include
./usr/include/x86/ieeefp.h			comp-c-include
./usr/include/x86/intr.h			comp-c-include
./usr/include/x86/intrdefs.h			comp-c-include
./usr/include/x86/lock.h			comp-c-include
./usr/include/x86/math.h			comp-c-include
./usr/include/x86/mtrr.h			comp-c-include
./usr/include/x86/mutex.h			comp-c-include
./usr/include/x86/pio.h				comp-c-include
./usr/include/x86/pmap.h			comp-c-include
./usr/include/x86/pmap_pv.h			comp-c-include
./usr/include/x86/psl.h				comp-c-include
./usr/include/x86/pte.h				comp-c-include
./usr/include/x86/rwlock.h			comp-c-include
./usr/include/x86/specialreg.h			comp-c-include
./usr/include/x86/sysarch.h			comp-c-include
./usr/include/x86/trap.h			comp-c-include
./usr/include/x86/via_padlock.h			comp-c-include
./usr/include/xen				comp-c-include
./usr/include/xen/xenio.h			comp-c-include
./usr/include/xen/xenio3.h			comp-c-include
./usr/include/xmmintrin.h			comp-obsolete		obsolete
./usr/lib/libi386.a				comp-c-lib
./usr/lib/libi386_p.a				comp-c-proflib		profile
./usr/lib/libi386_pic.a				comp-c-piclib		pic,picinstall
./usr/lib/libm387.a				comp-c-lib
./usr/lib/libm387_p.a				comp-c-proflib		profile
./usr/lib/libm387_pic.a				comp-c-piclib		pic,picinstall
./usr/lib/libpmc.a				comp-c-lib
./usr/lib/libpmc_p.a				comp-c-proflib		profile
./usr/lib/libpmc_pic.a				comp-c-piclib		pic,picinstall
./usr/libdata/lint/llib-li386.ln		comp-c-lintlib		lint
./usr/libdata/lint/llib-lpmc.ln			comp-c-lintlib		lint