Support Intel AMX-FP8

gcc/ChangeLog:

	* common/config/i386/cpuinfo.h
	(get_available_features): Detect amx-fp8.
	* common/config/i386/i386-common.cc
	(OPTION_MASK_ISA2_AMX_FP8_SET): New macros.
	(OPTION_MASK_ISA2_AMX_FP8_UNSET): Ditto.
	(ix86_handle_option): Handle -mamx-fp8.
	* common/config/i386/i386-cpuinfo.h (enum processor_features):
	Add FEATURE_AMX_FP8.
	* common/config/i386/i386-isas.h: Add ISA_NAME_TABLE_ENTRY for amx-fp8.
	* config.gcc: Add amxfp8intrin.h.
	* config/i386/cpuid.h (bit_AMX_FP8): New.
	* config/i386/i386-c.cc (ix86_target_macros_internal):
	Define __AMX_FP8__.
	* config/i386/i386-isa.def (AMX_FP8): Add DEF_PTA for AMX_FP8.
	* config/i386/i386-options.cc (ix86_valid_target_attribute_inner_p):
	Add new ATTR.
	* config/i386/i386.opt: Add -mamx-fp8.
	* config/i386/i386.opt.urls: Regenerated.
	* config/i386/immintrin.h: Include amxfp8intrin.h.
	* doc/extend.texi: Document -mamx-fp8.
	* doc/invoke.texi: Document -mamx-fp8.
	* doc/sourcebuild.texi: Document -mamx-fp8.
	* config/i386/amxfp8intrin.h: New file.

gcc/testsuite/ChangeLog:

	* g++.dg/other/i386-2.C: Add -mamx-fp8.
	* g++.dg/other/i386-3.C: Ditto.
	* gcc.target/i386/amx-check.h: Check for amx-fp8.
	* gcc.target/i386/amx-helper.h: Ditto.
	* gcc.target/i386/fp8-helper.h: Ditto.
	* gcc.target/i386/funcspec-56.inc: Add new target attribute.
	* gcc.target/i386/sse-12.c: Add -mamx-fp8.
	* gcc.target/i386/sse-13.c: Ditto.
	* gcc.target/i386/sse-14.c: Ditto.
	* gcc.target/i386/sse-22.c: Ditto.
	* gcc.target/i386/sse-23.c: Ditto.
	* lib/target-supports.exp: New proc.
	* gcc.target/i386/amxfp8-asmatt-1.c: New test.
	* gcc.target/i386/amxfp8-asmintel-1.c: Ditto.
	* gcc.target/i386/amxfp8-dpbf8ps-2.c: Ditto.
	* gcc.target/i386/amxfp8-dpbhf8ps-2.c: Ditto.
	* gcc.target/i386/amxfp8-dphbf8ps-2.c: Ditto.
	* gcc.target/i386/amxfp8-dphf8ps-2.c: Ditto.
	* gcc.target/i386/fp-emulation.h: Emulates NaN behaviour.

Co-authored-by: Hu, Lin1 <lin1.hu@intel.com>

4 files changed, 22 insertions, 1 deletions

diff --git a/gcc/common/config/i386/cpuinfo.h b/gcc/common/config/i386/cpuinfo.h
index 5a6aed0..b128c31 100644
--- a/gcc/common/config/i386/cpuinfo.h
+++ b/gcc/common/config/i386/cpuinfo.h
@@ -1007,6 +1007,8 @@ get_available_features (struct __processor_model *cpu_model,
 	    set_feature (FEATURE_AMX_TF32);
 	  if (eax & bit_AMX_TRANSPOSE)
 	    set_feature (FEATURE_AMX_TRANSPOSE);
+	  if (eax & bit_AMX_FP8)
+	    set_feature (FEATURE_AMX_FP8);
 	}
     }
 
diff --git a/gcc/common/config/i386/i386-common.cc b/gcc/common/config/i386/i386-common.cc
index a85b380..771bde2 100644
--- a/gcc/common/config/i386/i386-common.cc
+++ b/gcc/common/config/i386/i386-common.cc
@@ -134,6 +134,8 @@ along with GCC; see the file COPYING3.  If not see
   (OPTION_MASK_ISA2_AMX_TILE_SET | OPTION_MASK_ISA2_AMX_TF32)
 #define OPTION_MASK_ISA2_AMX_TRANSPOSE_SET \
   (OPTION_MASK_ISA2_AMX_TILE_SET | OPTION_MASK_ISA2_AMX_TRANSPOSE)
