/* ************************************************************************
 * Copyright 2016-2022 Advanced Micro Devices, Inc.
 * ************************************************************************ */

#include "testing_gemm_batched_ex.hpp"
#include "testing_gemm_ex.hpp"
#include "testing_gemm_strided_batched_ex.hpp"
#include "utility.h"
#include <math.h>
#include <stdexcept>
#include <vector>

using ::testing::Combine;
using ::testing::TestWithParam;
using ::testing::Values;
using ::testing::ValuesIn;
using namespace std;

/* =====================================================================
README: This file contains testers to verify the correctness of
        BLAS routines with google test

        It is supposed to be played/used by advance / expert users
        Normal users only need to get the library routines without testers
     =================================================================== */

// only GCC/VS 2010 comes with std::tr1::tuple, but it is unnecessary,  std::tuple is good enough;

typedef std::tuple<vector<int>, vector<double>, vector<char>, vector<hipblasDatatype_t>, int, bool>
    gemm_ex_tuple;

// clang-format off
// vector of vector, each vector is a {M, N, K, lda, ldb, ldc};
// add/delete as a group
const vector<vector<int>> int8_matrix_size_range = {

    { 4,  4,  4,  4,  4,  4},
    { 8,  8,  8,  8,  8,  8},
    {12, 12, 12, 12, 12, 12},
    {16, 16, 16, 16, 16, 16},
    {20, 20, 20, 20, 20, 20},
    { 8,  4,  4,  8,  8,  8},
    { 8, 12, 12, 12, 12, 12},
};

const vector<vector<int>> small_matrix_size_range = {
    { 1,  1,  1,  1,  1,  1},
    { 1,  2,  3,  4,  5,  6},
    { 7,  9, 15, 17, 18, 19},
    { 8,  1,  1,  8,  8,  8},
    { 2,  2,  2,  2,  2,  2},
    { 3,  3,  3,  3,  3,  3},
    { 4,  4,  4,  4,  4,  4},
    { 5,  5,  5,  5,  5,  5},
    { 6,  6,  6,  6,  6,  6},
    { 7,  7,  7,  7,  7,  7},
    { 8,  8,  8,  8,  8,  8},
    { 9,  9,  9,  9,  9,  9},
    {10, 10, 10, 10, 10, 10},
    {11, 11, 11, 11, 11, 11},
    {12, 12, 12, 12, 12, 12},
    {13, 13, 13, 13, 13, 13},
    {14, 14, 14, 14, 14, 14},
    {15, 15, 15, 15, 15, 15},
    {16, 16, 16, 16, 16, 16},
    {17, 17, 17, 17, 17, 17},
    {18, 18, 18, 18, 18, 18},
    {19, 19, 19, 19, 19, 19},
    {20, 20, 20, 20, 20, 20},
    { 2,  3,  4,  5,  6,  7},
    { 3,  4,  5,  6,  7,  8},
    { 4,  5,  6,  6,  6,  6},
    { 5,  6,  7,  7,  8,  9},
    { 6,  7,  8, 10,  9,  8},
    { 7,  8,  9, 11,  9, 10},
    { 8,  9, 10, 10, 11, 12},
    { 9, 10, 11, 12, 11, 13},
    {13, 12, 11, 15, 14, 13},
    {15, 16, 17, 17, 18, 19},
    {18, 17, 16, 18, 18, 18},
    {16, 17, 18, 20, 19, 18},
    { 8,  2,  2,  8,  8,  8},
    { 8,  3,  3,  8,  8,  8},
    { 8,  4,  4,  8,  8,  8},
    { 8,  5,  5,  8,  8,  8},
    { 8,  6,  6,  8,  8,  8},
    { 8,  7,  7,  8,  8,  8},
    { 8,  9,  9,  9,  9,  9},
    { 8, 10, 10, 10, 10, 10},
    { 8, 11, 11, 11, 11, 11},
    { 8, 12, 12, 12, 12, 12},
    { 8, 13, 13, 13, 13, 13},
    { 8, 14, 14, 14, 14, 14},
    { 8, 15, 15, 15, 15, 15},
//  {16, 15, 15, 16, 16, 16},
//  {16, 17, 17, 17, 17, 17},
//  {17, 16, 16, 17, 17, 17},
//  {16, 18, 18, 18, 18, 18},
//  {24, 24, 24, 24, 24, 24},
//  {32, 32, 32, 32, 32, 32},
//  {40, 40, 40, 40, 40, 40},
//  {48, 48, 48, 48, 48, 48},
//  {56, 56, 56, 56, 56, 56},
//  {64, 64, 64, 64, 64, 64},
//  {72, 72, 72, 72, 72, 72},
};
const vector<vector<int>> medium_matrix_size_range = {
    {127, 127,  63, 127, 127, 127},
    {128, 127,  63, 128, 128, 128},
    {129, 127,  63, 129, 129, 129},
//  {127, 128,  63, 128, 127, 127},
//  {128, 128,  63, 128, 127, 127},
//  {129, 128,  63, 129, 129, 129},
//  {127, 129,  63, 129, 129, 129},
//  {128, 129,  63, 129, 129, 129},
//  {129, 129,  63, 129, 129, 129},
//  {127, 127,  64, 127, 127, 127},
//  {128, 127,  64, 128, 128, 128},
//  {129, 127,  64, 129, 129, 129},
//  {127, 128,  64, 128, 127, 127},
//  {128, 128,  64, 128, 127, 127},
//  {129, 128,  64, 129, 129, 129},
//  {127, 129,  64, 129, 129, 129},
//  {128, 129,  64, 129, 129, 129},
//  {129, 129,  64, 129, 129, 129},
//  {127, 127,  65, 127, 127, 127},
//  {128, 127,  65, 128, 128, 128},
//  {129, 127,  65, 129, 129, 129},
//  {127, 128,  65, 128, 127, 127},
//  {128, 128,  65, 128, 127, 127},
//  {129, 128,  65, 129, 129, 129},
//  {127, 129,  65, 129, 129, 129},
//  {128, 129,  65, 129, 129, 129},
//  {129, 129,  65, 129, 129, 129},
//  {191, 193, 194, 195, 196, 197},
//  {500, 501, 502, 503, 604, 505},
//  {639, 640, 347, 960, 961,1062},
};

