Files
derek.holloway 7502bf64a4
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
Flatten subprojects into a single base monorepo
2026-09-02 16:34:47 -07:00

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);
}