| /****************************************************************************** |
| * |
| * Copyright (C) 2015 The Android Open Source Project |
| * |
| * Licensed under the Apache License, Version 2.0 (the "License"); |
| * you may not use this file except in compliance with the License. |
| * You may obtain a copy of the License at: |
| * |
| * http://www.apache.org/licenses/LICENSE-2.0 |
| * |
| * Unless required by applicable law or agreed to in writing, software |
| * distributed under the License is distributed on an "AS IS" BASIS, |
| * WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied. |
| * See the License for the specific language governing permissions and |
| * limitations under the License. |
| * |
| ***************************************************************************** |
| * Originally developed and contributed by Ittiam Systems Pvt. Ltd, Bangalore |
| */ |
| |
| /** |
| ******************************************************************************* |
| * @file |
| * impeg2_mem_func_sse42_intr.c |
| * |
| * @brief |
| * Contains utility function definitions for MPEG2 codec |
| * |
| * @author |
| * Mohit [100664] |
| * |
| * @par List of Functions: |
| * - impeg2_memset0_16bit_8x8_linear_block_sse42() |
| * - impeg2_memset_8bit_8x8_block_sse42() |
| * |
| * @remarks |
| * None |
| * |
| ******************************************************************************* |
| */ |
| #include <stdio.h> |
| #include <string.h> |
| #include "iv_datatypedef.h" |
| #include "impeg2_defs.h" |
| |
| #include <immintrin.h> |
| #include <emmintrin.h> |
| #include <smmintrin.h> |
| #include <tmmintrin.h> |
| |
| /******************************************************************************* |
| * Function Name : impeg2_memset0_16bit_8x8_linear_block |
| * |
| * Description : memsets resudial buf to 0 |
| * |
| * Arguments : destination buffer |
| * |
| * Values Returned : None |
| *******************************************************************************/ |
| |
| |
| void impeg2_memset0_16bit_8x8_linear_block_sse42 (WORD16 *buf) |
| { |
| __m128i zero_8x8_16b = _mm_set1_epi16(0); |
| _mm_storeu_si128((__m128i *) buf, zero_8x8_16b); |
| _mm_storeu_si128((__m128i *) (buf + 8), zero_8x8_16b); |
| _mm_storeu_si128((__m128i *) (buf + 16), zero_8x8_16b); |
| _mm_storeu_si128((__m128i *) (buf + 24), zero_8x8_16b); |
| _mm_storeu_si128((__m128i *) (buf + 32), zero_8x8_16b); |
| _mm_storeu_si128((__m128i *) (buf + 40), zero_8x8_16b); |
| _mm_storeu_si128((__m128i *) (buf + 48), zero_8x8_16b); |
| _mm_storeu_si128((__m128i *) (buf + 56), zero_8x8_16b); |
| } |
| |
| |
| |
| /******************************************************************************* |
| * Function Name : impeg2_memset_8bit_8x8_block |
| * |
| * Description : memsets residual buf to value |
| * |
| * Arguments : destination buffer, value and stride |
| * |
| * Values Returned : None |
| *******************************************************************************/ |
| |
| |
| void impeg2_memset_8bit_8x8_block_sse42(UWORD8 *dst, WORD32 dc_val, WORD32 dst_wd) |
| { |
| __m128i value = _mm_set1_epi8((WORD8)dc_val); |
| |
| _mm_storel_epi64((__m128i *)dst, value); |
| _mm_storel_epi64((__m128i *) (dst + dst_wd), value); |
| _mm_storel_epi64((__m128i *) (dst + 2 * dst_wd), value); |
| _mm_storel_epi64((__m128i *) (dst + 3 * dst_wd), value); |
| _mm_storel_epi64((__m128i *) (dst + 4 * dst_wd), value); |
| _mm_storel_epi64((__m128i *) (dst + 5 * dst_wd), value); |
| _mm_storel_epi64((__m128i *) (dst + 6 * dst_wd), value); |
| _mm_storel_epi64((__m128i *) (dst + 7 * dst_wd), value); |
| } |