From 41f8d1fc011e0da012bd00624fd2668da83d9f31 Mon Sep 17 00:00:00 2001 From: Andi Kleen Date: Fri, 9 Nov 2018 05:42:43 +0000 Subject: [PATCH] Add PTWRITE builtins for x86 Add builtins/intrinsics for PTWRITE. PTWRITE is a new instruction on Intel Gemini Lake/ Goldmont Plus that allows to write values into the Processor Trace log. This allows very light weight instrumentation of programs. The intrinsics are compatible to icc. Automatically enabled for Goldmont Plus. gcc/: 2018-11-08 Andi Kleen * common/config/i386/i386-common.c (OPTION_MASK_ISA_PTWRITE_SET): New. (OPTION_MASK_ISA_PTWRITE_UNSET): New. (ix86_handle_option): Handle OPT_mptwrite. * config/i386/cpuid.h (bit_PTWRITE): Add. * config/i386/driver-i386.c (host_detect_local_cpu): Detect ptwrite. * config/i386/i386-builtin.def (BDESC): Add ptwrite32/64. * config/i386/i386-c.c (ix86_target_macros_internal): Define __PTWRITE__. * config/i386/i386.c (ix86_target_string): Handle ptwrite. (ix86_option_override_internal): Handle PTA_PTWRITE. (ix86_valid_target_attribute_inner_p): Define ptwrite. (def_builtin2): Force UINT64 to be 64bit only. * config/i386/i386.h (TARGET_PTWRITE): Add. (TARGET_PTWRITE_P): Add. (PTA_PTWRITE): Add. * config/i386/i386.md: Define ptwrite. * config/i386/i386.opt: Add -mptwrite. * config/i386/immintrin.h (_ptwrite64): Add. (_ptwrite32): Add * doc/extend.texi: Document __builtin_ia32_ptwrite*. * doc/invoke.texi: Document -mptwrite. gcc/testsuite/: 2018-11-08 Andi Kleen * gcc.target/i386/ptwrite1.c: New test. * gcc.target/i386/ptwrite2.c: New test. From-SVN: r265947 --- gcc/ChangeLog | 23 ++++++++++++++++++ gcc/common/config/i386/i386-common.c | 15 ++++++++++++ gcc/config/i386/cpuid.h | 4 ++++ gcc/config/i386/driver-i386.c | 12 ++++++++++ gcc/config/i386/i386-builtin.def | 4 ++++ gcc/config/i386/i386-c.c | 2 ++ gcc/config/i386/i386.c | 9 ++++++- gcc/config/i386/i386.h | 5 +++- gcc/config/i386/i386.md | 10 ++++++++ gcc/config/i386/i386.opt | 4 ++++ gcc/config/i386/immintrin.h | 26 ++++++++++++++++++++ gcc/doc/extend.texi | 9 +++++++ gcc/doc/invoke.texi | 7 ++++-- gcc/testsuite/ChangeLog | 5 ++++ gcc/testsuite/gcc.target/i386/ptwrite1.c | 30 ++++++++++++++++++++++++ gcc/testsuite/gcc.target/i386/ptwrite2.c | 14 +++++++++++ 16 files changed, 175 insertions(+), 4 deletions(-) create mode 100644 gcc/testsuite/gcc.target/i386/ptwrite1.c create mode 100644 gcc/testsuite/gcc.target/i386/ptwrite2.c diff --git a/gcc/ChangeLog b/gcc/ChangeLog index 85788749b46d..8961e8034e35 100644 --- a/gcc/ChangeLog +++ b/gcc/ChangeLog @@ -1,3 +1,26 @@ +2018-11-08 Andi Kleen + + * common/config/i386/i386-common.c (OPTION_MASK_ISA_PTWRITE_SET): New. + (OPTION_MASK_ISA_PTWRITE_UNSET): New. + (ix86_handle_option): Handle OPT_mptwrite. + * config/i386/cpuid.h (bit_PTWRITE): Add. + * config/i386/driver-i386.c (host_detect_local_cpu): Detect ptwrite. + * config/i386/i386-builtin.def (BDESC): Add ptwrite32/64. + * config/i386/i386-c.c (ix86_target_macros_internal): Define __PTWRITE__. + * config/i386/i386.c (ix86_target_string): Handle ptwrite. + (ix86_option_override_internal): Handle PTA_PTWRITE. + (ix86_valid_target_attribute_inner_p): Define ptwrite. + (def_builtin2): Force UINT64 to be 64bit only. + * config/i386/i386.h (TARGET_PTWRITE): Add. + (TARGET_PTWRITE_P): Add. + (PTA_PTWRITE): Add. + * config/i386/i386.md: Define ptwrite. + * config/i386/i386.opt: Add -mptwrite. + * config/i386/immintrin.h (_ptwrite64): Add. + (_ptwrite32): Add + * doc/extend.texi: Document __builtin_ia32_ptwrite*. + * doc/invoke.texi: Document -mptwrite. + 2018-11-08 Peter Bergner PR rtl-optimization/87600 diff --git a/gcc/common/config/i386/i386-common.c b/gcc/common/config/i386/i386-common.c index ff13ea5f69f3..1017147599c5 100644 --- a/gcc/common/config/i386/i386-common.c +++ b/gcc/common/config/i386/i386-common.c @@ -140,6 +140,7 @@ along with GCC; see the file COPYING3. If not see #define OPTION_MASK_ISA_FSGSBASE_SET OPTION_MASK_ISA_FSGSBASE #define OPTION_MASK_ISA_RDRND_SET OPTION_MASK_ISA_RDRND +#define OPTION_MASK_ISA_PTWRITE_SET OPTION_MASK_ISA_PTWRITE #define OPTION_MASK_ISA_F16C_SET \ (OPTION_MASK_ISA_F16C | OPTION_MASK_ISA_AVX_SET) #define OPTION_MASK_ISA_MWAITX_SET OPTION_MASK_ISA_MWAITX @@ -267,6 +268,7 @@ along with GCC; see the file COPYING3. If not see #define OPTION_MASK_ISA_FSGSBASE_UNSET OPTION_MASK_ISA_FSGSBASE #define OPTION_MASK_ISA_RDRND_UNSET OPTION_MASK_ISA_RDRND +#define OPTION_MASK_ISA_PTWRITE_UNSET OPTION_MASK_ISA_PTWRITE #define OPTION_MASK_ISA_F16C_UNSET OPTION_MASK_ISA_F16C #define OPTION_MASK_ISA_GENERAL_REGS_ONLY_UNSET \ @@ -1125,6 +1127,19 @@ ix86_handle_option (struct gcc_options *opts, } return true; + case OPT_mptwrite: + if (value) + { + opts->x_ix86_isa_flags2 |= OPTION_MASK_ISA_PTWRITE_SET; + opts->x_ix86_isa_flags2_explicit |= OPTION_MASK_ISA_PTWRITE_SET; + } + else + { + opts->x_ix86_isa_flags2 &= ~OPTION_MASK_ISA_PTWRITE_UNSET; + opts->x_ix86_isa_flags2_explicit |= OPTION_MASK_ISA_PTWRITE_UNSET; + } + return true; + case OPT_mf16c: if (value) { diff --git a/gcc/config/i386/cpuid.h b/gcc/config/i386/cpuid.h index 7e9e2d153dca..2e6d4a55602b 100644 --- a/gcc/config/i386/cpuid.h +++ b/gcc/config/i386/cpuid.h @@ -126,6 +126,10 @@ #define bit_XSAVEC (1 << 1) #define bit_XSAVES (1 << 3) +/* PT sub leaf (%eax == 14, %ecx == 0) */ +/* %ebx */ +#define bit_PTWRITE (1 << 4) + /* Signatures for different CPU implementations as returned in uses of cpuid with level 0. */ #define signature_AMD_ebx 0x68747541 diff --git a/gcc/config/i386/driver-i386.c b/gcc/config/i386/driver-i386.c index 95ba393cee90..e910038d11d5 100644 --- a/gcc/config/i386/driver-i386.c +++ b/gcc/config/i386/driver-i386.c @@ -427,6 +427,8 @@ const char *host_detect_local_cpu (int argc, const char **argv) unsigned int has_waitpkg = 0; unsigned int has_cldemote = 0; + unsigned int has_ptwrite = 0; + bool arch; unsigned int l2sizekb = 0; @@ -542,6 +544,13 @@ const char *host_detect_local_cpu (int argc, const char **argv) has_xsaves = eax & bit_XSAVES; } + if (max_level >= 0x14) + { + __cpuid_count (0x14, 0, eax, ebx, ecx, edx); + + has_ptwrite = ebx & bit_PTWRITE; + } + /* Check cpuid level of extended features. */ __cpuid (0x80000000, ext_level, ebx, ecx, edx); @@ -1129,6 +1138,8 @@ const char *host_detect_local_cpu (int argc, const char **argv) const char *movdir64b = has_movdir64b ? " -mmovdir64b" : " -mno-movdir64b"; const char *waitpkg = has_waitpkg ? " -mwaitpkg" : " -mno-waitpkg"; const char *cldemote = has_cldemote ? " -mcldemote" : " -mno-cldemote"; + const char *ptwrite = has_ptwrite ? " -mptwrite" : " -mno-ptwrite"; + options = concat (options, mmx, mmx3dnow, sse, sse2, sse3, ssse3, sse4a, cx16, sahf, movbe, aes, sha, pclmul, popcnt, abm, lwp, fma, fma4, xop, bmi, sgx, bmi2, @@ -1142,6 +1153,7 @@ const char *host_detect_local_cpu (int argc, const char **argv) clwb, mwaitx, clzero, pku, rdpid, gfni, shstk, avx512vbmi2, avx512vnni, vaes, vpclmulqdq, avx512bitalg, movdiri, movdir64b, waitpkg, cldemote, + ptwrite, NULL); } diff --git a/gcc/config/i386/i386-builtin.def b/gcc/config/i386/i386-builtin.def index f85acee85bb1..e80abe4ace95 100644 --- a/gcc/config/i386/i386-builtin.def +++ b/gcc/config/i386/i386-builtin.def @@ -2887,6 +2887,10 @@ BDESC_FIRST (special_args2, SPECIAL_ARGS2, OPTION_MASK_ISA_WBNOINVD, CODE_FOR_wbnoinvd, "__builtin_ia32_wbnoinvd", IX86_BUILTIN_WBNOINVD, UNKNOWN, (int) VOID_FTYPE_VOID) BDESC (OPTION_MASK_ISA_MOVDIR64B, CODE_FOR_nothing, "__builtin_ia32_movdir64b", IX86_BUILTIN_MOVDIR64B, UNKNOWN, (int) VOID_FTYPE_PVOID_PCVOID) +/* PTWRITE */ +BDESC (OPTION_MASK_ISA_PTWRITE, CODE_FOR_ptwritesi, "__builtin_ia32_ptwrite32", IX86_BUILTIN_PTWRITE32, UNKNOWN, (int) VOID_FTYPE_UNSIGNED) +BDESC (OPTION_MASK_ISA_PTWRITE, CODE_FOR_ptwritedi, "__builtin_ia32_ptwrite64", IX86_BUILTIN_PTWRITE64, UNKNOWN, (int) VOID_FTYPE_UINT64) + BDESC_END (SPECIAL_ARGS2, MULTI_ARG) /* FMA4 and XOP. */ diff --git a/gcc/config/i386/i386-c.c b/gcc/config/i386/i386-c.c index a11be6fb8b6f..16c6a2d5503e 100644 --- a/gcc/config/i386/i386-c.c +++ b/gcc/config/i386/i386-c.c @@ -539,6 +539,8 @@ ix86_target_macros_internal (HOST_WIDE_INT isa_flag, def_or_undef (parse_in, "__WAITPKG__"); if (isa_flag2 & OPTION_MASK_ISA_CLDEMOTE) def_or_undef (parse_in, "__CLDEMOTE__"); + if (isa_flag2 & OPTION_MASK_ISA_PTWRITE) + def_or_undef (parse_in, "__PTWRITE__"); if (TARGET_IAMCU) { def_or_undef (parse_in, "__iamcu"); diff --git a/gcc/config/i386/i386.c b/gcc/config/i386/i386.c index ae8971c82b0a..77dec0f21b35 100644 --- a/gcc/config/i386/i386.c +++ b/gcc/config/i386/i386.c @@ -2796,7 +2796,8 @@ ix86_target_string (HOST_WIDE_INT isa, HOST_WIDE_INT isa2, { "-mmwaitx", OPTION_MASK_ISA_MWAITX }, { "-mmovdir64b", OPTION_MASK_ISA_MOVDIR64B }, { "-mwaitpkg", OPTION_MASK_ISA_WAITPKG }, - { "-mcldemote", OPTION_MASK_ISA_CLDEMOTE } + { "-mcldemote", OPTION_MASK_ISA_CLDEMOTE }, + { "-mptwrite", OPTION_MASK_ISA_PTWRITE } }; static struct ix86_target_opts isa_opts[] = { @@ -3878,6 +3879,9 @@ ix86_option_override_internal (bool main_args_p, if (((processor_alias_table[i].flags & PTA_WBNOINVD) != 0) && !(opts->x_ix86_isa_flags2_explicit & OPTION_MASK_ISA_WBNOINVD)) opts->x_ix86_isa_flags2 |= OPTION_MASK_ISA_WBNOINVD; + if (((processor_alias_table[i].flags & PTA_PTWRITE) != 0) + && !(opts->x_ix86_isa_flags2_explicit & OPTION_MASK_ISA_PTWRITE)) + opts->x_ix86_isa_flags2 |= OPTION_MASK_ISA_PTWRITE; if ((processor_alias_table[i].flags & (PTA_PREFETCH_SSE | PTA_SSE)) != 0) @@ -5080,6 +5084,7 @@ ix86_valid_target_attribute_inner_p (tree args, char *p_strings[], IX86_ATTR_ISA ("movdir64b", OPT_mmovdir64b), IX86_ATTR_ISA ("waitpkg", OPT_mwaitpkg), IX86_ATTR_ISA ("cldemote", OPT_mcldemote), + IX86_ATTR_ISA ("ptwrite", OPT_mptwrite), /* enum options */ IX86_ATTR_ENUM ("fpmath=", OPT_mfpmath_), @@ -30183,6 +30188,8 @@ def_builtin2 (HOST_WIDE_INT mask, const char *name, tree decl = NULL_TREE; ix86_builtins_isa[(int) code].isa2 = mask; + if (tcode == VOID_FTYPE_UINT64) + ix86_builtins_isa[(int) code].isa = OPTION_MASK_ISA_64BIT; if (mask == 0 || (mask & ix86_isa_flags2) != 0 diff --git a/gcc/config/i386/i386.h b/gcc/config/i386/i386.h index 58caab2bb55b..3a26644b4900 100644 --- a/gcc/config/i386/i386.h +++ b/gcc/config/i386/i386.h @@ -191,6 +191,8 @@ see the files COPYING3 and COPYING.RUNTIME respectively. If not, see #define TARGET_WAITPKG_P(x) TARGET_ISA_WAITPKG_P(x) #define TARGET_CLDEMOTE TARGET_ISA_CLDEMOTE #define TARGET_CLDEMOTE_P(x) TARGET_ISA_CLDEMOTE_P(x) +#define TARGET_PTWRITE TARGET_ISA_PTWRITE +#define TARGET_PTWRITE_P(x) TARGET_ISA_PTWRITE_P(x) #define TARGET_LP64 TARGET_ABI_64 #define TARGET_LP64_P(x) TARGET_ABI_64_P(x) @@ -2356,6 +2358,7 @@ const wide_int_bitmask PTA_RDPID (0, HOST_WIDE_INT_1U << 6); const wide_int_bitmask PTA_PCONFIG (0, HOST_WIDE_INT_1U << 7); const wide_int_bitmask PTA_WBNOINVD (0, HOST_WIDE_INT_1U << 8); const wide_int_bitmask PTA_WAITPKG (0, HOST_WIDE_INT_1U << 9); +const wide_int_bitmask PTA_PTWRITE (0, HOST_WIDE_INT_1U << 10); const wide_int_bitmask PTA_CORE2 = PTA_64BIT | PTA_MMX | PTA_SSE | PTA_SSE2 | PTA_SSE3 | PTA_SSSE3 | PTA_CX16 | PTA_FXSR; @@ -2391,7 +2394,7 @@ const wide_int_bitmask PTA_GOLDMONT = PTA_SILVERMONT | PTA_SHA | PTA_XSAVE | PTA_RDSEED | PTA_XSAVEC | PTA_XSAVES | PTA_CLFLUSHOPT | PTA_XSAVEOPT | PTA_FSGSBASE; const wide_int_bitmask PTA_GOLDMONT_PLUS = PTA_GOLDMONT | PTA_RDPID - | PTA_SGX; + | PTA_SGX | PTA_PTWRITE; const wide_int_bitmask PTA_TREMONT = PTA_GOLDMONT_PLUS | PTA_CLWB | PTA_GFNI; const wide_int_bitmask PTA_KNM = PTA_KNL | PTA_AVX5124VNNIW diff --git a/gcc/config/i386/i386.md b/gcc/config/i386/i386.md index 8061a2383f97..44db8ac954cf 100644 --- a/gcc/config/i386/i386.md +++ b/gcc/config/i386/i386.md @@ -292,6 +292,8 @@ ;; For Speculation Barrier support UNSPECV_SPECULATION_BARRIER + + UNSPECV_PTWRITE ]) ;; Constants to represent rounding modes in the ROUND instruction @@ -19498,6 +19500,14 @@ [(set_attr "type" "other") (set_attr "prefix_extra" "2")]) +(define_insn "ptwrite" + [(unspec_volatile [(match_operand:SWI48 0 "register_operand" "r")] + UNSPECV_PTWRITE)] + "TARGET_PTWRITE" + "ptwrite\t%0" + [(set_attr "type" "other") + (set_attr "prefix_extra" "2")]) + (define_insn "rdrand_1" [(set (match_operand:SWI248 0 "register_operand" "=r") (unspec_volatile:SWI248 [(const_int 0)] UNSPECV_RDRAND)) diff --git a/gcc/config/i386/i386.opt b/gcc/config/i386/i386.opt index e7fbf9b6f994..1705815a2ec5 100644 --- a/gcc/config/i386/i386.opt +++ b/gcc/config/i386/i386.opt @@ -785,6 +785,10 @@ mwbnoinvd Target Report Mask(ISA_WBNOINVD) Var(ix86_isa_flags2) Save Support WBNOINVD built-in functions and code generation. +mptwrite +Target Report Mask(ISA_PTWRITE) Var(ix86_isa_flags2) Save +Support PTWRITE built-in functions and code generation. + msgx Target Report Mask(ISA_SGX) Var(ix86_isa_flags2) Save Support SGX built-in functions and code generation. diff --git a/gcc/config/i386/immintrin.h b/gcc/config/i386/immintrin.h index 344e92c745a7..b52ab91b4d50 100644 --- a/gcc/config/i386/immintrin.h +++ b/gcc/config/i386/immintrin.h @@ -251,4 +251,30 @@ _rdrand64_step (unsigned long long *__P) #endif /* __x86_64__ */ +#ifndef __PTWRITE__ +#pragma GCC push_options +#pragma GCC target("ptwrite") +#define __DISABLE_PTWRITE__ +#endif + +#ifdef __x86_64__ +extern __inline void +__attribute__((__gnu_inline__, __always_inline__, __artificial__)) +_ptwrite64 (unsigned long long __B) +{ + __builtin_ia32_ptwrite64 (__B); +} +#endif /* __x86_64__ */ + +extern __inline void +__attribute__((__gnu_inline__, __always_inline__, __artificial__)) +_ptwrite32 (unsigned __B) +{ + __builtin_ia32_ptwrite32 (__B); +} +#ifdef __DISABLE_PTWRITE__ +#undef __DISABLE_PTWRITE__ +#pragma GCC pop_options +#endif /* __DISABLE_PTWRITE__ */ + #endif /* _IMMINTRIN_H_INCLUDED */ diff --git a/gcc/doc/extend.texi b/gcc/doc/extend.texi index dc8fc6e2c4ac..985d0418aa47 100644 --- a/gcc/doc/extend.texi +++ b/gcc/doc/extend.texi @@ -21335,6 +21335,15 @@ unsigned int __builtin_ia32_rdrand32_step (unsigned int *) unsigned int __builtin_ia32_rdrand64_step (unsigned long long *) @end smallexample +The following built-in function is available when @option{-mptwrite} is +used. All of them generate the machine instruction that is part of the +name. + +@smallexample +void __builtin_ia32_ptwrite32 (unsigned) +void __builtin_ia32_ptwrite64 (unsigned long long) +@end smallexample + The following built-in functions are available when @option{-msse4a} is used. All of them generate the machine instruction that is part of the name. diff --git a/gcc/doc/invoke.texi b/gcc/doc/invoke.texi index 8762f3f7bc30..b8d55cfa8884 100644 --- a/gcc/doc/invoke.texi +++ b/gcc/doc/invoke.texi @@ -1286,7 +1286,7 @@ See RS/6000 and PowerPC Options. -mmmx -msse -msse2 -msse3 -mssse3 -msse4.1 -msse4.2 -msse4 -mavx @gol -mavx2 -mavx512f -mavx512pf -mavx512er -mavx512cd -mavx512vl @gol -mavx512bw -mavx512dq -mavx512ifma -mavx512vbmi -msha -maes @gol --mpclmul -mfsgsbase -mrdrnd -mf16c -mfma -mpconfig -mwbnoinvd @gol +-mpclmul -mfsgsbase -mrdrnd -mf16c -mfma -mpconfig -mwbnoinvd -mptwrite @gol -mprefetchwt1 -mclflushopt -mxsavec -mxsaves @gol -msse4a -m3dnow -m3dnowa -mpopcnt -mabm -mbmi -mtbm -mfma4 -mxop @gol -mlzcnt -mbmi2 -mfxsr -mxsave -mxsaveopt -mrtm -mlwp @gol @@ -27880,6 +27880,9 @@ preferred alignment to @option{-mpreferred-stack-boundary=2}. @itemx -mfsgsbase @opindex mfsgsbase @need 200 +@itemx -mptwrite +@opindex mptwrite +@need 200 @itemx -mrdrnd @opindex mrdrnd @need 200 @@ -27988,7 +27991,7 @@ preferred alignment to @option{-mpreferred-stack-boundary=2}. @opindex mcldemote These switches enable the use of instructions in the MMX, SSE, SSE2, SSE3, SSSE3, SSE4.1, AVX, AVX2, AVX512F, AVX512PF, AVX512ER, AVX512CD, -SHA, AES, PCLMUL, FSGSBASE, RDRND, F16C, FMA, SSE4A, FMA4, XOP, LWP, ABM, +SHA, AES, PCLMUL, FSGSBASE, PTWRITE, RDRND, F16C, FMA, SSE4A, FMA4, XOP, LWP, ABM, AVX512VL, AVX512BW, AVX512DQ, AVX512IFMA, AVX512VBMI, BMI, BMI2, VAES, WAITPKG, FXSR, XSAVE, XSAVEOPT, LZCNT, RTM, MWAITX, PKU, IBT, SHSTK, AVX512VBMI2, GFNI, VPCLMULQDQ, AVX512BITALG, MOVDIRI, MOVDIR64B, diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog index b300e5f0d957..e5641fe5a89a 100644 --- a/gcc/testsuite/ChangeLog +++ b/gcc/testsuite/ChangeLog @@ -1,3 +1,8 @@ +2018-11-08 Andi Kleen + + * gcc.target/i386/ptwrite1.c: New test. + * gcc.target/i386/ptwrite2.c: New test. + 2018-11-08 Jerry DeLisle PR libfortran/78351 diff --git a/gcc/testsuite/gcc.target/i386/ptwrite1.c b/gcc/testsuite/gcc.target/i386/ptwrite1.c new file mode 100644 index 000000000000..e09028ed428c --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/ptwrite1.c @@ -0,0 +1,30 @@ +/* { dg-do compile } */ +/* { dg-options "-O2 -mptwrite" } */ +/* { dg-final { scan-assembler "ptwrite" } } */ + +void ptwrite1(int a) +{ + __builtin_ia32_ptwrite32 (a); +} + +#ifdef __x86_64__ +void ptwrite2(unsigned long b) +{ + __builtin_ia32_ptwrite64 (b); +} + +void ptwrite3(unsigned char b) +{ + __builtin_ia32_ptwrite64 (b); +} + +void ptwrite4(unsigned short b) +{ + __builtin_ia32_ptwrite64 (b); +} +#endif + +void ptwrite5(unsigned short b) +{ + __builtin_ia32_ptwrite32 (b); +} diff --git a/gcc/testsuite/gcc.target/i386/ptwrite2.c b/gcc/testsuite/gcc.target/i386/ptwrite2.c new file mode 100644 index 000000000000..bd144fc07793 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/ptwrite2.c @@ -0,0 +1,14 @@ +/* { dg-do compile } */ +/* { dg-options "-O2 -mptwrite " } */ +/* { dg-final { scan-assembler "ptwrite\[^\n\r\]+r" } } */ +/* { dg-final { scan-assembler "ptwrite\[^\n\r\]+e" } } */ + +#include + +void ptwrite1(void) +{ + _ptwrite32 (1); +#ifdef __x86_64__ + _ptwrite64 (2); +#endif +} -- 2.47.2