CodeQL / Analyze (actions) (push) Canceled after 0s
CodeQL / Analyze (python) (push) Canceled after 0s
pre-commit / pre-commit (push) Canceled after 0s
Multi-Arch CI / setup (push) Canceled after 0s
Publish build_manylinux_x86_64 images / publish_build_manylinux_x86_64 (push) Canceled after 0s
Setup (Multi-Arch) / setup (push) Canceled after 0s
Multi-Arch CI / Linux::${{ fromJSON(needs.setup.outputs.linux_build_config || '{}').build_variant_label || 'skip' }} (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Publish no_rocm_image_ubi10 image / publish_no_rocm_image_ubi10 (push) Canceled after 0s
Multi-Arch CI / Windows::${{ fromJSON(needs.setup.outputs.windows_build_config || '{}').build_variant_label || 'skip' }} (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Multi-Arch CI / Manifest Diff (push) Canceled after 0s
TheRock Manifest Diff Report / Generate Manifest Diff Report (push) Canceled after 0s
Multi-Arch CI / CI Summary (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04 (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04_ocl_rt images / publish_no_rocm_image_ubuntu24_04_ocl_rt (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04_rocgdb (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04_rocgdb images / publish_no_rocm_image_ubuntu24_04_rocgdb (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04_ocl_rt (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Unit Tests / Unit Tests :: ubuntu-24.04 (push) Canceled after 0s
Unit Tests / Unit Tests :: windows-2022 (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04_media (push) Canceled after 0s
Unit Tests / Unit Tests Summary (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04_openmpi (push) Canceled after 0s
216 lines
7.5 KiB
C++
216 lines
7.5 KiB
C++
/* ************************************************************************
|
|
* Copyright (C) 2020-2026 Advanced Micro Devices, Inc. All rights reserved.
|
|
*
|
|
* Permission is hereby granted, free of charge, to any person obtaining a copy
|
|
* of this software and associated documentation files (the "Software"), to deal
|
|
* in the Software without restriction, including without limitation the rights
|
|
* to use, copy, modify, merge, publish, distribute, sublicense, and/or sell cop-
|
|
* ies of the Software, and to permit persons to whom the Software is furnished
|
|
* to do so, subject to the following conditions:
|
|
*
|
|
* The above copyright notice and this permission notice shall be included in all
|
|
* copies or substantial portions of the Software.
|
|
*
|
|
* THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR IM-
|
|
* PLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY, FITNESS
|
|
* FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE AUTHORS OR
|
|
* COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER
|
|
* IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNE-
|
|
* CTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN THE SOFTWARE.
|
|
*
|
|
*
|
|
* ************************************************************************ */
|
|
|
|
#pragma once
|
|
|
|
#include <vector>
|
|
|
|
#include "../include/complex.hpp"
|
|
#include "hipsolver.h"
|
|
|
|
using rocblas_float_complex = hipsolverComplex;
|
|
using rocblas_double_complex = hipsolverDoubleComplex;
|
|
|
|
/* LAPACK fortran library functionality */
|
|
|
|
extern "C" {
|
|
float slange_(char* norm_type, int* m, int* n, float* A, int* lda, float* work);
|
|
double dlange_(char* norm_type, int* m, int* n, double* A, int* lda, double* work);
|
|
float clange_(char* norm_type, int* m, int* n, rocblas_float_complex* A, int* lda, float* work);
|
|
double zlange_(char* norm_type, int* m, int* n, rocblas_double_complex* A, int* lda, double* work);
|
|
|
|
void daxpy_(int* n, double* alpha, double* x, int* incx, double* y, int* incy);
|
|
void zaxpy_(int* n,
|
|
rocblas_double_complex* alpha,
|
|
rocblas_double_complex* x,
|
|
int* incx,
|
|
rocblas_double_complex* y,
|
|
int* incy);
|
|
}
|
|
|
|
inline float xlange(char* norm_type, int* m, int* n, float* A, int* lda, float* work)
|
|
{
|
|
return slange_(norm_type, m, n, A, lda, work);
|
|
}
|
|
|
|
inline double xlange(char* norm_type, int* m, int* n, double* A, int* lda, double* work)
|
|
{
|
|
return dlange_(norm_type, m, n, A, lda, work);
|
|
}
|
|
|
|
inline float
|
|
xlange(char* norm_type, int* m, int* n, rocblas_float_complex* A, int* lda, float* work)
|
|
{
|
|
return clange_(norm_type, m, n, A, lda, work);
|
|
}
|
|
|
|
inline double
|
|
xlange(char* norm_type, int* m, int* n, rocblas_double_complex* A, int* lda, double* work)
|
|
{
|
|
return zlange_(norm_type, m, n, A, lda, work);
|
|
}
|
|
|
|
inline void xaxpy(int* n, double* alpha, double* x, int* incx, double* y, int* incy)
|
|
{
|
|
return daxpy_(n, alpha, x, incx, y, incy);
|
|
}
|
|
|
|
inline void xaxpy(int* n,
|
|
rocblas_double_complex* alpha,
|
|
rocblas_double_complex* x,
|
|
int* incx,
|
|
rocblas_double_complex* y,
|
|
int* incy)
|
|
{
|
|
return zaxpy_(n, alpha, x, incx, y, incy);
|
|
}
|
|
|
|
/* Norm of error functions */
|
|
template <typename T, std::enable_if_t<!is_complex<T>, int> = 0>
|
|
double norm_error(char norm_type,
|
|
rocblas_int M,
|
|
rocblas_int N,
|
|
rocblas_int lda_gold,
|
|
T* gold,
|
|
T* comp,
|
|
rocblas_int lda_comp = 0)
|
|
{
|
|
// norm type can be 'O', 'I', 'F', 'o', 'i', 'f' for one, infinity or
|
|
// Frobenius norm one norm is max column sum infinity norm is max row sum
|
|
// Frobenius is l2 norm of matrix entries
|
|
|
|
rocblas_int lda = M;
|
|
lda_comp = lda_comp > 0 ? lda_comp : lda_gold;
|
|
|
|
std::vector<double> gold_double(N * lda);
|
|
std::vector<double> comp_double(N * lda);
|
|
|
|
for(rocblas_int i = 0; i < M; i++)
|
|
{
|
|
for(rocblas_int j = 0; j < N; j++)
|
|
{
|
|
gold_double[i + j * lda] = double(gold[i + j * lda_gold]);
|
|
comp_double[i + j * lda] = double(comp[i + j * lda_comp]);
|
|
}
|
|
}
|
|
|
|
std::vector<double> work(M);
|
|
rocblas_int incx = 1;
|
|
double alpha = -1.0;
|
|
rocblas_int size = lda * N;
|
|
|
|
double gold_norm = xlange(&norm_type, &M, &N, gold_double.data(), &lda, work.data());
|
|
xaxpy(&size, &alpha, gold_double.data(), &incx, comp_double.data(), &incx);
|
|
double error = xlange(&norm_type, &M, &N, comp_double.data(), &lda, work.data());
|
|
if(gold_norm > 0)
|
|
error /= gold_norm;
|
|
|
|
return error;
|
|
}
|
|
|
|
template <typename T, std::enable_if_t<is_complex<T>, int> = 0>
|
|
double norm_error(char norm_type,
|
|
rocblas_int M,
|
|
rocblas_int N,
|
|
rocblas_int lda_gold,
|
|
T* gold,
|
|
T* comp,
|
|
rocblas_int lda_comp = 0)
|
|
{
|
|
// norm type can be 'O', 'I', 'F', 'o', 'i', 'f' for one, infinity or
|
|
// Frobenius norm one norm is max column sum infinity norm is max row sum
|
|
// Frobenius is l2 norm of matrix entries
|
|
|
|
rocblas_int lda = M;
|
|
lda_comp = lda_comp > 0 ? lda_comp : lda_gold;
|
|
|
|
std::vector<rocblas_double_complex> gold_double(N * lda);
|
|
std::vector<rocblas_double_complex> comp_double(N * lda);
|
|
|
|
for(rocblas_int i = 0; i < M; i++)
|
|
{
|
|
for(rocblas_int j = 0; j < N; j++)
|
|
{
|
|
gold_double[i + j * lda] = rocblas_double_complex(std::real(gold[i + j * lda_gold]),
|
|
std::imag(gold[i + j * lda_gold]));
|
|
comp_double[i + j * lda] = rocblas_double_complex(std::real(comp[i + j * lda_comp]),
|
|
std::imag(comp[i + j * lda_comp]));
|
|
}
|
|
}
|
|
|
|
std::vector<double> work(M);
|
|
rocblas_int incx = 1;
|
|
rocblas_double_complex alpha = -1.0;
|
|
rocblas_int size = lda * N;
|
|
|
|
double gold_norm = xlange(&norm_type, &M, &N, gold_double.data(), &lda, work.data());
|
|
xaxpy(&size, &alpha, gold_double.data(), &incx, comp_double.data(), &incx);
|
|
double error = xlange(&norm_type, &M, &N, comp_double.data(), &lda, work.data());
|
|
if(gold_norm > 0)
|
|
error /= gold_norm;
|
|
|
|
return error;
|
|
}
|
|
|
|
template <typename T>
|
|
double norm_error_upperTr(
|
|
char norm_type, rocblas_int M, rocblas_int N, rocblas_int lda, T* gold, T* comp)
|
|
{
|
|
for(rocblas_int i = 0; i < M; ++i)
|
|
{
|
|
for(rocblas_int j = 0; j < N; ++j)
|
|
{
|
|
if(i > j)
|
|
{
|
|
gold[i + j * lda] = T(0);
|
|
comp[i + j * lda] = T(0);
|
|
}
|
|
}
|
|
}
|
|
return norm_error(norm_type, M, N, lda, gold, comp);
|
|
}
|
|
|
|
template <typename T>
|
|
double norm_error_lowerTr(
|
|
char norm_type, rocblas_int M, rocblas_int N, rocblas_int lda, T* gold, T* comp)
|
|
{
|
|
for(rocblas_int i = 0; i < M; ++i)
|
|
{
|
|
for(rocblas_int j = 0; j < N; ++j)
|
|
{
|
|
if(i < j)
|
|
{
|
|
gold[i + j * lda] = T(0);
|
|
comp[i + j * lda] = T(0);
|
|
}
|
|
}
|
|
}
|
|
return norm_error(norm_type, M, N, lda, gold, comp);
|
|
}
|
|
|
|
template <typename T, typename S = decltype(std::real(T{}))>
|
|
S snorm(char norm_type, rocblas_int m, rocblas_int n, T* A, rocblas_int lda)
|
|
{
|
|
return xlange(&norm_type, &m, &n, A, &lda, (S*)nullptr);
|
|
}
|