// vector of vector, each vector is a {M, N, K, lda, ldb, ldc};
const vector<vector<int>> large_matrix_size_range = {
    {1000, 1001,  101, 2002, 1003, 1004},
    { 925, 1026, 1027, 1028, 2029, 1031},
    {4011, 4012,  103, 4014, 4015, 4016},
};

// vector of vector, each vector is a {M, N, K, lda, ldb, ldc};
const vector<vector<int>> chunk_matrix_size_range = {
    {24000,   256, 256, 24010,   256, 24000},
    {24000,   256, 256, 24000,   256, 24020},
    {  256, 24001, 256,   256, 24030, 24000},
    {  256, 24001, 256,   256, 24000, 24040},
};

// vector of vector, each vector is a {M, N, K, lda, ldb, ldc};
const vector<vector<int>> NaN_matrix_size_range = {
    {   5,    6,   7,    8,    9,   10},
    {4011, 4012, 111, 4013, 4014, 4015},
};

// vector of vector, each pair is a {alpha, alphai, beta, betai};
// add/delete this list in pairs, like {2.0, 3.0, 4.0, 5.0}
const vector<vector<double>> alpha_beta_range = {
    {5.0, 2.0, 0.0, 0.0}, {0.0, 0.0, 3.0, 0.0}, {1.0, -2.0, -3.0, 4.0},
};

// For Cuda v < 10.0, only alpha and beta = 1 or = 0 are
// supported.
const vector<vector<double>> alpha_beta_range_int8 = {
    {1.0, 0.0, 1.0, 0.0}, {1.0, 0.0, 0.0, 0.0},
};

// vector of vector, each pair is a {transA, transB};
// add/delete this list in pairs, like {'N', 'T'}
// for single/double precision, 'C'(conjTranspose) will downgraded to 'T' (transpose) internally in
// sgemm/dgemm,
const vector<vector<char>> small_transA_transB_range = {{'N', 'N'}};
const vector<vector<char>> transA_transB_range = {{'N', 'N'}, {'N', 'T'}, {'C', 'N'}, {'T', 'C'}};

