Code

add half gemm support#68

Code

Draft

cayrols wants to merge 25 commits intoicl-utk-edu:mastericl-utk-edu/blaspp:masterfrom cayrols:seb/gemm.add_hgemm_supportcayrols/blaspp:seb/gemm.add_hgemm_supportCopy head branch name to clipboard

+1,339-12

Commits

Commits on Dec 14, 2023

• hgemm: add half definition and interfaces

  cayrols

  committed
  3998ebd

  Copy full SHA for 3998ebd

• hgemm: add hgemm tester; conversion routine from and to half; Nvidia support for now.

  cayrols

  committed
  60afc47

  Copy full SHA for 60afc47

• utils: move utils into test/cuda; Add missing NVCC flag; Clean utils header.

  cayrols

  committed
  f51f0c2

  Copy full SHA for f51f0c2

• utils: move utils into test/cuda; Add missing NVCC flag; Clean utils header.

  cayrols

  committed
  98e452b

  Copy full SHA for 98e452b

• half: Add hipify from the cuda utils; update the compilation chain to detect hip.

  cayrols

  committed
  64e6697

  Copy full SHA for 64e6697

• Replace the definition of half from __half to _float16; rename blas::half into blas::float16

  cayrols

  committed
  c7061d0

  Copy full SHA for c7061d0

• Rename test/utils.cuh into test/utils.hh

  cayrols

  committed
  68cb36d

  Copy full SHA for 68cb36d

• Add hip files that got generated from cuda files.

  cayrols

  committed
  1c99c49

  Copy full SHA for 1c99c49

• hgemm: Add hip support for hgemm

  cayrols

  committed
  7edd364

  Copy full SHA for 7edd364

• hgemm: fix compilation after cleaning.

  cayrols

  committed
  ffac1ae

  Copy full SHA for ffac1ae

• test: gemm change the bound by removing sqrt.

  cayrols

  committed
  bd9511d

  Copy full SHA for bd9511d

• test: fix scalar type used to get the flop count in half gemm.

  cayrols

  committed
  44a9e73

  Copy full SHA for 44a9e73

• hgemm: Use a class float16 instead of an alias.

  cayrols

  committed
  82752bf

  Copy full SHA for 82752bf

• config: fix gpu_backend name issue.

  cayrols

  committed
  b3c836c

  Copy full SHA for b3c836c

• hgemm: fix compilation issue.

  cayrols

  committed
  6a181e8

  Copy full SHA for 6a181e8

• TMP: Add explicit compilation flag for reproducer purpose.

  cayrols

  committed
  3ced0ce

  Copy full SHA for 3ced0ce

• hgemm: Search _Float16 support from compiler; If so, the macro BLAS_USE_ISO_FLOAT16 is defined.

  cayrols

  committed
  d1fd85c

  Copy full SHA for d1fd85c

• hgemm: add CPU support through MKL.

  cayrols

  committed
  8b8320b

  Copy full SHA for 8b8320b

• hgemm: add CPU test with cblas wrapper; add cast_onto_device util that cast from and to float16.

  cayrols

  committed
  30cd556

  Copy full SHA for 30cd556

• float16: update configure search and macro definition.

  cayrols

  committed
  d686451

  Copy full SHA for d686451

• hgemm: Fake casting in cublas_wrapper through pointer casting.

  cayrols

  committed
  5a30ad8

  Copy full SHA for 5a30ad8

• test: in hgemm, add cpu casting support, remove cast_onto_device routine; Fix compilation issue.

  cayrols

  committed
  f4fed1a

  Copy full SHA for f4fed1a

• float16: add casting routines from/to fp16 to/from fp32.

  cayrols

  committed
  d0d2867

  Copy full SHA for d0d2867

• float16: add missing config file.

  cayrols

  committed
  70d893b

  Copy full SHA for 70d893b

• hgemm: enable CPU hgemm only when MKL is provided.

  cayrols

  committed
  8678c82

  Copy full SHA for 8678c82