Support Intel AMX-TRANSPOSE

gcc/ChangeLog:

	* common/config/i386/cpuinfo.h (get_available_features):
	Detect AMX-TRANSPOSE.
	* common/config/i386/i386-common.cc
	(OPTION_MASK_ISA2_AMX_TRANSPOSE_SET,
	OPTION_MASK_ISA2_AMX_TRANSPOSE_UNSET): New.
	(ix86_handle_option): Handle -mamx-transpose.
	* common/config/i386/i386-cpuinfo.h (enum processor_features):
	Add FEATURE_AMX_TRANSPOSE.
	* common/config/i386/i386-isas.h: Add ISA_NAME_TABLE_ENTRY for
	amx-transpose.
	* config.gcc: Add amxtransposeintrin.h.
	* config/i386/cpuid.h (bit_AMX_TRANSPOSE): New.
	* config/i386/i386-c.cc (ix86_target_macros_internal): Define
	__AMX_TRANSPOSE__.
	* config/i386/i386-isa.def (AMX_TRANSPOSE): Add
	DEF_PTA(AMX_TRANSPOSE).
	* config/i386/i386-options.cc (ix86_valid_target_attribute_inner_p):
	Handle amx-transpose.
	* config/i386/i386.opt: Add option -mamx-transpose.
	* config/i386/i386.opt.urls: Regenerated.
	* config/i386/immintrin.h: Include amxtransposeintrin.h.
	* doc/extend.texi: Document amx-transpose.
	* doc/invoke.texi: Document -mamx-transpose.
	* doc/sourcebuild.texi: Document target amx-transpose.
	* config/i386/amxtransposeintrin.h: New file.

gcc/testsuite/ChangeLog:

	* g++.dg/other/i386-2.C: Add -mamx-transpose.
	* g++.dg/other/i386-3.C: Ditto.
	* gcc.target/i386/amx-check.h: Add new check for amx-transpose.
	(__tilepair): New.
	(zero_pair_tile_src): New.
	(check_pair_tile_register): New.
	* gcc.target/i386/funcspec-56.inc: Add new target attribute.
	* gcc.target/i386/amx-helper.h: Add amx-transpose support.
	(init_pair_tile_src): New function.
	* gcc.target/i386/sse-12.c: Add -mamx-tranpose.
	* gcc.target/i386/sse-13.c: Ditto.
	* gcc.target/i386/sse-14.c: Ditto.
	* gcc.target/i386/sse-22.c: Add amx-transpose.
	* gcc.target/i386/sse-23.c: Ditto.
	* lib/target-supports.exp (check_effective_target_amx_transposed): New.
	* gcc.target/i386/amxtranspose-asmatt-1.c: New test.
	* gcc.target/i386/amxtranspose-asmintel-1.c: Ditto.
	* gcc.target/i386/amxtranspose-2rpntlvw-2.c: Ditto.
	* gcc.target/i386/amxtranspose-conjtcmmimfp16ps-2.c: Ditto.
	* gcc.target/i386/amxtranspose-conjtfp16-2.c: Ditto.
	* gcc.target/i386/amxtranspose-tcmmimfp16ps-2.c: Ditto.
	* gcc.target/i386/amxtranspose-tcmmrlfp16ps-2.c: Ditto.
	* gcc.target/i386/amxtranspose-tdpbf16ps-2.c: Ditto.
	* gcc.target/i386/amxtranspose-tdpfp16ps-2.c: Ditto.
	* gcc.target/i386/amxtranspose-tmmultf32ps-2.c: Ditto.
	* gcc.target/i386/amxtranspose-transposed-2.c: Ditto.

4 files changed, 23 insertions, 1 deletions

diff --git a/gcc/common/config/i386/cpuinfo.h b/gcc/common/config/i386/cpuinfo.h
index 5d0a644..5a6aed0 100644
--- a/gcc/common/config/i386/cpuinfo.h
+++ b/gcc/common/config/i386/cpuinfo.h
@@ -1005,6 +1005,8 @@ get_available_features (struct __processor_model *cpu_model,
 	    set_feature (FEATURE_AMX_AVX512);
 	  if (eax & bit_AMX_TF32)
 	    set_feature (FEATURE_AMX_TF32);
+	  if (eax & bit_AMX_TRANSPOSE)
+	    set_feature (FEATURE_AMX_TRANSPOSE);
 	}
     }
 
diff --git a/gcc/common/config/i386/i386-common.cc b/gcc/common/config/i386/i386-common.cc
index 74ad039..a85b380 100644
--- a/gcc/common/config/i386/i386-common.cc
+++ b/gcc/common/config/i386/i386-common.cc
@@ -132,6 +132,8 @@ along with GCC; see the file COPYING3.  If not see
    | OPTION_MASK_ISA2_AMX_AVX512)
 #define OPTION_MASK_ISA2_AMX_TF32_SET \
   (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)
 
 /* SSE4 includes both SSE4.1 and SSE4.2. -msse4 should be the same
    as -msse4.2.  */
@@ -295,7 +297,7 @@ 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_TF32_UNSET | OPTION_MASK_ISA2_AMX_TRANSPOSE_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
@@ -327,6 +329,7 @@ along with GCC; see the file COPYING3.  If not see
   (OPTION_MASK_ISA2_AVX10_2_512 | OPTION_MASK_ISA2_AMX_AVX512_UNSET)
 #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
 
 /* SSE4 includes both SSE4.1 and SSE4.2.  -mno-sse4 should the same
    as -mno-sse4.1. */
@@ -1446,6 +1449,20 @@ ix86_handle_option (struct gcc_options *opts,
 	}
       return true;
 
+    case OPT_mamx_transpose:
+      if (value)
+	{
+	  opts->x_ix86_isa_flags2 |= OPTION_MASK_ISA2_AMX_TRANSPOSE_SET;
+	  opts->x_ix86_isa_flags2_explicit |= OPTION_MASK_ISA2_AMX_TRANSPOSE_SET;
+	}
+      else
+	{
+	  opts->x_ix86_isa_flags2 &= ~OPTION_MASK_ISA2_AMX_TRANSPOSE_UNSET;
+	  opts->x_ix86_isa_flags2_explicit |=
+	    OPTION_MASK_ISA2_AMX_TRANSPOSE_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 d19de25..f5f8ba2 100644
--- a/gcc/common/config/i386/i386-cpuinfo.h
+++ b/gcc/common/config/i386/i386-cpuinfo.h
@@ -271,6 +271,7 @@ enum processor_features
   FEATURE_AVX10_2_512,
   FEATURE_AMX_AVX512,
   FEATURE_AMX_TF32,
+  FEATURE_AMX_TRANSPOSE,
   CPU_FEATURE_MAX
 };
 
diff --git a/gcc/common/config/i386/i386-isas.h b/gcc/common/config/i386/i386-isas.h
index 0ba2e88..28c8d07 100644
--- a/gcc/common/config/i386/i386-isas.h
+++ b/gcc/common/config/i386/i386-isas.h
@@ -192,4 +192,6 @@ ISA_NAMES_TABLE_START
   ISA_NAMES_TABLE_ENTRY("amx-avx512", FEATURE_AMX_AVX512, P_NONE,
 			"-mamx-avx512")
   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_END