Skip to content
GitLab
Explore
Sign in
Primary navigation
Search or go to…
Project
H
hpvm-release
Manage
Activity
Members
Labels
Plan
Issues
Issue boards
Milestones
Wiki
Code
Merge requests
Repository
Branches
Commits
Tags
Repository graph
Compare revisions
Snippets
Build
Pipelines
Jobs
Pipeline schedules
Artifacts
Deploy
Releases
Model registry
Operate
Environments
Monitor
Incidents
Analyze
Value stream analytics
Contributor analytics
CI/CD analytics
Repository analytics
Model experiments
Help
Help
Support
GitLab documentation
Compare GitLab plans
Community forum
Contribute to GitLab
Provide feedback
Keyboard shortcuts
?
Snippets
Groups
Projects
Show more breadcrumbs
llvm
hpvm-release
Commits
b788846e
Commit
b788846e
authored
4 years ago
by
Akash Kothari
Browse files
Options
Downloads
Patches
Plain Diff
Change VISC to HPVM in benchmark headers
parent
d614fce6
No related branches found
Branches containing commit
No related tags found
No related merge requests found
Changes
1
Hide whitespace changes
Inline
Side-by-side
Showing
1 changed file
hpvm/test/dnn_benchmarks/common/include/visc.h
+86
-86
86 additions, 86 deletions
hpvm/test/dnn_benchmarks/common/include/visc.h
with
86 additions
and
86 deletions
hpvm/test/dnn_benchmarks/common/include/visc.h
+
86
−
86
View file @
b788846e
...
@@ -10,110 +10,110 @@
...
@@ -10,110 +10,110 @@
#define DEVICE CUDNN_TARGET
#define DEVICE CUDNN_TARGET
#endif
#endif
#include
"
llvm/
Support
VISC/VISC
Hint.h"
#include
"Support
HPVM/HPVM
Hint.h"
#ifdef __cplusplus
#ifdef __cplusplus
extern
"C"
{
extern
"C"
{
void
__
visc
__hint
(
visc
::
Target
);
void
__
hpvm
__hint
(
visc
::
Target
);
#else
#else
void
__
visc
__hint
(
enum
Target
);
void
__
hpvm
__hint
(
enum
Target
);
#endif
#endif
#ifdef __cplusplus
#ifdef __cplusplus
void
*
__
visc
__node
(...);
void
*
__
hpvm
__node
(...);
//void* __
visc
__createNode(...);
//void* __
hpvm
__createNode(...);
//void* __
visc
__createNode1D(...);
//void* __
hpvm
__createNode1D(...);
//void* __
visc
__createNode2D(...);
//void* __
hpvm
__createNode2D(...);
//void* __
visc
__createNode3D(...);
//void* __
hpvm
__createNode3D(...);
//void __
visc
__return(...);
//void __
hpvm
__return(...);
#endif
#endif
void
*
__
visc
__createNodeND
(
unsigned
,
...);
void
*
__
hpvm
__createNodeND
(
unsigned
,
...);
void
__
visc
__return
(
unsigned
,
...);
void
__
hpvm
__return
(
unsigned
,
...);
void
__
visc
__attributes
(
unsigned
,
...);
void
__
hpvm
__attributes
(
unsigned
,
...);
void
__
visc
__init
();
void
__
hpvm
__init
();
void
__
visc
__cleanup
();
void
__
hpvm
__cleanup
();
void
__
visc
__bindIn
(
void
*
,
unsigned
,
unsigned
,
unsigned
);
void
__
hpvm
__bindIn
(
void
*
,
unsigned
,
unsigned
,
unsigned
);
void
__
visc
__bindOut
(
void
*
,
unsigned
,
unsigned
,
unsigned
);
void
__
hpvm
__bindOut
(
void
*
,
unsigned
,
unsigned
,
unsigned
);
void
*
__
visc
__edge
(
void
*
,
void
*
,
unsigned
,
unsigned
,
unsigned
,
unsigned
);
void
*
__
hpvm
__edge
(
void
*
,
void
*
,
unsigned
,
unsigned
,
unsigned
,
unsigned
);
void
__
visc
__push
(
void
*
,
void
*
);
void
__
hpvm
__push
(
void
*
,
void
*
);
void
*
__
visc
__pop
(
void
*
);
void
*
__
hpvm
__pop
(
void
*
);
void
*
__
visc
__launch
(
unsigned
,
...);
void
*
__
hpvm
__launch
(
unsigned
,
...);
void
__
visc
__wait
(
void
*
);
void
__
hpvm
__wait
(
void
*
);
void
*
__
visc
__getNode
();
void
*
__
hpvm
__getNode
();
void
*
__
visc
__getParentNode
(
void
*
);
void
*
__
hpvm
__getParentNode
(
void
*
);
void
__
visc
__barrier
();
void
__
hpvm
__barrier
();
void
*
__
visc
__malloc
(
long
);
void
*
__
hpvm
__malloc
(
long
);
long
__
visc
__getNodeInstanceID_x
(
void
*
);
long
__
hpvm
__getNodeInstanceID_x
(
void
*
);
long
__
visc
__getNodeInstanceID_y
(
void
*
);
long
__
hpvm
__getNodeInstanceID_y
(
void
*
);
long
__
visc
__getNodeInstanceID_z
(
void
*
);
long
__
hpvm
__getNodeInstanceID_z
(
void
*
);
long
__
visc
__getNumNodeInstances_x
(
void
*
);
long
__
hpvm
__getNumNodeInstances_x
(
void
*
);
long
__
visc
__getNumNodeInstances_y
(
void
*
);
long
__
hpvm
__getNumNodeInstances_y
(
void
*
);
long
__
visc
__getNumNodeInstances_z
(
void
*
);
long
__
hpvm
__getNumNodeInstances_z
(
void
*
);
// Atomic
// Atomic
// signed int
// signed int
int
__
visc
__atomic_cmpxchg
(
int
*
,
int
,
int
);
int
__
hpvm
__atomic_cmpxchg
(
int
*
,
int
,
int
);
int
__
visc
__atomic_add
(
int
*
,
int
);
int
__
hpvm
__atomic_add
(
int
*
,
int
);
int
__
visc
__atomic_sub
(
int
*
,
int
);
int
__
hpvm
__atomic_sub
(
int
*
,
int
);
int
__
visc
__atomic_xchg
(
int
*
,
int
);
int
__
hpvm
__atomic_xchg
(
int
*
,
int
);
int
__
visc
__atomic_inc
(
int
*
);
int
__
hpvm
__atomic_inc
(
int
*
);
int
__
visc
__atomic_dec
(
int
*
);
int
__
hpvm
__atomic_dec
(
int
*
);
int
__
visc
__atomic_min
(
int
*
,
int
);
int
__
hpvm
__atomic_min
(
int
*
,
int
);
int
__
visc
__atomic_max
(
int
*
,
int
);
int
__
hpvm
__atomic_max
(
int
*
,
int
);
int
__
visc
__atomic_umax
(
int
*
,
int
);
int
__
hpvm
__atomic_umax
(
int
*
,
int
);
int
__
visc
__atomic_umin
(
int
*
,
int
);
int
__
hpvm
__atomic_umin
(
int
*
,
int
);
int
__
visc
__atomic_and
(
int
*
,
int
);
int
__
hpvm
__atomic_and
(
int
*
,
int
);
int
__
visc
__atomic_or
(
int
*
,
int
);
int
__
hpvm
__atomic_or
(
int
*
,
int
);
int
__
visc
__atomic_xor
(
int
*
,
int
);
int
__
hpvm
__atomic_xor
(
int
*
,
int
);
// Special Func
// Special Func
float
__
visc
__floor
(
float
);
float
__
hpvm
__floor
(
float
);
float
__
visc
__rsqrt
(
float
);
float
__
hpvm
__rsqrt
(
float
);
float
__
visc
__sqrt
(
float
);
float
__
hpvm
__sqrt
(
float
);
float
__
visc
__sin
(
float
);
float
__
hpvm
__sin
(
float
);
float
__
visc
__cos
(
float
);
float
__
hpvm
__cos
(
float
);
// unsigned int
// unsigned int
//unsigned __
visc
__atomic_cmpxchg(unsigned*, unsigned, unsigned);
//unsigned __
hpvm
__atomic_cmpxchg(unsigned*, unsigned, unsigned);
//unsigned __
visc
__atomic_add(unsigned*, unsigned);
//unsigned __
hpvm
__atomic_add(unsigned*, unsigned);
//unsigned __
visc
__atomic_sub(unsigned*, unsigned);
//unsigned __
hpvm
__atomic_sub(unsigned*, unsigned);
//unsigned __
visc
__atomic_xchg(unsigned*, unsigned);
//unsigned __
hpvm
__atomic_xchg(unsigned*, unsigned);
//unsigned __
visc
__atomic_inc(unsigned*);
//unsigned __
hpvm
__atomic_inc(unsigned*);
//unsigned __
visc
__atomic_dec(unsigned*);
//unsigned __
hpvm
__atomic_dec(unsigned*);
//unsigned __
visc
__atomic_min(unsigned*, unsigned);
//unsigned __
hpvm
__atomic_min(unsigned*, unsigned);
//unsigned __
visc
__atomic_max(unsigned*, unsigned);
//unsigned __
hpvm
__atomic_max(unsigned*, unsigned);
//unsigned __
visc
__atomic_and(unsigned*, unsigned);
//unsigned __
hpvm
__atomic_and(unsigned*, unsigned);
//unsigned __
visc
__atomic_or(unsigned*, unsigned);
//unsigned __
hpvm
__atomic_or(unsigned*, unsigned);
//unsigned __
visc
__atomic_xor(unsigned*, unsigned);
//unsigned __
hpvm
__atomic_xor(unsigned*, unsigned);
/*
/*
* ApproxHPVM specific function calls
* ApproxHPVM specific function calls
*/
*/
void
*
__
visc
__tensor_add
(
void
*
,
void
*
);
void
*
__
hpvm
__tensor_add
(
void
*
,
void
*
);
void
*
__
visc
__tensor_mul
(
void
*
,
void
*
);
void
*
__
hpvm
__tensor_mul
(
void
*
,
void
*
);
void
*
__
visc
__tensor_convolution
(
void
*
,
void
*
,
int
,
int
,
int
,
int
);
void
*
__
hpvm
__tensor_convolution
(
void
*
,
void
*
,
int
,
int
,
int
,
int
);
void
*
__
visc
__tensor_group_convolution
(
void
*
,
void
*
,
int
,
int
,
int
,
int
,
int
,
int
);
void
*
__
hpvm
__tensor_group_convolution
(
void
*
,
void
*
,
int
,
int
,
int
,
int
,
int
,
int
);
void
*
__
visc
__tensor_batchnorm
(
void
*
,
void
*
,
void
*
,
void
*
,
void
*
,
double
);
void
*
__
hpvm
__tensor_batchnorm
(
void
*
,
void
*
,
void
*
,
void
*
,
void
*
,
double
);
void
*
__
visc
__tensor_pool_max
(
void
*
,
int
,
int
,
int
,
int
,
int
,
int
);
void
*
__
hpvm
__tensor_pool_max
(
void
*
,
int
,
int
,
int
,
int
,
int
,
int
);
void
*
__
visc
__tensor_pool_mean
(
void
*
,
int
,
int
,
int
,
int
,
int
,
int
);
void
*
__
hpvm
__tensor_pool_mean
(
void
*
,
int
,
int
,
int
,
int
,
int
,
int
);
void
*
__
visc
__tensor_relu
(
void
*
);
void
*
__
hpvm
__tensor_relu
(
void
*
);
void
*
__
visc
__tensor_tanh
(
void
*
);
void
*
__
hpvm
__tensor_tanh
(
void
*
);
void
*
__
visc
__tensor_softmax
(
void
*
);
void
*
__
hpvm
__tensor_softmax
(
void
*
);
// Tensor ops for image processing
// Tensor ops for image processing
void
*
__
visc
__tensor_fft
(
void
*
);
void
*
__
hpvm
__tensor_fft
(
void
*
);
void
*
__
visc
__tensor_reduce
(
void
*
,
int
,
void
*
);
void
*
__
hpvm
__tensor_reduce
(
void
*
,
int
,
void
*
);
void
*
__
visc
__tensor_projectiveT
(
void
*
,
void
*
);
void
*
__
hpvm
__tensor_projectiveT
(
void
*
,
void
*
);
void
*
__
visc
__tensor_map1
(
void
*
,
void
*
);
void
*
__
hpvm
__tensor_map1
(
void
*
,
void
*
);
void
*
__
visc
__tensor_map2
(
void
*
,
void
*
,
void
*
);
void
*
__
hpvm
__tensor_map2
(
void
*
,
void
*
,
void
*
);
void
*
__
visc
__tensor_map3
(
void
*
,
void
*
,
void
*
,
void
*
);
void
*
__
hpvm
__tensor_map3
(
void
*
,
void
*
,
void
*
,
void
*
);
void
*
__
visc
__tensor_cosineT
(
void
*
);
void
*
__
hpvm
__tensor_cosineT
(
void
*
);
void
*
__
visc
__tensor_stencil
(
void
*
);
void
*
__
hpvm
__tensor_stencil
(
void
*
);
// New HPVM intrinsic for Setting Node ID
// New HPVM intrinsic for Setting Node ID
void
*
__
visc
__node_id
(
int
);
void
*
__
hpvm
__node_id
(
int
);
#include
<unistd.h>
#include
<unistd.h>
...
@@ -124,12 +124,12 @@ long get_local_id(int);
...
@@ -124,12 +124,12 @@ long get_local_id(int);
long
get_local_size
(
int
);
long
get_local_size
(
int
);
void
llvm_
visc
_track_mem
(
void
*
,
size_t
);
void
llvm_
hpvm
_track_mem
(
void
*
,
size_t
);
void
llvm_
visc
_untrack_mem
(
void
*
);
void
llvm_
hpvm
_untrack_mem
(
void
*
);
void
llvm_
visc
_request_mem
(
void
*
,
size_t
);
void
llvm_
hpvm
_request_mem
(
void
*
,
size_t
);
/*#ifdef __cplusplus
/*#ifdef __cplusplus
void hpvm_request_tensor(void*,
visc
::Target);
void hpvm_request_tensor(void*,
hpvm
::Target);
#else
#else
void hpvm_request_tensor(void*, enum Target);
void hpvm_request_tensor(void*, enum Target);
#endif
#endif
...
...
This diff is collapsed.
Click to expand it.
Preview
0%
Loading
Try again
or
attach a new file
.
Cancel
You are about to add
0
people
to the discussion. Proceed with caution.
Finish editing this message first!
Save comment
Cancel
Please
register
or
sign in
to comment