Skip to content
New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

Sign up for GitHub

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Jump to bottom

Removed unnecessary inline helpers used in water kernel #276

Merged
merged 1 commit into from
Jun 4, 2024
Merged

Removed unnecessary inline helpers used in water kernel #276

Show file tree
Hide file tree
Changes from all commits
Commits
Show all changes
1 commit
Select commit
File filter

Filter by extension

Filter by extension
Conversations
Failed to load comments.
Loading
Jump to
Jump to file
Failed to load files.
Loading
Diff view
Diff view
12 changes: 0 additions & 12 deletions src/include/cpu/rpp_cpu_simd.hpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -3085,12 +3085,6 @@ inline void rpp_store24_f32pln3_to_u8pkd3_avx(Rpp8u* dstPtr, __m256* p)
_mm256_storeu_si256((__m256i *)(dstPtr), px1); /* store the 24 U8 pixels in dst */
}

inline void rpp_store8_u8pln1_to_u8pln1_avx(Rpp8u* dstPtr, __m256i &p)
{
__m128i pTemp = _mm256_castsi256_si128(p);
rpp_storeu_si64((__m128i *)(dstPtr), pTemp);
}

inline void rpp_store8_f32pln1_to_u8pln1_avx(Rpp8u* dstPtr, __m256 &p)
{
__m256i px1 = _mm256_permute4x64_epi64(_mm256_packus_epi32(_mm256_cvtps_epi32(p), avx_px0), _MM_SHUFFLE(3,1,2,0));
Expand Down Expand Up @@ -3256,12 +3250,6 @@ inline void rpp_store24_f32pln3_to_i8pkd3_avx(Rpp8s* dstPtr, __m256* p)
_mm256_storeu_si256((__m256i *)(dstPtr), px1); /* store the 12 U8 pixels in dst */
}

inline void rpp_store8_i8pln1_to_i8pln1_avx(Rpp8s* dstPtr, __m256i &p)
{
__m128i pTemp = _mm256_castsi256_si128(p);
rpp_storeu_si64((__m128i *)(dstPtr), pTemp);
}

inline void rpp_store8_f32pln1_to_i8pln1_avx(Rpp8s* dstPtr, __m256 &p)
{
__m256i px1 = _mm256_permute4x64_epi64(_mm256_packus_epi32(_mm256_cvtps_epi32(p), avx_px0), _MM_SHUFFLE(3,1,2,0));
Expand Down
4 changes: 2 additions & 2 deletions src/modules/cpu/kernel/water.hpp
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -281,7 +281,7 @@ RppStatus water_u8_u8_host_tensor(Rpp8u *srcPtr,
{
__m256i pRow;
rpp_simd_load(rpp_generic_nn_load_u8pln1_avx, srcPtrTempChn, srcLocArray, invalidLoad, pRow);
rpp_simd_store(rpp_store8_u8pln1_to_u8pln1_avx, dstPtrTempChn, pRow);
rpp_storeu_si64((__m128i *)(dstPtrTempChn), _mm256_castsi256_si128(pRow));
srcPtrTempChn += srcDescPtr->strides.cStride;
dstPtrTempChn += dstDescPtr->strides.cStride;
}
Expand Down Expand Up @@ -965,7 +965,7 @@ RppStatus water_i8_i8_host_tensor(Rpp8s *srcPtr,
{
__m256i pRow;
rpp_simd_load(rpp_generic_nn_load_i8pln1_avx, srcPtrTempChn, srcLocArray, invalidLoad, pRow);
rpp_simd_store(rpp_store8_i8pln1_to_i8pln1_avx, dstPtrTempChn, pRow);
rpp_storeu_si64((__m128i *)(dstPtrTempChn), _mm256_castsi256_si128(pRow));
srcPtrTempChn += srcDescPtr->strides.cStride;
dstPtrTempChn += dstDescPtr->strides.cStride;
}
Expand Down