fix datatypr

Signed-off-by: jiqing-feng <jiqing.feng@intel.com>

Author: jiqing-feng

csrc/common.h

@@ -5,6 +5,12 @@
 
 using namespace BinSearch;
 
+typedef enum DataType_t {
+    General8bit = 0,
+    FP4 = 1,
+    NF4 = 2,
+} DataType_t;
+
 struct quantize_block_args {
     BinAlgo<Scalar, float, Direct2>* bin_searcher;
     float* code;

csrc/cpu_ops.h

@@ -6,12 +6,6 @@
 
 void quantize_cpu(float* code, float* A, float* absmax, unsigned char* out, long long blocksize, long long n);
 
-typedef enum DataType_t {
-    General8bit = 0,
-    FP4 = 1,
-    NF4 = 2,
-} DataType_t;
-
 struct fp16_t {
     uint16_t v;
 };

csrc/ops.cuh

@@ -77,12 +77,6 @@ typedef enum Transform_t {
     COL_AMPERE = 4,
 } Transform_t;
 
-typedef enum DataType_t {
-    General8bit = 0,
-    FP4 = 1,
-    NF4 = 2,
-} DataType_t;
-
 typedef enum Funcs_t {
     FILL = 0,
     ARANGE = 1,

csrc/ops_hip.cuh

@@ -79,12 +79,6 @@ typedef enum Transform_t {
     COL_AMPERE = 4,
 } Transform_t;
 
-typedef enum DataType_t {
-    General8bit = 0,
-    FP4 = 1,
-    NF4 = 2,
-} DataType_t;
-
 typedef enum Funcs_t {
     FILL = 0,
     ARANGE = 1,

csrc/xpu_ops.h

@@ -27,12 +27,6 @@ static inline void sycl_comp_kernel_submit(sycl::nd_range<dim> range, sycl::queu
     q.submit(cgf);
 }
 
-typedef enum DataType_t {
-    General8bit = 0,
-    FP4 = 1,
-    NF4 = 2,
-} DataType_t;
-
 template <typename T, int DATA_TYPE>
 void dequantizeBlockwise(
     float* code, unsigned char* A, float* absmax, T* out, int workgroup_size, const int n, sycl::queue* stream