// a_type, b_type, c_type, d_type, compute_type
const vector<vector<hipblasDatatype_t>> precision_half = {{ HIPBLAS_R_16F,
                                                            HIPBLAS_R_16F,
                                                            HIPBLAS_R_16F,
                                                            HIPBLAS_R_16F,
                                                            HIPBLAS_R_16F  }};

const vector<vector<hipblasDatatype_t>> precision_hpa_half = {{ HIPBLAS_R_16F,
                                                                HIPBLAS_R_16F,
                                                                HIPBLAS_R_16F,
                                                                HIPBLAS_R_16F,
                                                                HIPBLAS_R_32F  }};

const vector<vector<hipblasDatatype_t>> precision_single = {{ HIPBLAS_R_32F,
                                                              HIPBLAS_R_32F,
                                                              HIPBLAS_R_32F,
                                                              HIPBLAS_R_32F,
                                                              HIPBLAS_R_32F  }};

const vector<vector<hipblasDatatype_t>> precision_double = {{ HIPBLAS_R_64F,
                                                              HIPBLAS_R_64F,
                                                              HIPBLAS_R_64F,
                                                              HIPBLAS_R_64F,
                                                              HIPBLAS_R_64F  }};

const vector<vector<hipblasDatatype_t>> precision_single_complex = {{ HIPBLAS_C_32F,
                                                              HIPBLAS_C_32F,
                                                              HIPBLAS_C_32F,
                                                              HIPBLAS_C_32F,
                                                              HIPBLAS_C_32F  }};

const vector<vector<hipblasDatatype_t>> precision_double_complex = {{ HIPBLAS_C_64F,
                                                              HIPBLAS_C_64F,
                                                              HIPBLAS_C_64F,
                                                              HIPBLAS_C_64F,
                                                              HIPBLAS_C_64F  }};

const vector<vector<hipblasDatatype_t>> precision_int8 = {{ HIPBLAS_R_8I,
                                                              HIPBLAS_R_8I,
                                                              HIPBLAS_R_32I,
                                                              HIPBLAS_R_32I,
                                                              HIPBLAS_R_32I  }};


const vector<vector<hipblasDatatype_t>> precision_type_range = {{HIPBLAS_R_16F,
                                                                 HIPBLAS_R_16F,
                                                                 HIPBLAS_R_16F,
                                                                 HIPBLAS_R_16F,
                                                                 HIPBLAS_R_16F},
                                                                {HIPBLAS_R_16F,
                                                                 HIPBLAS_R_16F,
                                                                 HIPBLAS_R_16F,
                                                                 HIPBLAS_R_16F,
                                                                 HIPBLAS_R_32F},
                                                                {HIPBLAS_R_32F,
                                                                 HIPBLAS_R_32F,
                                                                 HIPBLAS_R_32F,
                                                                 HIPBLAS_R_32F,
                                                                 HIPBLAS_R_32F},
                                                                {HIPBLAS_R_64F,
                                                                 HIPBLAS_R_64F,
                                                                 HIPBLAS_R_64F,
                                                                 HIPBLAS_R_64F,
                                                                 HIPBLAS_R_64F},
                                                                {HIPBLAS_C_32F,
                                                                 HIPBLAS_C_32F,
                                                                 HIPBLAS_C_32F,
                                                                 HIPBLAS_C_32F,
                                                                 HIPBLAS_C_32F},
                                                                {HIPBLAS_C_64F,
                                                                 HIPBLAS_C_64F,
                                                                 HIPBLAS_C_64F,
                                                                 HIPBLAS_C_64F,
                                                                 HIPBLAS_C_64F},
                                                                {HIPBLAS_R_8I,
                                                                 HIPBLAS_R_8I,
                                                                 HIPBLAS_R_32I,
                                                                 HIPBLAS_R_32I,
                                                                 HIPBLAS_R_32I}};

