mirror of
https://github.com/ROCm/composable_kernel.git
synced 2026-05-16 19:09:59 +00:00
Unified conv3D API + support for all data types. (#133)
* Convolution ND
* Code unification across dimensions for generating tensor descriptors.
* Example
* Instances
* Move convnd f32 instance file to comply with repo structure.
* Conv 1D tensor layouts.
* Formatting and use ReferenceConv
* Reference ConvFwd supporting 1D and 2D convolution.
* Debug printing TensorLayout name.
* Conv fwd 1D instance f32
* Refactor conv ND example.
Needed to support various conv dimensio.
Needed to support various conv dimensions
* Rename conv nd example director to prevent conflicts.
* Refactor some common utility to single file.
Plus some tests.
* Refactor GetHostTensorDescriptor + UT.
* Add 1D test case.
* Test reference convolution 1d/2d
* Remove some leftovers.
* Fix convolution example error for 1D
* Refactor test check errors utility function.
* Test Conv2D Fwd XDL
* More UT for 1D case.
* Parameterize input & weight initializers.
* Rename example to prevent conflicts.
* Split convnd instance into separate files for 1d/2d
* Address review comments.
* Fix data type for flops/gbytes calculations.
* Assign example number 11.
* 3D cases for convolution utility functions.
* 3D reference convolution.
* Add support for 3D convolution.
* Check for inputs bigger than 2GB.
* Formatting
* Support for bf16/f16/f32/i8 - conv instances + UT.
* Use check_err from test_util.hpp.
* Split convnd test into separate files for each dim.
* Fix data generation and use proper instances.
* Formatting
* Skip tensor initialization if not necessary.
* Fix CMakefiles.
* Remove redundant conv2d_fwd test.
* Lower problem size for conv3D UT.
* 3D case for convnd example.
* Remove leftovers after merge.
* Add Conv Specialization string to GetTypeString
* Skip instance causing numerical errors.
* Small fixes.
* Remove redundant includes.
* Fix namespace name error.
* Script for automatic testing and logging convolution fwd UTs
* Comment out numactl cmd.
* Refine weights initalization and relax rtol for fp16
* Fix weights initialization for int8.
* Add type_convert when store output in ref conv 1D.
* Get back old conv2d_fwd_xdl operation.
* Silence conv debug print.
* format
* clean
* clean
* Fix merge.
* Fix namespace for check_err
Co-authored-by: Adam Osewski <aosewski@amd.com>
Co-authored-by: Chao Liu <chao.liu2@amd.com>
[ROCm/composable_kernel commit: f91579aab6]
This commit is contained in:
Adam Osewski
110
script/test_convnd_fwd.sh
Normal file
110
script/test_convnd_fwd.sh
Normal file
@@ -0,0 +1,110 @@
|
||||
#!/usr/bin/env bash
|
||||
|
||||
# set -e
|
||||
|
||||
DIM1=False
|
||||
DIM2=True
|
||||
DIM3=False
|
||||
DATE=220317
|
||||
GIT_HASH=4e6dfda
|
||||
LOG_DIR=${DATE}_${GIT_HASH}
|
||||
SUFFIX=${GIT_HASH}
|
||||
|
||||
|
||||
#--------------------------------------------------------------------------
|
||||
# Commandline arguments parsing
|
||||
# like: cmd -key[--key] value
|
||||
#--------------------------------------------------------------------------
|
||||
|
||||
POSITIONAL=()
|
||||
while [[ $# -gt 0 ]]
|
||||
do
|
||||
key="$1"
|
||||
|
||||
case $key in
|
||||
-d1|--d1)
|
||||
DIM1=True
|
||||
echo DIM1: "${DIM1}"
|
||||
shift # past argument
|
||||
;;
|
||||
-d2|--d2)
|
||||
DIM2=True
|
||||
echo DIM2: "${DIM2}"
|
||||
shift # past argument
|
||||
;;
|
||||
-d3|--d3)
|
||||
DIM3=True
|
||||
echo DIM3: "${DIM3}"
|
||||
shift # past argument
|
||||
;;
|
||||
-all|--all)
|
||||
DIM1=True
|
||||
DIM2=True
|
||||
DIM3=True
|
||||
echo DIM1: "${DIM1}"
|
||||
echo DIM2: "${DIM2}"
|
||||
echo DIM3: "${DIM3}"
|
||||
shift # past argument
|
||||
;;
|
||||
-s|--suffix)
|
||||
SUFFIX=${SUFFIX}_"$2"
|
||||
echo SUFFIX: "${SUFFIX}"
|
||||
shift # past argument
|
||||
shift # past value
|
||||
;;
|
||||
*) # unknown option
|
||||
POSITIONAL+=("$1") # save it in an array for later
|
||||
shift # past argument
|
||||
;;
|
||||
esac
|
||||
done
|
||||
set -- "${POSITIONAL[@]}" # restore positional parameters
|
||||
|
||||
#--------------------------------------------------------------------------
|
||||
|
||||
# NUMACTL="numactl --cpunodebind=1 --membind=1"
|
||||
NUMACTL=
|
||||
# ENV_CONF=
|
||||
GPU=mi100
|
||||
PROF_ITER_COUNT=10000
|
||||
LOG_DIR_PATH=../log/${LOG_DIR}
|
||||
set -x
|
||||
|
||||
#-------------------------------------------------------------------------------
|
||||
# 1D
|
||||
#-------------------------------------------------------------------------------
|
||||
|
||||
if [[ "${DIM1}" == "True" ]]; then
|
||||
mkdir -p ${LOG_DIR_PATH}
|
||||
echo ">>>>>>>> RUN test conv1d nwc <<<<<<<<<<"
|
||||
CMD="./../build/bin/test_conv1d_fwd"
|
||||
${NUMACTL} ${CMD} 2>&1 \
|
||||
| tee ${LOG_DIR_PATH}/test_conv1d_fwd_nwc_${SUFFIX}_${GPU}.log
|
||||
|
||||
fi
|
||||
|
||||
#-------------------------------------------------------------------------------
|
||||
# 2D
|
||||
#-------------------------------------------------------------------------------
|
||||
|
||||
if [[ "${DIM2}" == "True" ]]; then
|
||||
mkdir -p ${LOG_DIR_PATH}
|
||||
echo ">>>>>>>> RUN test conv2d nhwc <<<<<<<<<<"
|
||||
CMD="./../build/bin/test_conv2d_fwd"
|
||||
${NUMACTL} ${CMD} 2>&1 \
|
||||
| tee ${LOG_DIR_PATH}/test_conv2d_fwd_nhwc_${SUFFIX}_${GPU}.log
|
||||
|
||||
fi
|
||||
|
||||
#-------------------------------------------------------------------------------
|
||||
# 3D
|
||||
#-------------------------------------------------------------------------------
|
||||
|
||||
if [[ "${DIM3}" == "True" ]]; then
|
||||
mkdir -p ${LOG_DIR_PATH}
|
||||
echo ">>>>>>>> RUN test conv3d ndhwc <<<<<<<<<<"
|
||||
CMD="./../build/bin/test_conv3d_fwd"
|
||||
${NUMACTL} ${CMD} 2>&1 \
|
||||
| tee ${LOG_DIR_PATH}/test_conv3d_fwd_ndhwc_${SUFFIX}_${GPU}.log
|
||||
|
||||
fi
|
||||
Reference in New Issue
Block a user