+#define OPTION_MASK_ISA2_AMX_FP8_SET \
+  (OPTION_MASK_ISA2_AMX_TILE_SET | OPTION_MASK_ISA2_AMX_FP8)
 
 /* SSE4 includes both SSE4.1 and SSE4.2. -msse4 should be the same
    as -msse4.2.  */
@@ -297,7 +299,8 @@ along with GCC; see the file COPYING3.  If not see
   (OPTION_MASK_ISA2_AMX_TILE | OPTION_MASK_ISA2_AMX_INT8_UNSET \
    | OPTION_MASK_ISA2_AMX_BF16_UNSET | OPTION_MASK_ISA2_AMX_FP16_UNSET \
    | OPTION_MASK_ISA2_AMX_COMPLEX_UNSET | OPTION_MASK_ISA2_AMX_AVX512_UNSET \
-   | OPTION_MASK_ISA2_AMX_TF32_UNSET | OPTION_MASK_ISA2_AMX_TRANSPOSE_UNSET)
+   | OPTION_MASK_ISA2_AMX_TF32_UNSET | OPTION_MASK_ISA2_AMX_TRANSPOSE_UNSET \
+   | OPTION_MASK_ISA2_AMX_FP8_UNSET)
 #define OPTION_MASK_ISA2_AMX_INT8_UNSET OPTION_MASK_ISA2_AMX_INT8
 #define OPTION_MASK_ISA2_AMX_BF16_UNSET OPTION_MASK_ISA2_AMX_BF16
 #define OPTION_MASK_ISA2_UINTR_UNSET OPTION_MASK_ISA2_UINTR
@@ -330,6 +333,7 @@ along with GCC; see the file COPYING3.  If not see
 #define OPTION_MASK_ISA2_AMX_AVX512_UNSET OPTION_MASK_ISA2_AMX_AVX512
 #define OPTION_MASK_ISA2_AMX_TF32_UNSET OPTION_MASK_ISA2_AMX_TF32
 #define OPTION_MASK_ISA2_AMX_TRANSPOSE_UNSET OPTION_MASK_ISA2_AMX_TRANSPOSE
+#define OPTION_MASK_ISA2_AMX_FP8_UNSET OPTION_MASK_ISA2_AMX_FP8
 
 /* SSE4 includes both SSE4.1 and SSE4.2.  -mno-sse4 should the same
    as -mno-sse4.1. */
@@ -1463,6 +1467,19 @@ ix86_handle_option (struct gcc_options *opts,
 	}
       return true;
 
+    case OPT_mamx_fp8:
+      if (value)
+	{
+	  opts->x_ix86_isa_flags2 |= OPTION_MASK_ISA2_AMX_FP8_SET;
+	  opts->x_ix86_isa_flags2_explicit |= OPTION_MASK_ISA2_AMX_FP8_SET;
+	}
+      else
+	{
+	  opts->x_ix86_isa_flags2 &= ~OPTION_MASK_ISA2_AMX_FP8_UNSET;
+	  opts->x_ix86_isa_flags2_explicit |= OPTION_MASK_ISA2_AMX_FP8_UNSET;
+	}
+      return true;
+
     case OPT_mfma:
       if (value)
 	{
diff --git a/gcc/common/config/i386/i386-cpuinfo.h b/gcc/common/config/i386/i386-cpuinfo.h
index f5f8ba2..68d6325 100644
--- a/gcc/common/config/i386/i386-cpuinfo.h
+++ b/gcc/common/config/i386/i386-cpuinfo.h
@@ -272,6 +272,7 @@ enum processor_features
   FEATURE_AMX_AVX512,
   FEATURE_AMX_TF32,
   FEATURE_AMX_TRANSPOSE,
+  FEATURE_AMX_FP8, 
   CPU_FEATURE_MAX
 };
 
diff --git a/gcc/common/config/i386/i386-isas.h b/gcc/common/config/i386/i386-isas.h
index 28c8d07..ccd0d19 100644
--- a/gcc/common/config/i386/i386-isas.h
+++ b/gcc/common/config/i386/i386-isas.h
@@ -194,4 +194,5 @@ ISA_NAMES_TABLE_START
   ISA_NAMES_TABLE_ENTRY("amx-tf32", FEATURE_AMX_TF32, P_NONE, "-mamx-tf32")
   ISA_NAMES_TABLE_ENTRY("amx-transpose", FEATURE_AMX_TRANSPOSE,
 			P_NONE, "-mamx-transpose")
+  ISA_NAMES_TABLE_ENTRY("amx-fp8", FEATURE_AMX_FP8, P_NONE, "-mamx-fp8")
 ISA_NAMES_TABLE_END