const int batch_count_range[] = { -1, 1, 5 };
const int batch_count_range_small[] = { 1 };

const bool is_fortran[] = {false, true};
const bool is_fortran_false[] = {false};
// clang-format on

/* ===============Google Unit Test==================================================== */

/* =====================================================================
     BLAS-3 GEMM:
=================================================================== */
/* ============================Setup Arguments======================================= */

// Please use "class Arguments" (see utility.hpp) to pass parameters to templated testers;
// Some routines may not touch/use certain "members" of objects "argus".
// like BLAS-1 Scal does not have lda, BLAS-2 GEMV does not have ldb, ldc;
// That is fine. These testers & routines will leave untouched members alone.
// Do not use std::tuple to directly pass parameters to testers
// by std:tuple, you have unpack it with extreme care for each one by like "std::get<0>" which is
// not intuitive and error-prone

Arguments setup_gemm_ex_arguments(gemm_ex_tuple tup)
{
    vector<int>               matrix_size     = std::get<0>(tup);
    vector<double>            alpha_beta      = std::get<1>(tup);
    vector<char>              transA_transB   = std::get<2>(tup);
    vector<hipblasDatatype_t> precision_types = std::get<3>(tup);
    int                       batch_count     = std::get<4>(tup);
    bool                      fortran         = std::get<5>(tup);

    Arguments arg;

    // see the comments about matrix_size_range above
    arg.M   = matrix_size[0];
    arg.N   = matrix_size[1];
    arg.K   = matrix_size[2];
    arg.lda = matrix_size[3];
    arg.ldb = matrix_size[4];
    arg.ldc = matrix_size[5];

    // the first 2 elements of alpha_beta_range are always alpha, and the second 2 are always beta
    arg.alpha  = alpha_beta[0];
    arg.alphai = alpha_beta[1];
    arg.beta   = alpha_beta[2];
    arg.betai  = alpha_beta[3];

    arg.transA_option = transA_transB[0];
    arg.transB_option = transA_transB[1];

    arg.timing = 0;

    arg.a_type       = precision_types[0];
    arg.b_type       = precision_types[1];
    arg.c_type       = precision_types[2];
    arg.compute_type = precision_types[4];

    arg.batch_count = batch_count;

    arg.fortran = fortran;

    return arg;
}

class parameterized_gemm_ex : public ::TestWithParam<gemm_ex_tuple>
{
protected:
    parameterized_gemm_ex() {}
    virtual ~parameterized_gemm_ex() {}
    virtual void SetUp() {}
    virtual void TearDown() {}
};

TEST_P(parameterized_gemm_ex, standard)
{
    // GetParam return a tuple. Tee setup routine unpack the tuple
    // and initializes arg(Arguments) which will be passed to testing routine
    // The Arguments data struture have physical meaning associated.
    // while the tuple is non-intuitive.

    Arguments arg = setup_gemm_ex_arguments(GetParam());

    hipblasStatus_t status = testing_gemm_ex(arg);

    // if not success, then the input argument is problematic, so detect the error message
    if(status != HIPBLAS_STATUS_SUCCESS)
    {
        if(arg.M < 0 || arg.N < 0 || arg.K < 0)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else if(arg.transA_option == 'N' ? arg.lda < arg.M : arg.lda < arg.K)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else if(arg.transB_option == 'N' ? arg.ldb < arg.K : arg.ldb < arg.N)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else
        {
            // Only available in cuda cc >= 5.0.
            // If we want we can change this to call query_device_property() and
            // call this only if cc < 5.0 on a CUDA device, else fail.
            EXPECT_EQ(HIPBLAS_STATUS_ARCH_MISMATCH, status);
        }
    }
}

class parameterized_gemm_batched_ex : public ::TestWithParam<gemm_ex_tuple>
{
protected:
    parameterized_gemm_batched_ex() {}
    virtual ~parameterized_gemm_batched_ex() {}
    virtual void SetUp() {}
    virtual void TearDown() {}
};

