libcamera3/common_v2/ExynosCameraUtils.h - LeafOS-Devices/android_hardware_samsung_slsi-linaro_exynos - Gitiles

 /*
 **
 ** Copyright 2017, Samsung Electronics Co. LTD
 **
 ** 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.
 */

 #ifndef EXYNOS_CAMERA_UTILS_H
 #define EXYNOS_CAMERA_UTILS_H

 #include <cutils/properties.h>
 #include <utils/threads.h>
 #include <utils/String8.h>
 #include <arm_neon.h>

 #include "exynos_format.h"
 #include "ExynosRect.h"

 #include "ExynosCameraCommonInclude.h"
 #include "ExynosCameraSensorInfo.h"
 #include "videodev2_exynos_media.h"
 #include "ExynosCameraBuffer.h"

 #ifdef SAMSUNG_SENSOR_LISTENER
 #include "sensor_listener_wrapper.h"
 #endif

 //#define USE_INTERNAL_ALLOC_DEBUG
 #ifdef USE_INTERNAL_ALLOC_DEBUG
 //#define ALLOC_INFO_DUMP
 #endif
 #define MIN(a,b)             (((a) < (b)) ? (a) : (b))
 #define CLIP3(a, minV, maxV) (((a) < (minV)) ? (minV) : (((a) > (maxV)) ? (maxV) : (a)))

 #define ROUND_OFF(x, dig)           (floor((x) * pow(10.0f, dig)) / pow(10.0f, dig))
 #define GET_MAX_NUM(a, b, c) \
     ((a) < (b) ? \
     ((b) < (c) ? (c) : (b)) \
    :((a) < (c) ? (c) : (a)) )

 #define SAFE_DELETE(obj) \
     do { \
         if (obj) { \
             delete obj; \
             obj = NULL; \
         } \
     } while(0)

 #define MAKE_STRING(s) (char *)(#s)

 /* [CameraId]_[Bufffer Manager Name]_[FramcCount]_[Buffer Index]_[Batch Index]_[YYYYMMDD]_[HHMMSS].dump */
 #define DEBUG_DUMP_NAME "/data/camera/CAM%d_%s_F%d_I%d_B%d_%02d%02d%02d_%02d%02d%02d.dump"

 namespace android {

 bool            getCropRect(
                     int  src_w,  int   src_h,
                     int  dst_w,  int   dst_h,
                     int *crop_x, int *crop_y,
                     int *crop_w, int *crop_h,
                     int  zoom);

 bool            getCropRect2(
                     int  src_w,     int   src_h,
                     int  dst_w,     int   dst_h,
                     int *new_src_x, int *new_src_y,
                     int *new_src_w, int *new_src_h,
                     int  zoom);

 status_t        getCropRectAlign(
                     int  src_w,  int   src_h,
                     int  dst_w,  int   dst_h,
                     int *crop_x, int *crop_y,
                     int *crop_w, int *crop_h,
                     int align_w, int align_h,
                     int  zoom, float zoomRatio);

 status_t        getCropRectAlign(
                     int  src_w,  int   src_h,
                     int  dst_w,  int   dst_h,
                     int *crop_x, int *crop_y,
                     int *crop_w, int *crop_h,
                     int align_w, int align_h,
                     float zoomRatio);

 uint32_t        bracketsStr2Ints(
                     char *str,
                     uint32_t num,
                     ExynosRect2 *rect2s,
                     int *weights,
                     int mode);
 bool            subBracketsStr2Ints(int num, char *str, int *arr);

 void            convertingRectToRect2(ExynosRect *rect, ExynosRect2 *rect2);
 void            convertingRect2ToRect(ExynosRect2 *rect2, ExynosRect *rect);

 bool            isRectNull(ExynosRect *rect);
 bool            isRectNull(ExynosRect2 *rect2);
 bool            isRectEqual(ExynosRect *rect1, ExynosRect *rect2);
 bool            isRectEqual(ExynosRect2 *rect1, ExynosRect2 *rect2);

 char            v4l2Format2Char(int v4l2Format, int pos);
 ExynosRect2     convertingAndroidArea2HWArea(ExynosRect2 *srcRect, const ExynosRect *regionRect);
 ExynosRect2     convertingAndroidArea2HWAreaBcropOut(ExynosRect2 *srcRect, const ExynosRect *regionRect);
 ExynosRect2     convertingHWArea2AndroidArea(ExynosRect2 *srcRect, ExynosRect *regionRect);

 ExynosRect      convertingBufferDst2Rect(ExynosCameraBuffer *buffer, int colorFormat);

 /*
  * Control struct camera2_shot_ext
  */
 int32_t getMetaDmRequestFrameCount(struct camera2_shot_ext *shot_ext);
 int32_t getMetaDmRequestFrameCount(struct camera2_dm *dm);

 void setMetaCtlAeTargetFpsRange(struct camera2_shot_ext *shot_ext, uint32_t min, uint32_t max);
 void getMetaCtlAeTargetFpsRange(struct camera2_shot_ext *shot_ext, uint32_t *min, uint32_t *max);

 void setMetaCtlSensorFrameDuration(struct camera2_shot_ext *shot_ext, uint64_t duration);
 void getMetaCtlSensorFrameDuration(struct camera2_shot_ext *shot_ext, uint64_t *duration);

 void setMetaCtlAeMode(struct camera2_shot_ext *shot_ext, enum aa_aemode aeMode);
 void getMetaCtlAeMode(struct camera2_shot_ext *shot_ext, enum aa_aemode *aeMode);

 void setMetaCtlAeLock(struct camera2_shot_ext *shot_ext, bool lock);
 void getMetaCtlAeLock(struct camera2_shot_ext *shot_ext, bool *lock);
 void setMetaVtMode(struct camera2_shot_ext *shot_ext, enum camera_vt_mode mode);
 void setMetaVideoMode(struct camera2_shot_ext *shot_ext, enum aa_videomode mode);

 void setMetaCtlExposureCompensation(struct camera2_shot_ext *shot_ext, int32_t expCompensation);
 void getMetaCtlExposureCompensation(struct camera2_shot_ext *shot_ext, int32_t *expCompensatione);
 #ifdef USE_SUBDIVIDED_EV
 void setMetaCtlExposureCompensationStep(struct camera2_shot_ext *shot_ext, float expCompensationStep);
 #endif
 void setMetaCtlExposureTime(struct camera2_shot_ext *shot_ext, uint64_t exposureTime);
 void getMetaCtlExposureTime(struct camera2_shot_ext *shot_ext, uint64_t *exposureTime);
 void setMetaCtlCaptureExposureTime(struct camera2_shot_ext *shot_ext, uint32_t exposureTime);
 void getMetaCtlCaptureExposureTime(struct camera2_shot_ext *shot_ext, uint32_t *exposureTime);

 #ifdef SUPPORT_DEPTH_MAP
 void setMetaCtlDisparityMode(struct camera2_shot_ext *shot_ext, enum camera2_disparity_mode disparity_mode);
 #endif

 void setMetaCtlWbLevel(struct camera2_shot_ext *shot_ext, int32_t wbLevel);
 void getMetaCtlWbLevel(struct camera2_shot_ext *shot_ext, int32_t *wbLevel);

 #ifdef USE_FW_ZOOMRATIO
 void setMetaCtlZoom(struct camera2_shot_ext *shot_ext, float data);
 void getMetaCtlZoom(struct camera2_shot_ext *shot_ext, float *data);
 #endif

 status_t setMetaCtlCropRegion(
         struct camera2_shot_ext *shot_ext,
         int x, int y, int w, int h);
 status_t setMetaCtlCropRegion(
         struct camera2_shot_ext *shot_ext,
         int zoom,
         int srcW, int srcH,
         int dstW, int dstH, float zoomRatio);
 void getMetaCtlCropRegion(
             struct camera2_shot_ext *shot_ext,
             int *x, int *y,
             int *w, int *h);

 void setMetaCtlAeRegion(
             struct camera2_shot_ext *shot_ext,
             int x, int y,
             int w, int h,
             int weight);
 void getMetaCtlAeRegion(
             struct camera2_shot_ext *shot_ext,
             int *x, int *y,
             int *w, int *h,
             int *weight);

 void setMetaCtlAntibandingMode(struct camera2_shot_ext *shot_ext, enum aa_ae_antibanding_mode antibandingMode);
 void getMetaCtlAntibandingMode(struct camera2_shot_ext *shot_ext, enum aa_ae_antibanding_mode *antibandingMode);

 void setMetaCtlSceneMode(struct camera2_shot_ext *shot_ext, enum aa_mode mode, enum aa_scene_mode sceneMode);
 void getMetaCtlSceneMode(struct camera2_shot_ext *shot_ext, enum aa_mode *mode, enum aa_scene_mode *sceneMode);

 void setMetaCtlAwbMode(struct camera2_shot_ext *shot_ext, enum aa_awbmode awbMode);
 void getMetaCtlAwbMode(struct camera2_shot_ext *shot_ext, enum aa_awbmode *awbMode);
 void setMetaCtlAwbLock(struct camera2_shot_ext *shot_ext, bool lock);
 void getMetaCtlAwbLock(struct camera2_shot_ext *shot_ext, bool *lock);
 void setMetaCtlAfRegion(struct camera2_shot_ext *shot_ext,
                             int x, int y, int w, int h, int weight);
 void getMetaCtlAfRegion(struct camera2_shot_ext *shot_ext,
                         int *x, int *y, int *w, int *h, int *weight);

 void setMetaCtlColorCorrectionMode(struct camera2_shot_ext *shot_ext, enum colorcorrection_mode mode);
 void getMetaCtlColorCorrectionMode(struct camera2_shot_ext *shot_ext, enum colorcorrection_mode *mode);
 void setMetaCtlAaEffect(struct camera2_shot_ext *shot_ext, aa_effect_mode_t effect);
 void getMetaCtlAaEffect(struct camera2_shot_ext *shot_ext, aa_effect_mode_t *effect);
 void setMetaCtlBrightness(struct camera2_shot_ext *shot_ext, int32_t brightness);
 void getMetaCtlBrightness(struct camera2_shot_ext *shot_ext, int32_t *brightness);

 void setMetaCtlSaturation(struct camera2_shot_ext *shot_ext, int32_t saturation);
 void getMetaCtlSaturation(struct camera2_shot_ext *shot_ext, int32_t *saturation);

 void setMetaCtlHue(struct camera2_shot_ext *shot_ext, int32_t hue);
 void getMetaCtlHue(struct camera2_shot_ext *shot_ext, int32_t *hue);

 void setMetaCtlContrast(struct camera2_shot_ext *shot_ext, uint32_t contrast);
 void getMetaCtlContrast(struct camera2_shot_ext *shot_ext, uint32_t *contrast);

 void setMetaCtlSharpness(struct camera2_shot_ext *shot_ext, enum processing_mode edge_mode, int32_t edge_sharpness,
                             enum processing_mode noise_mode, int32_t noise_sharpness);
 void getMetaCtlSharpness(struct camera2_shot_ext *shot_ext, enum processing_mode *mode, int32_t *sharpness,
                             enum processing_mode *noise_mode, int32_t *noise_sharpness);


 void setMetaCtlIso(struct camera2_shot_ext *shot_ext, enum aa_isomode mode, uint32_t iso);
 void getMetaCtlIso(struct camera2_shot_ext *shot_ext, enum aa_isomode *mode, uint32_t *iso);
 void setMetaCtlFdMode(struct camera2_shot_ext *shot_ext, enum facedetect_mode mode);

 void setMetaUctlYsumPort(struct camera2_shot_ext *shot_ext, enum mcsc_port ysumPort);

 void getStreamFrameValid(struct camera2_stream *shot_stream, uint32_t *fvalid);
 void getStreamFrameCount(struct camera2_stream *shot_stream, uint32_t *fcount);

 status_t setMetaDmSensorTimeStamp(struct camera2_shot_ext *shot_ext, uint64_t timeStamp);
 nsecs_t getMetaDmSensorTimeStamp(struct camera2_shot_ext *shot_ext);
 status_t setMetaUdmSensorTimeStampBoot(struct camera2_shot_ext *shot_ext, uint64_t timeStamp);
 nsecs_t getMetaUdmSensorTimeStampBoot(struct camera2_shot_ext *shot_ext);

 void setMetaNodeLeaderRequest(struct camera2_shot_ext* shot_ext, int value);
 void setMetaNodeLeaderVideoID(struct camera2_shot_ext* shot_ext, int value);
 void setMetaNodeLeaderPixFormat(struct camera2_shot_ext* shot_ext, int value);
 void setMetaNodeLeaderInputSize(struct camera2_shot_ext * shot_ext, unsigned int x, unsigned int y, unsigned int w, unsigned int h);
 void setMetaNodeLeaderOutputSize(struct camera2_shot_ext * shot_ext, unsigned int x, unsigned int y, unsigned int w, unsigned int h);
 void setMetaNodeCaptureRequest(struct camera2_shot_ext* shot_ext, int index, int value);
 void setMetaNodeCaptureVideoID(struct camera2_shot_ext* shot_ext, int index, int value);
 void setMetaNodeCapturePixFormat(struct camera2_shot_ext* shot_ext, int index, int value);
 void setMetaNodeCaptureInputSize(struct camera2_shot_ext * shot_ext, int index, unsigned int x, unsigned int y, unsigned int w, unsigned int h);
 void setMetaNodeCaptureOutputSize(struct camera2_shot_ext * shot_ext, int index, unsigned int x, unsigned int y, unsigned int w, unsigned int h);

 void setMetaBypassDrc(struct camera2_shot_ext *shot_ext, int value);
 void setMetaBypassDis(struct camera2_shot_ext *shot_ext, int value);
 void setMetaBypassDnr(struct camera2_shot_ext *shot_ext, int value);
 void setMetaBypassFd(struct camera2_shot_ext *shot_ext, int value);

 void setMetaSetfile(struct camera2_shot_ext *shot_ext, int value);


 int mergeSetfileYuvRange(int setfile, int yuvRange);

 int getPlaneSizeFlite(int width, int height);
 int getBayerLineSize(int width, int bayerFormat);
 int getBayerPlaneSize(int width, int height, int bayerFormat);

 bool directDumpToFile(ExynosCameraBuffer *buffer, uint32_t cameraId, uint32_t frameCount);
 bool dumpToFile(char *filename, char *srcBuf, unsigned int size);
 bool dumpToFilePacked12(char *filename, char *srcBuf, unsigned int size);
 bool dumpToFile2plane(char *filename, char *srcBuf, char *srcBuf1, unsigned int size, unsigned int size1);
 status_t readFromFile(char *filename, char *dstBuf, uint32_t size);

 /* TODO: This functions need to be commonized */
 status_t getYuvPlaneSize(int format, unsigned int *size,
                          unsigned int width, unsigned int height,
                          camera_pixel_size pixelSize = CAMERA_PIXEL_SIZE_8BIT);
 status_t getV4l2FormatInfo(unsigned int v4l2_pixel_format,
                          unsigned int *bpp, unsigned int *planes,
                          camera_pixel_size pixelSize = CAMERA_PIXEL_SIZE_8BIT);
 int getYuvPlaneCount(unsigned int v4l2_pixel_format,
                         camera_pixel_size pixelSize = CAMERA_PIXEL_SIZE_8BIT);
 int displayExynosBuffer( ExynosCameraBuffer *buffer);

 int checkBit(unsigned int *target, int index);
 void clearBit(unsigned int *target, int index, bool isStatePrint = false);
 void setBit(unsigned int *target, int index, bool isStatePrint = false);
 void resetBit(unsigned int *target, int value, bool isStatePrint = false);

 status_t addBayerBuffer(struct ExynosCameraBuffer *srcBuf,
                         struct ExynosCameraBuffer *dstBuf,
                         ExynosRect *dstRect,
                         bool isPacked = false);
 status_t addBayerBufferByNeon(struct ExynosCameraBuffer *srcBuf,
                               struct ExynosCameraBuffer *dstBuf,
                               unsigned int copySize);
 status_t addBayerBufferByNeonPacked(struct ExynosCameraBuffer *srcBuf,
                                     struct ExynosCameraBuffer *dstBuf,
                                     ExynosRect *dstRect,
                                     unsigned int copySize);
 status_t addBayerBufferByCpu(struct ExynosCameraBuffer *srcBuf,
                              struct ExynosCameraBuffer *dstBuf,
                              unsigned int copySize);

 char clip(int i);
 void convertingYUYVtoRGB888(char *dstBuf, char *srcBuf, int width, int height);

 void checkAndroidVersion(void);

 int  getFliteNodenum(int cameraId);
 int  getFliteCaptureNodenum(int cameraId, int fliteOutputNode);

 #ifdef SUPPORT_DEPTH_MAP
 int  getDepthVcNodeNum(int cameraId);
 #endif

 int calibratePosition(int w, int new_w, int pos);

 status_t updateYsumBuffer(struct ysum_data *ysumdata, ExynosCameraBuffer *dstBuf);
 #ifdef SAMSUNG_HDR10_RECORDING
 status_t updateHDRBuffer(ExynosCameraBuffer *dstBuf);
 #endif /* SAMSUNG_HDR10_RECORDING */
 void getV4l2Name(char* colorName, size_t length, int colorFormat);

 template <typename THREAD, typename THREADQ>
 void stopThreadAndInputQ(THREAD thread, int qCnt, THREADQ inputQ, ...)
 {
     /*
      * Note: The type of THREAD must be ExynosCameraThread <template>,
      * and The type of THREAQ must be ExynosCameraList <template> * .
      */

     va_list list;
     THREADQ wakeupQ = inputQ, releaseQ = inputQ;

     if (thread == NULL)
         return;

     thread->requestExit();

     va_start(list, inputQ);
     for (int i = 0; i < qCnt; i++) {
         if (wakeupQ != NULL) {
             wakeupQ->wakeupAll();
         }
         wakeupQ = va_arg(list, THREADQ);
     }
     va_end(list);

     thread->requestExitAndWait();

     va_start(list, inputQ);
     for (int i = 0; i < qCnt; i++) {
         if (releaseQ != NULL) {
             releaseQ->release();
         }
         releaseQ = va_arg(list, THREADQ);
     }
     va_end(list);
 };

 void setPreviewProperty(bool on);

 #ifdef CAMERA_GED_FEATURE
 bool isFastenAeStableSupported(int cameraId);
 #endif

 }; /* namespace android */


 #ifdef USE_INTERNAL_ALLOC_DEBUG
 void* operator new(std::size_t);
 void  operator delete(void*);
 void* operator new[](std::size_t);
 void  operator delete[](void*);
 int alloc_info_print(int flag = 0);
 #endif

 #endif
	/*
	**
	** Copyright 2017, Samsung Electronics Co. LTD
	**
	** 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.
	*/

	#ifndef EXYNOS_CAMERA_UTILS_H
	#define EXYNOS_CAMERA_UTILS_H

	#include <cutils/properties.h>
	#include <utils/threads.h>
	#include <utils/String8.h>
	#include <arm_neon.h>

	#include "exynos_format.h"
	#include "ExynosRect.h"

	#include "ExynosCameraCommonInclude.h"
	#include "ExynosCameraSensorInfo.h"
	#include "videodev2_exynos_media.h"
	#include "ExynosCameraBuffer.h"

	#ifdef SAMSUNG_SENSOR_LISTENER
	#include "sensor_listener_wrapper.h"
	#endif

	//#define USE_INTERNAL_ALLOC_DEBUG
	#ifdef USE_INTERNAL_ALLOC_DEBUG
	//#define ALLOC_INFO_DUMP
	#endif
	#define MIN(a,b) (((a) < (b)) ? (a) : (b))
	#define CLIP3(a, minV, maxV) (((a) < (minV)) ? (minV) : (((a) > (maxV)) ? (maxV) : (a)))

	#define ROUND_OFF(x, dig) (floor((x) * pow(10.0f, dig)) / pow(10.0f, dig))
	#define GET_MAX_NUM(a, b, c) \
	((a) < (b) ? \
	((b) < (c) ? (c) : (b)) \
	:((a) < (c) ? (c) : (a)) )

	#define SAFE_DELETE(obj) \
	do { \
	if (obj) { \
	delete obj; \
	obj = NULL; \
	} \
	} while(0)

	#define MAKE_STRING(s) (char *)(#s)

	/* [CameraId]_[Bufffer Manager Name]_[FramcCount]_[Buffer Index]_[Batch Index]_[YYYYMMDD]_[HHMMSS].dump */
	#define DEBUG_DUMP_NAME "/data/camera/CAM%d_%s_F%d_I%d_B%d_%02d%02d%02d_%02d%02d%02d.dump"

	namespace android {

	bool getCropRect(
	int src_w, int src_h,
	int dst_w, int dst_h,
	int crop_x, int crop_y,
	int crop_w, int crop_h,
	int zoom);

	bool getCropRect2(
	int src_w, int src_h,
	int dst_w, int dst_h,
	int new_src_x, int new_src_y,
	int new_src_w, int new_src_h,
	int zoom);

	status_t getCropRectAlign(
	int src_w, int src_h,
	int dst_w, int dst_h,
	int crop_x, int crop_y,
	int crop_w, int crop_h,
	int align_w, int align_h,
	int zoom, float zoomRatio);

	status_t getCropRectAlign(
	int src_w, int src_h,
	int dst_w, int dst_h,
	int crop_x, int crop_y,
	int crop_w, int crop_h,
	int align_w, int align_h,
	float zoomRatio);

	uint32_t bracketsStr2Ints(
	char *str,
	uint32_t num,
	ExynosRect2 *rect2s,
	int *weights,
	int mode);
	bool subBracketsStr2Ints(int num, char str, int arr);

	void convertingRectToRect2(ExynosRect rect, ExynosRect2 rect2);
	void convertingRect2ToRect(ExynosRect2 rect2, ExynosRect rect);

	bool isRectNull(ExynosRect *rect);
	bool isRectNull(ExynosRect2 *rect2);
	bool isRectEqual(ExynosRect rect1, ExynosRect rect2);
	bool isRectEqual(ExynosRect2 rect1, ExynosRect2 rect2);

	char v4l2Format2Char(int v4l2Format, int pos);
	ExynosRect2 convertingAndroidArea2HWArea(ExynosRect2 srcRect, const ExynosRect regionRect);
	ExynosRect2 convertingAndroidArea2HWAreaBcropOut(ExynosRect2 srcRect, const ExynosRect regionRect);
	ExynosRect2 convertingHWArea2AndroidArea(ExynosRect2 srcRect, ExynosRect regionRect);

	ExynosRect convertingBufferDst2Rect(ExynosCameraBuffer *buffer, int colorFormat);

	/*
	* Control struct camera2_shot_ext
	*/
	int32_t getMetaDmRequestFrameCount(struct camera2_shot_ext *shot_ext);
	int32_t getMetaDmRequestFrameCount(struct camera2_dm *dm);

	void setMetaCtlAeTargetFpsRange(struct camera2_shot_ext *shot_ext, uint32_t min, uint32_t max);
	void getMetaCtlAeTargetFpsRange(struct camera2_shot_ext shot_ext, uint32_t min, uint32_t *max);

	void setMetaCtlSensorFrameDuration(struct camera2_shot_ext *shot_ext, uint64_t duration);
	void getMetaCtlSensorFrameDuration(struct camera2_shot_ext shot_ext, uint64_t duration);

	void setMetaCtlAeMode(struct camera2_shot_ext *shot_ext, enum aa_aemode aeMode);
	void getMetaCtlAeMode(struct camera2_shot_ext shot_ext, enum aa_aemode aeMode);

	void setMetaCtlAeLock(struct camera2_shot_ext *shot_ext, bool lock);
	void getMetaCtlAeLock(struct camera2_shot_ext shot_ext, bool lock);
	void setMetaVtMode(struct camera2_shot_ext *shot_ext, enum camera_vt_mode mode);
	void setMetaVideoMode(struct camera2_shot_ext *shot_ext, enum aa_videomode mode);

	void setMetaCtlExposureCompensation(struct camera2_shot_ext *shot_ext, int32_t expCompensation);
	void getMetaCtlExposureCompensation(struct camera2_shot_ext shot_ext, int32_t expCompensatione);
	#ifdef USE_SUBDIVIDED_EV
	void setMetaCtlExposureCompensationStep(struct camera2_shot_ext *shot_ext, float expCompensationStep);
	#endif
	void setMetaCtlExposureTime(struct camera2_shot_ext *shot_ext, uint64_t exposureTime);
	void getMetaCtlExposureTime(struct camera2_shot_ext shot_ext, uint64_t exposureTime);
	void setMetaCtlCaptureExposureTime(struct camera2_shot_ext *shot_ext, uint32_t exposureTime);
	void getMetaCtlCaptureExposureTime(struct camera2_shot_ext shot_ext, uint32_t exposureTime);

	#ifdef SUPPORT_DEPTH_MAP
	void setMetaCtlDisparityMode(struct camera2_shot_ext *shot_ext, enum camera2_disparity_mode disparity_mode);
	#endif

	void setMetaCtlWbLevel(struct camera2_shot_ext *shot_ext, int32_t wbLevel);
	void getMetaCtlWbLevel(struct camera2_shot_ext shot_ext, int32_t wbLevel);

	#ifdef USE_FW_ZOOMRATIO
	void setMetaCtlZoom(struct camera2_shot_ext *shot_ext, float data);
	void getMetaCtlZoom(struct camera2_shot_ext shot_ext, float data);
	#endif

	status_t setMetaCtlCropRegion(
	struct camera2_shot_ext *shot_ext,
	int x, int y, int w, int h);
	status_t setMetaCtlCropRegion(
	struct camera2_shot_ext *shot_ext,
	int zoom,
	int srcW, int srcH,
	int dstW, int dstH, float zoomRatio);
	void getMetaCtlCropRegion(
	struct camera2_shot_ext *shot_ext,
	int x, int y,
	int w, int h);

	void setMetaCtlAeRegion(
	struct camera2_shot_ext *shot_ext,
	int x, int y,
	int w, int h,
	int weight);
	void getMetaCtlAeRegion(
	struct camera2_shot_ext *shot_ext,
	int x, int y,
	int w, int h,
	int *weight);

	void setMetaCtlAntibandingMode(struct camera2_shot_ext *shot_ext, enum aa_ae_antibanding_mode antibandingMode);
	void getMetaCtlAntibandingMode(struct camera2_shot_ext shot_ext, enum aa_ae_antibanding_mode antibandingMode);

	void setMetaCtlSceneMode(struct camera2_shot_ext *shot_ext, enum aa_mode mode, enum aa_scene_mode sceneMode);
	void getMetaCtlSceneMode(struct camera2_shot_ext shot_ext, enum aa_mode mode, enum aa_scene_mode *sceneMode);

	void setMetaCtlAwbMode(struct camera2_shot_ext *shot_ext, enum aa_awbmode awbMode);
	void getMetaCtlAwbMode(struct camera2_shot_ext shot_ext, enum aa_awbmode awbMode);
	void setMetaCtlAwbLock(struct camera2_shot_ext *shot_ext, bool lock);
	void getMetaCtlAwbLock(struct camera2_shot_ext shot_ext, bool lock);
	void setMetaCtlAfRegion(struct camera2_shot_ext *shot_ext,
	int x, int y, int w, int h, int weight);
	void getMetaCtlAfRegion(struct camera2_shot_ext *shot_ext,
	int x, int y, int w, int h, int *weight);

	void setMetaCtlColorCorrectionMode(struct camera2_shot_ext *shot_ext, enum colorcorrection_mode mode);
	void getMetaCtlColorCorrectionMode(struct camera2_shot_ext shot_ext, enum colorcorrection_mode mode);
	void setMetaCtlAaEffect(struct camera2_shot_ext *shot_ext, aa_effect_mode_t effect);
	void getMetaCtlAaEffect(struct camera2_shot_ext shot_ext, aa_effect_mode_t effect);
	void setMetaCtlBrightness(struct camera2_shot_ext *shot_ext, int32_t brightness);
	void getMetaCtlBrightness(struct camera2_shot_ext shot_ext, int32_t brightness);

	void setMetaCtlSaturation(struct camera2_shot_ext *shot_ext, int32_t saturation);
	void getMetaCtlSaturation(struct camera2_shot_ext shot_ext, int32_t saturation);

	void setMetaCtlHue(struct camera2_shot_ext *shot_ext, int32_t hue);
	void getMetaCtlHue(struct camera2_shot_ext shot_ext, int32_t hue);

	void setMetaCtlContrast(struct camera2_shot_ext *shot_ext, uint32_t contrast);
	void getMetaCtlContrast(struct camera2_shot_ext shot_ext, uint32_t contrast);

	void setMetaCtlSharpness(struct camera2_shot_ext *shot_ext, enum processing_mode edge_mode, int32_t edge_sharpness,
	enum processing_mode noise_mode, int32_t noise_sharpness);
	void getMetaCtlSharpness(struct camera2_shot_ext shot_ext, enum processing_mode mode, int32_t *sharpness,
	enum processing_mode noise_mode, int32_t noise_sharpness);


	void setMetaCtlIso(struct camera2_shot_ext *shot_ext, enum aa_isomode mode, uint32_t iso);
	void getMetaCtlIso(struct camera2_shot_ext shot_ext, enum aa_isomode mode, uint32_t *iso);
	void setMetaCtlFdMode(struct camera2_shot_ext *shot_ext, enum facedetect_mode mode);

	void setMetaUctlYsumPort(struct camera2_shot_ext *shot_ext, enum mcsc_port ysumPort);

	void getStreamFrameValid(struct camera2_stream shot_stream, uint32_t fvalid);
	void getStreamFrameCount(struct camera2_stream shot_stream, uint32_t fcount);

	status_t setMetaDmSensorTimeStamp(struct camera2_shot_ext *shot_ext, uint64_t timeStamp);
	nsecs_t getMetaDmSensorTimeStamp(struct camera2_shot_ext *shot_ext);
	status_t setMetaUdmSensorTimeStampBoot(struct camera2_shot_ext *shot_ext, uint64_t timeStamp);
	nsecs_t getMetaUdmSensorTimeStampBoot(struct camera2_shot_ext *shot_ext);

	void setMetaNodeLeaderRequest(struct camera2_shot_ext* shot_ext, int value);
	void setMetaNodeLeaderVideoID(struct camera2_shot_ext* shot_ext, int value);
	void setMetaNodeLeaderPixFormat(struct camera2_shot_ext* shot_ext, int value);
	void setMetaNodeLeaderInputSize(struct camera2_shot_ext * shot_ext, unsigned int x, unsigned int y, unsigned int w, unsigned int h);
	void setMetaNodeLeaderOutputSize(struct camera2_shot_ext * shot_ext, unsigned int x, unsigned int y, unsigned int w, unsigned int h);
	void setMetaNodeCaptureRequest(struct camera2_shot_ext* shot_ext, int index, int value);
	void setMetaNodeCaptureVideoID(struct camera2_shot_ext* shot_ext, int index, int value);
	void setMetaNodeCapturePixFormat(struct camera2_shot_ext* shot_ext, int index, int value);
	void setMetaNodeCaptureInputSize(struct camera2_shot_ext * shot_ext, int index, unsigned int x, unsigned int y, unsigned int w, unsigned int h);
	void setMetaNodeCaptureOutputSize(struct camera2_shot_ext * shot_ext, int index, unsigned int x, unsigned int y, unsigned int w, unsigned int h);

	void setMetaBypassDrc(struct camera2_shot_ext *shot_ext, int value);
	void setMetaBypassDis(struct camera2_shot_ext *shot_ext, int value);
	void setMetaBypassDnr(struct camera2_shot_ext *shot_ext, int value);
	void setMetaBypassFd(struct camera2_shot_ext *shot_ext, int value);

	void setMetaSetfile(struct camera2_shot_ext *shot_ext, int value);


	int mergeSetfileYuvRange(int setfile, int yuvRange);

	int getPlaneSizeFlite(int width, int height);
	int getBayerLineSize(int width, int bayerFormat);
	int getBayerPlaneSize(int width, int height, int bayerFormat);

	bool directDumpToFile(ExynosCameraBuffer *buffer, uint32_t cameraId, uint32_t frameCount);
	bool dumpToFile(char filename, char srcBuf, unsigned int size);
	bool dumpToFilePacked12(char filename, char srcBuf, unsigned int size);
	bool dumpToFile2plane(char filename, char srcBuf, char *srcBuf1, unsigned int size, unsigned int size1);
	status_t readFromFile(char filename, char dstBuf, uint32_t size);

	/* TODO: This functions need to be commonized */
	status_t getYuvPlaneSize(int format, unsigned int *size,
	unsigned int width, unsigned int height,
	camera_pixel_size pixelSize = CAMERA_PIXEL_SIZE_8BIT);
	status_t getV4l2FormatInfo(unsigned int v4l2_pixel_format,
	unsigned int bpp, unsigned int planes,
	camera_pixel_size pixelSize = CAMERA_PIXEL_SIZE_8BIT);
	int getYuvPlaneCount(unsigned int v4l2_pixel_format,
	camera_pixel_size pixelSize = CAMERA_PIXEL_SIZE_8BIT);
	int displayExynosBuffer( ExynosCameraBuffer *buffer);

	int checkBit(unsigned int *target, int index);
	void clearBit(unsigned int *target, int index, bool isStatePrint = false);
	void setBit(unsigned int *target, int index, bool isStatePrint = false);
	void resetBit(unsigned int *target, int value, bool isStatePrint = false);

	status_t addBayerBuffer(struct ExynosCameraBuffer *srcBuf,
	struct ExynosCameraBuffer *dstBuf,
	ExynosRect *dstRect,
	bool isPacked = false);
	status_t addBayerBufferByNeon(struct ExynosCameraBuffer *srcBuf,
	struct ExynosCameraBuffer *dstBuf,
	unsigned int copySize);
	status_t addBayerBufferByNeonPacked(struct ExynosCameraBuffer *srcBuf,
	struct ExynosCameraBuffer *dstBuf,
	ExynosRect *dstRect,
	unsigned int copySize);
	status_t addBayerBufferByCpu(struct ExynosCameraBuffer *srcBuf,
	struct ExynosCameraBuffer *dstBuf,
	unsigned int copySize);

	char clip(int i);
	void convertingYUYVtoRGB888(char dstBuf, char srcBuf, int width, int height);

	void checkAndroidVersion(void);

	int getFliteNodenum(int cameraId);
	int getFliteCaptureNodenum(int cameraId, int fliteOutputNode);

	#ifdef SUPPORT_DEPTH_MAP
	int getDepthVcNodeNum(int cameraId);
	#endif

	int calibratePosition(int w, int new_w, int pos);

	status_t updateYsumBuffer(struct ysum_data ysumdata, ExynosCameraBuffer dstBuf);
	#ifdef SAMSUNG_HDR10_RECORDING
	status_t updateHDRBuffer(ExynosCameraBuffer *dstBuf);
	#endif /* SAMSUNG_HDR10_RECORDING */
	void getV4l2Name(char* colorName, size_t length, int colorFormat);

	template <typename THREAD, typename THREADQ>
	void stopThreadAndInputQ(THREAD thread, int qCnt, THREADQ inputQ, ...)
	{
	/*
	* Note: The type of THREAD must be ExynosCameraThread <template>,
	* and The type of THREAQ must be ExynosCameraList <template> * .
	*/

	va_list list;
	THREADQ wakeupQ = inputQ, releaseQ = inputQ;

	if (thread == NULL)
	return;

	thread->requestExit();

	va_start(list, inputQ);
	for (int i = 0; i < qCnt; i++) {
	if (wakeupQ != NULL) {
	wakeupQ->wakeupAll();
	}
	wakeupQ = va_arg(list, THREADQ);
	}
	va_end(list);

	thread->requestExitAndWait();

	va_start(list, inputQ);
	for (int i = 0; i < qCnt; i++) {
	if (releaseQ != NULL) {
	releaseQ->release();
	}
	releaseQ = va_arg(list, THREADQ);
	}
	va_end(list);
	};

	void setPreviewProperty(bool on);

	#ifdef CAMERA_GED_FEATURE
	bool isFastenAeStableSupported(int cameraId);
	#endif

	}; /* namespace android */


	#ifdef USE_INTERNAL_ALLOC_DEBUG
	void* operator new(std::size_t);
	void operator delete(void*);
	void* operator new[](std::size_t);
	void operator delete[](void*);
	int alloc_info_print(int flag = 0);
	#endif

	#endif