TEST_P(parameterized_gemm_batched_ex, standard_batched)
{
    // GetParam return a tuple. Tee setup routine unpack the tuple
    // and initializes arg(Arguments) which will be passed to testing routine
    // The Arguments data struture have physical meaning associated.
    // while the tuple is non-intuitive.

    Arguments arg = setup_gemm_ex_arguments(GetParam());

    hipblasStatus_t status = testing_gemm_batched_ex(arg);

    // if not success, then the input argument is problematic, so detect the error message
    if(status != HIPBLAS_STATUS_SUCCESS)
    {
        if(arg.M < 0 || arg.N < 0 || arg.K < 0 || arg.batch_count < 0)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else if(arg.transA_option == 'N' ? arg.lda < arg.M : arg.lda < arg.K)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else if(arg.transB_option == 'N' ? arg.ldb < arg.K : arg.ldb < arg.N)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else if(status == HIPBLAS_STATUS_ARCH_MISMATCH)
        {
            // Only available in cuda cc >= 5.0.
            // If we want we can change this to call query_device_property() and
            // call this only if cc < 5.0 on a CUDA device, else fail.
            EXPECT_EQ(HIPBLAS_STATUS_ARCH_MISMATCH, status);
        }
        else
        {
#ifndef __HIP_PLATFORM_NVCC__
            // on HIP we should pass all tests
            EXPECT_EQ(HIPBLAS_STATUS_SUCCESS, status);
#else
            // cublas/rocblas do not have identical support
            // (i.e. cublas doesn't support i8/i32 here)
            EXPECT_EQ(HIPBLAS_STATUS_NOT_SUPPORTED, status);
#endif
        }
    }
}

TEST_P(parameterized_gemm_batched_ex, standard_strided_batched)
{
    // GetParam return a tuple. Tee setup routine unpack the tuple
    // and initializes arg(Arguments) which will be passed to testing routine
    // The Arguments data struture have physical meaning associated.
    // while the tuple is non-intuitive.

    Arguments arg = setup_gemm_ex_arguments(GetParam());

    hipblasStatus_t status = testing_gemm_strided_batched_ex(arg);

    // if not success, then the input argument is problematic, so detect the error message
    if(status != HIPBLAS_STATUS_SUCCESS)
    {
        if(arg.M < 0 || arg.N < 0 || arg.K < 0 || arg.batch_count < 0)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else if(arg.transA_option == 'N' ? arg.lda < arg.M : arg.lda < arg.K)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else if(arg.transB_option == 'N' ? arg.ldb < arg.K : arg.ldb < arg.N)
        {
            EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
        }
        else if(status == HIPBLAS_STATUS_ARCH_MISMATCH)
        {
            // Only available in cuda cc >= 5.0.
            // If we want we can change this to call query_device_property() and
            // call this only if cc < 5.0 on a CUDA device, else fail.
            EXPECT_EQ(HIPBLAS_STATUS_ARCH_MISMATCH, status);
        }
        else
        {
#ifndef __HIP_PLATFORM_NVCC__
            // on HIP we should pass all tests
            EXPECT_EQ(HIPBLAS_STATUS_SUCCESS, status);
#else
            // cublas/rocblas do not have identical support
            // (i.e. cublas doesn't support i8/i32 here)
            EXPECT_EQ(HIPBLAS_STATUS_NOT_SUPPORTED, status);
#endif
        }
    }
}

// TODO: Disabling some gemm int8 tests as not supported by rocBLAS for all architectures
// class parameterized_chunk_gemm_ex : public ::TestWithParam<gemm_ex_tuple>
// {
// protected:
//     parameterized_chunk_gemm_ex() {}
//     virtual ~parameterized_chunk_gemm_ex() {}
//     virtual void SetUp() {}
//     virtual void TearDown() {}
// };

// TEST_P(parameterized_chunk_gemm_ex, float)
// {
//     // GetParam return a tuple. Tee setup routine unpack the tuple
//     // and initializes arg(Arguments) which will be passed to testing routine
//     // The Arguments data struture have physical meaning associated.
//     // while the tuple is non-intuitive.

//     Arguments arg = setup_gemm_ex_arguments(GetParam());

//     hipblasStatus_t status = testing_gemm_ex(arg);

//     // if not success, then the input argument is problematic, so detect the error message
//     if(status != HIPBLAS_STATUS_SUCCESS)
//     {
//         if(arg.M < 0 || arg.N < 0 || arg.K < 0)
//         {
//             EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
//         }
//         else if(arg.transA_option == 'N' ? arg.lda < arg.M : arg.lda < arg.K)
//         {
//             EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
//         }
//         else if(arg.transB_option == 'N' ? arg.ldb < arg.K : arg.ldb < arg.N)
//         {
//             EXPECT_EQ(HIPBLAS_STATUS_INVALID_VALUE, status);
//         }
//         else
//         {
//             // Only available in cuda cc >= 5.0.
//             // If we want we can change this to call query_device_property() and
//             // call this only if cc < 5.0 on a CUDA device, else fail.
//             EXPECT_EQ(HIPBLAS_STATUS_ARCH_MISMATCH, status);
//         }
//     }
// }

// class parameterized_half_gemm_ex : public ::TestWithParam<gemm_ex_tuple>
// {
// protected:
//     parameterized_half_gemm_ex() {}
//     virtual ~parameterized_half_gemm_ex() {}
//     virtual void SetUp() {}
//     virtual void TearDown() {}
// };

INSTANTIATE_TEST_SUITE_P(quick_blas_ex_small_int8,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(int8_matrix_size_range),
                                 ValuesIn(alpha_beta_range_int8),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_int8),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran)));

// TEST(pre_checkin_blas_ex_bad_arg, float) { testing_gemm_ex_bad_arg(); }

//----small
INSTANTIATE_TEST_SUITE_P(quick_blas_ex_small_hpa_half,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_hpa_half),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_ex_small_half,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_half),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_ex_small_single,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_single),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_ex_small_double,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_double),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_ex_small_single_complex,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_single_complex),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_ex_small_double_complex,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_double_complex),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran)));

//----medium
INSTANTIATE_TEST_SUITE_P(pre_checkin_blas_ex_medium_hpa_half,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(medium_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_hpa_half),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran_false)));

INSTANTIATE_TEST_SUITE_P(pre_checkin_blas_ex_medium_half,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(medium_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_half),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran_false)));

INSTANTIATE_TEST_SUITE_P(pre_checkin_blas_ex_medium_float,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(medium_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_single),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran_false)));

INSTANTIATE_TEST_SUITE_P(pre_checkin_blas_ex_medium_double,
                         parameterized_gemm_ex,
                         Combine(ValuesIn(medium_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_double),
                                 ValuesIn(batch_count_range_small),
                                 ValuesIn(is_fortran_false)));

//----small-batched
INSTANTIATE_TEST_SUITE_P(quick_blas_batched_ex_small_hpa_half,
                         parameterized_gemm_batched_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_hpa_half),
                                 ValuesIn(batch_count_range),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_batched_ex_small_half,
                         parameterized_gemm_batched_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_half),
                                 ValuesIn(batch_count_range),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_batched_ex_small_single,
                         parameterized_gemm_batched_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_single),
                                 ValuesIn(batch_count_range),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_batched_ex_small_double,
                         parameterized_gemm_batched_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_double),
                                 ValuesIn(batch_count_range),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_batched_ex_small_single_complex,
                         parameterized_gemm_batched_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_single_complex),
                                 ValuesIn(batch_count_range),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_batched_ex_small_double_complex,
                         parameterized_gemm_batched_ex,
                         Combine(ValuesIn(small_matrix_size_range),
                                 ValuesIn(alpha_beta_range),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_double_complex),
                                 ValuesIn(batch_count_range),
                                 ValuesIn(is_fortran)));

INSTANTIATE_TEST_SUITE_P(quick_blas_batched_ex_small_int8,
                         parameterized_gemm_batched_ex,
                         Combine(ValuesIn(int8_matrix_size_range),
                                 ValuesIn(alpha_beta_range_int8),
                                 ValuesIn(transA_transB_range),
                                 ValuesIn(precision_int8),
                                 ValuesIn(batch_count_range),
                                 ValuesIn(is_fortran)));